/* //////////////////////////////////////////////////////////////////////////// -- testing any solver */ int main( int argc, char** argv ) { magma_int_t info = 0; TESTING_CHECK( magma_init() ); magma_print_environment(); magma_dopts zopts; magma_queue_t queue=NULL; magma_queue_create( 0, &queue ); real_Double_t res; magma_d_matrix A={Magma_CSR}, A2={Magma_CSR}, A3={Magma_CSR}, A4={Magma_CSR}, A5={Magma_CSR}; int i=1; TESTING_CHECK( magma_dparse_opts( argc, argv, &zopts, &i, queue )); while( i < argc ) { if ( strcmp("LAPLACE2D", argv[i]) == 0 && i+1 < argc ) { // Laplace test i++; magma_int_t laplace_size = atoi( argv[i] ); TESTING_CHECK( magma_dm_5stencil( laplace_size, &A, queue )); } else { // file-matrix test TESTING_CHECK( magma_d_csr_mtx( &A, argv[i], queue )); } printf("%% matrix info: %lld-by-%lld with %lld nonzeros\n", (long long) A.num_rows, (long long) A.num_cols, (long long) A.nnz ); // filename for temporary matrix storage const char *filename = "testmatrix.mtx"; // write to file TESTING_CHECK( magma_dwrite_csrtomtx( A, filename, queue )); // read from file TESTING_CHECK( magma_d_csr_mtx( &A2, filename, queue )); // delete temporary matrix unlink( filename ); //visualize printf("A2:\n"); TESTING_CHECK( magma_dprint_matrix( A2, queue )); //visualize TESTING_CHECK( magma_dmconvert(A2, &A4, Magma_CSR, Magma_CSRL, queue )); printf("A4:\n"); TESTING_CHECK( magma_dprint_matrix( A4, queue )); TESTING_CHECK( magma_dmconvert(A4, &A5, Magma_CSR, Magma_ELL, queue )); printf("A5:\n"); TESTING_CHECK( magma_dprint_matrix( A5, queue )); // pass it to another application and back magma_int_t m, n; magma_index_t *row, *col; double *val=NULL; TESTING_CHECK( magma_dcsrget( A2, &m, &n, &row, &col, &val, queue )); TESTING_CHECK( magma_dcsrset( m, n, row, col, val, &A3, queue )); TESTING_CHECK( magma_dmdiff( A, A2, &res, queue )); printf("%% ||A-B||_F = %8.2e\n", res); if ( res < .000001 ) printf("%% tester IO: ok\n"); else printf("%% tester IO: failed\n"); TESTING_CHECK( magma_dmdiff( A, A3, &res, queue )); printf("%% ||A-B||_F = %8.2e\n", res); if ( res < .000001 ) printf("%% tester matrix interface: ok\n"); else printf("%% tester matrix interface: failed\n"); magma_dmfree(&A, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&A4, queue ); magma_dmfree(&A5, queue ); i++; } magma_queue_destroy( queue ); TESTING_CHECK( magma_finalize() ); return info; }
magma_int_t magma_dprint_matrix( magma_d_matrix A, magma_queue_t queue ) { magma_int_t info = 0; //************************************************************** #define REAL #ifdef COMPLEX #define magma_dprintval( tmp ) { \ if ( MAGMA_D_EQUAL( tmp, c_zero )) { \ printf( " 0. " ); \ } \ else { \ printf( " %8.4f+%8.4fi", \ MAGMA_D_REAL( tmp ), MAGMA_D_IMAG( tmp )); \ } \ } #else #define magma_dprintval( tmp ) { \ if ( MAGMA_D_EQUAL( tmp, c_zero )) { \ printf( " 0. " ); \ } \ else { \ printf( " %8.4f", MAGMA_D_REAL( tmp )); \ } \ } #endif //************************************************************** magma_index_t i, j, k; double c_zero = MAGMA_D_ZERO; magma_d_matrix C={Magma_CSR}; if ( A.memory_location == Magma_CPU ) { printf("visualizing matrix of size %d x %d with %d nonzeros:\n", int(A.num_rows), int(A.num_cols), int(A.nnz)); if ( A.storage_type == Magma_DENSE ) { for( i=0; i < (A.num_rows); i++ ) { for( j=0; j < A.num_cols; j++ ) { magma_dprintval( A.val[i*(A.num_cols)+j] ); } printf( "\n" ); } } else if( A.num_cols < 8 || A.num_rows < 8 ) { CHECK( magma_dmconvert( A, &C, A.storage_type, Magma_DENSE, queue )); CHECK( magma_dprint_matrix( C, queue )); } else if ( A.storage_type == Magma_CSR ) { // visualize only small matrices like dense if ( A.num_rows < 11 && A.num_cols < 11 ) { CHECK( magma_dmconvert( A, &C, A.storage_type, Magma_DENSE, queue )); CHECK( magma_dprint_matrix( C, queue )); magma_dmfree( &C, queue ); } // otherwise visualize only coners else { // 4 beginning and 4 last elements of first four rows for( i=0; i < 4; i++ ) { // upper left corner for( j=0; j < 4; j++ ) { double tmp = MAGMA_D_ZERO; magma_index_t rbound = min( A.row[i]+4, A.row[i+1]); magma_index_t lbound = max( A.row[i], A.row[i]); for( k=lbound; k < rbound; k++ ) { if ( A.col[k] == j ) { tmp = A.val[k]; } } magma_dprintval( tmp ); } if ( i == 0 ) { printf( " . . . " ); } else { printf( " " ); } // upper right corner for( j=A.num_cols-4; j < A.num_cols; j++ ) { double tmp = MAGMA_D_ZERO; magma_index_t rbound = min( A.row[i+1], A.row[i+1]); magma_index_t lbound = max( A.row[i+1]-4, A.row[i]); for( k=lbound; k < rbound; k++ ) { if ( A.col[k] == j ) { tmp = A.val[k]; } } magma_dprintval( tmp ); } printf( "\n"); } printf( " . . . .\n" " . . . .\n" " . . . .\n" " . . . .\n" ); for( i=A.num_rows-4; i < A.num_rows; i++ ) { // lower left corner for( j=0; j < 4; j++ ) { double tmp = MAGMA_D_ZERO; magma_index_t rbound = min( A.row[i]+4, A.row[i+1]); magma_index_t lbound = max( A.row[i], A.row[i]); for( k=lbound; k < rbound; k++ ) { if ( A.col[k] == j ) { tmp = A.val[k]; } } magma_dprintval( tmp ); } printf( " "); // lower right corner for( j=A.num_cols-4; j < A.num_cols; j++ ) { double tmp = MAGMA_D_ZERO; magma_index_t rbound = min( A.row[i+1], A.row[i+1]); magma_index_t lbound = max( A.row[i+1]-4, A.row[i]); for( k=lbound; k < rbound; k++ ) { if ( A.col[k] == j ) { tmp = A.val[k]; } } magma_dprintval( tmp ); } printf( "\n"); } } } else { CHECK( magma_dmconvert( A, &C, A.storage_type, Magma_CSR, queue )); CHECK( magma_dprint_matrix( C, queue )); } } else { //magma_d_matrix C={Magma_CSR}; CHECK( magma_dmtransfer( A, &C, A.memory_location, Magma_CPU, queue )); CHECK( magma_dprint_matrix( C, queue )); } cleanup: magma_dmfree( &C, queue ); return info; }
/* //////////////////////////////////////////////////////////////////////////// -- testing any solver */ int main( int argc, char** argv ) { magma_int_t info = 0; TESTING_INIT(); magma_dopts zopts; magma_queue_t queue=NULL; magma_queue_create( 0, &queue ); real_Double_t res; magma_d_matrix Z={Magma_CSR}, A={Magma_CSR}, AT={Magma_CSR}, A2={Magma_CSR}, B={Magma_CSR}, B_d={Magma_CSR}; magma_index_t *comm_i=NULL; double *comm_v=NULL; magma_int_t start, end; int i=1; CHECK( magma_dparse_opts( argc, argv, &zopts, &i, queue )); B.blocksize = zopts.blocksize; B.alignment = zopts.alignment; while( i < argc ) { if ( strcmp("LAPLACE2D", argv[i]) == 0 && i+1 < argc ) { // Laplace test i++; magma_int_t laplace_size = atoi( argv[i] ); CHECK( magma_dm_5stencil( laplace_size, &Z, queue )); } else { // file-matrix test CHECK( magma_d_csr_mtx( &Z, argv[i], queue )); } printf("%% matrix info: %d-by-%d with %d nonzeros\n", int(Z.num_rows), int(Z.num_cols), int(Z.nnz) ); // slice matrix CHECK( magma_index_malloc_cpu( &comm_i, Z.num_rows ) ); CHECK( magma_dmalloc_cpu( &comm_v, Z.num_rows ) ); CHECK( magma_dmslice( 1, 0, Z, &A2, &AT, &B, comm_i, comm_v, &start, &end, queue ) ); magma_dprint_matrix( A2, queue ); magma_dprint_matrix( AT, queue ); magma_dprint_matrix( B, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&AT, queue ); magma_dmfree(&B, queue ); CHECK( magma_dmslice( 9, 0, Z, &A2, &AT, &B, comm_i, comm_v, &start, &end, queue ) ); magma_dprint_matrix( A2, queue ); magma_dprint_matrix( AT, queue ); magma_dprint_matrix( B, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&AT, queue ); magma_dmfree(&B, queue ); CHECK( magma_dmslice( 9, 1, Z, &A2, &AT, &B, comm_i, comm_v, &start, &end, queue ) ); magma_dprint_matrix( A2, queue ); magma_dprint_matrix( AT, queue ); magma_dprint_matrix( B, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&AT, queue ); magma_dmfree(&B, queue ); CHECK( magma_dmslice( 9, 8, Z, &A2, &AT, &B, comm_i, comm_v, &start, &end, queue ) ); magma_dprint_matrix( A2, queue ); magma_dprint_matrix( AT, queue ); magma_dprint_matrix( B, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&AT, queue ); magma_dmfree(&B, queue ); // scale matrix CHECK( magma_dmscale( &Z, zopts.scaling, queue )); // remove nonzeros in matrix CHECK( magma_dmcsrcompressor( &Z, queue )); // convert to be non-symmetric CHECK( magma_dmconvert( Z, &A, Magma_CSR, Magma_CSRL, queue )); // transpose CHECK( magma_dmtranspose( A, &AT, queue )); // convert, copy back and forth to check everything works CHECK( magma_dmconvert( AT, &B, Magma_CSR, zopts.output_format, queue )); magma_dmfree(&AT, queue ); CHECK( magma_dmtransfer( B, &B_d, Magma_CPU, Magma_DEV, queue )); magma_dmfree(&B, queue ); CHECK( magma_dmcsrcompressor_gpu( &B_d, queue )); CHECK( magma_dmtransfer( B_d, &B, Magma_DEV, Magma_CPU, queue )); magma_dmfree(&B_d, queue ); CHECK( magma_dmconvert( B, &AT, zopts.output_format,Magma_CSR, queue )); magma_dmfree(&B, queue ); // transpose back CHECK( magma_dmtranspose( AT, &A2, queue )); magma_dmfree(&AT, queue ); CHECK( magma_dmdiff( A, A2, &res, queue)); printf("%% ||A-B||_F = %8.2e\n", res); if ( res < .000001 ) printf("%% tester: ok\n"); else printf("%% tester: failed\n"); magma_free_cpu( comm_i ); magma_free_cpu( comm_v ); comm_i=NULL; comm_v=NULL; magma_dmfree(&A, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&Z, queue ); i++; } cleanup: magma_free_cpu( comm_i ); magma_free_cpu( comm_v ); magma_dmfree(&AT, queue ); magma_dmfree(&A, queue ); magma_dmfree(&B, queue ); magma_dmfree(&B_d, queue ); magma_dmfree(&A2, queue ); magma_dmfree(&Z, queue ); magma_queue_destroy( queue ); TESTING_FINALIZE(); return info; }