/* ////////////////////////////////////////////////////////////////////////////
-- 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;
}
