1be1d678aSKris Buschelman 2b97cf49bSBarry Smith /* 3b97cf49bSBarry Smith Defines the basic matrix operations for the ADJ adjacency list matrix data-structure. 4b97cf49bSBarry Smith */ 5e37d9405SJed Brown #include <../src/mat/impls/adj/mpi/mpiadj.h> /*I "petscmat.h" I*/ 6b97cf49bSBarry Smith 74a2ae208SSatish Balay #undef __FUNCT__ 84a2ae208SSatish Balay #define __FUNCT__ "MatView_MPIAdj_ASCII" 9dfbe8321SBarry Smith PetscErrorCode MatView_MPIAdj_ASCII(Mat A,PetscViewer viewer) 10b97cf49bSBarry Smith { 113eda8832SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 12dfbe8321SBarry Smith PetscErrorCode ierr; 13d0f46423SBarry Smith PetscInt i,j,m = A->rmap->n; 142dcb1b2aSMatthew Knepley const char *name; 15ce1411ecSBarry Smith PetscViewerFormat format; 16b97cf49bSBarry Smith 17433994e6SBarry Smith PetscFunctionBegin; 183a7fca6bSBarry Smith ierr = PetscObjectGetName((PetscObject)A,&name);CHKERRQ(ierr); 19b0a32e0cSBarry Smith ierr = PetscViewerGetFormat(viewer,&format);CHKERRQ(ierr); 20fb9695e5SSatish Balay if (format == PETSC_VIEWER_ASCII_INFO) { 213a40ed3dSBarry Smith PetscFunctionReturn(0); 22fb9695e5SSatish Balay } else if (format == PETSC_VIEWER_ASCII_MATLAB) { 23ce94432eSBarry Smith SETERRQ(PetscObjectComm((PetscObject)A),PETSC_ERR_SUP,"MATLAB format not supported"); 240752156aSBarry Smith } else { 25d00279f6SBarry Smith ierr = PetscViewerASCIIUseTabs(viewer,PETSC_FALSE);CHKERRQ(ierr); 267b23a99aSBarry Smith ierr = PetscViewerASCIISynchronizedAllow(viewer,PETSC_TRUE);CHKERRQ(ierr); 27b97cf49bSBarry Smith for (i=0; i<m; i++) { 28d0f46423SBarry Smith ierr = PetscViewerASCIISynchronizedPrintf(viewer,"row %D:",i+A->rmap->rstart);CHKERRQ(ierr); 29b97cf49bSBarry Smith for (j=a->i[i]; j<a->i[i+1]; j++) { 3077431f27SBarry Smith ierr = PetscViewerASCIISynchronizedPrintf(viewer," %D ",a->j[j]);CHKERRQ(ierr); 310752156aSBarry Smith } 32b0a32e0cSBarry Smith ierr = PetscViewerASCIISynchronizedPrintf(viewer,"\n");CHKERRQ(ierr); 33b97cf49bSBarry Smith } 34d00279f6SBarry Smith ierr = PetscViewerASCIIUseTabs(viewer,PETSC_TRUE);CHKERRQ(ierr); 35b0a32e0cSBarry Smith ierr = PetscViewerFlush(viewer);CHKERRQ(ierr); 367b23a99aSBarry Smith ierr = PetscViewerASCIISynchronizedAllow(viewer,PETSC_FALSE);CHKERRQ(ierr); 377b23a99aSBarry Smith } 383a40ed3dSBarry Smith PetscFunctionReturn(0); 39b97cf49bSBarry Smith } 40b97cf49bSBarry Smith 414a2ae208SSatish Balay #undef __FUNCT__ 424a2ae208SSatish Balay #define __FUNCT__ "MatView_MPIAdj" 43dfbe8321SBarry Smith PetscErrorCode MatView_MPIAdj(Mat A,PetscViewer viewer) 44b97cf49bSBarry Smith { 45dfbe8321SBarry Smith PetscErrorCode ierr; 46ace3abfcSBarry Smith PetscBool iascii; 47b97cf49bSBarry Smith 48433994e6SBarry Smith PetscFunctionBegin; 49251f4c67SDmitry Karpeev ierr = PetscObjectTypeCompare((PetscObject)viewer,PETSCVIEWERASCII,&iascii);CHKERRQ(ierr); 5032077d6dSBarry Smith if (iascii) { 513eda8832SBarry Smith ierr = MatView_MPIAdj_ASCII(A,viewer);CHKERRQ(ierr); 52b97cf49bSBarry Smith } 533a40ed3dSBarry Smith PetscFunctionReturn(0); 54b97cf49bSBarry Smith } 55b97cf49bSBarry Smith 564a2ae208SSatish Balay #undef __FUNCT__ 574a2ae208SSatish Balay #define __FUNCT__ "MatDestroy_MPIAdj" 58dfbe8321SBarry Smith PetscErrorCode MatDestroy_MPIAdj(Mat mat) 59b97cf49bSBarry Smith { 603eda8832SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)mat->data; 61dfbe8321SBarry Smith PetscErrorCode ierr; 6294d884c6SBarry Smith 6394d884c6SBarry Smith PetscFunctionBegin; 64aa482453SBarry Smith #if defined(PETSC_USE_LOG) 65d0f46423SBarry Smith PetscLogObjectState((PetscObject)mat,"Rows=%D, Cols=%D, NZ=%D",mat->rmap->n,mat->cmap->n,a->nz); 66b97cf49bSBarry Smith #endif 6705b42c5fSBarry Smith ierr = PetscFree(a->diag);CHKERRQ(ierr); 680400557aSBarry Smith if (a->freeaij) { 6914196391SBarry Smith if (a->freeaijwithfree) { 7014196391SBarry Smith if (a->i) free(a->i); 7114196391SBarry Smith if (a->j) free(a->j); 7214196391SBarry Smith } else { 73606d414cSSatish Balay ierr = PetscFree(a->i);CHKERRQ(ierr); 74606d414cSSatish Balay ierr = PetscFree(a->j);CHKERRQ(ierr); 7505b42c5fSBarry Smith ierr = PetscFree(a->values);CHKERRQ(ierr); 7614196391SBarry Smith } 770400557aSBarry Smith } 78bf0cc555SLisandro Dalcin ierr = PetscFree(mat->data);CHKERRQ(ierr); 79dbd8c25aSHong Zhang ierr = PetscObjectChangeTypeName((PetscObject)mat,0);CHKERRQ(ierr); 80bdf89e91SBarry Smith ierr = PetscObjectComposeFunction((PetscObject)mat,"MatMPIAdjSetPreallocation_C",NULL);CHKERRQ(ierr); 81bdf89e91SBarry Smith ierr = PetscObjectComposeFunction((PetscObject)mat,"MatMPIAdjCreateNonemptySubcommMat_C",NULL);CHKERRQ(ierr); 823a40ed3dSBarry Smith PetscFunctionReturn(0); 83b97cf49bSBarry Smith } 84b97cf49bSBarry Smith 854a2ae208SSatish Balay #undef __FUNCT__ 864a2ae208SSatish Balay #define __FUNCT__ "MatSetOption_MPIAdj" 87ace3abfcSBarry Smith PetscErrorCode MatSetOption_MPIAdj(Mat A,MatOption op,PetscBool flg) 88b97cf49bSBarry Smith { 893eda8832SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 9063ba0a88SBarry Smith PetscErrorCode ierr; 91b97cf49bSBarry Smith 92433994e6SBarry Smith PetscFunctionBegin; 9312c028f9SKris Buschelman switch (op) { 9477e54ba9SKris Buschelman case MAT_SYMMETRIC: 9512c028f9SKris Buschelman case MAT_STRUCTURALLY_SYMMETRIC: 969a4540c5SBarry Smith case MAT_HERMITIAN: 974e0d8c25SBarry Smith a->symmetric = flg; 989a4540c5SBarry Smith break; 999a4540c5SBarry Smith case MAT_SYMMETRY_ETERNAL: 1009a4540c5SBarry Smith break; 10112c028f9SKris Buschelman default: 102290bbb0aSBarry Smith ierr = PetscInfo1(A,"Option %s ignored\n",MatOptions[op]);CHKERRQ(ierr); 10312c028f9SKris Buschelman break; 104b97cf49bSBarry Smith } 1053a40ed3dSBarry Smith PetscFunctionReturn(0); 106b97cf49bSBarry Smith } 107b97cf49bSBarry Smith 108b97cf49bSBarry Smith 109b97cf49bSBarry Smith /* 110b97cf49bSBarry Smith Adds diagonal pointers to sparse matrix structure. 111b97cf49bSBarry Smith */ 112b97cf49bSBarry Smith 1134a2ae208SSatish Balay #undef __FUNCT__ 1144a2ae208SSatish Balay #define __FUNCT__ "MatMarkDiagonal_MPIAdj" 115dfbe8321SBarry Smith PetscErrorCode MatMarkDiagonal_MPIAdj(Mat A) 116b97cf49bSBarry Smith { 1173eda8832SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 1186849ba73SBarry Smith PetscErrorCode ierr; 119d0f46423SBarry Smith PetscInt i,j,m = A->rmap->n; 120b97cf49bSBarry Smith 121433994e6SBarry Smith PetscFunctionBegin; 12209f38230SBarry Smith ierr = PetscMalloc(m*sizeof(PetscInt),&a->diag);CHKERRQ(ierr); 123*3bb1ff40SBarry Smith ierr = PetscLogObjectMemory((PetscObject)A,m*sizeof(PetscInt));CHKERRQ(ierr); 124d0f46423SBarry Smith for (i=0; i<A->rmap->n; i++) { 125b97cf49bSBarry Smith for (j=a->i[i]; j<a->i[i+1]; j++) { 126b97cf49bSBarry Smith if (a->j[j] == i) { 12709f38230SBarry Smith a->diag[i] = j; 128b97cf49bSBarry Smith break; 129b97cf49bSBarry Smith } 130b97cf49bSBarry Smith } 131b97cf49bSBarry Smith } 1323a40ed3dSBarry Smith PetscFunctionReturn(0); 133b97cf49bSBarry Smith } 134b97cf49bSBarry Smith 1354a2ae208SSatish Balay #undef __FUNCT__ 1364a2ae208SSatish Balay #define __FUNCT__ "MatGetRow_MPIAdj" 137b24ad042SBarry Smith PetscErrorCode MatGetRow_MPIAdj(Mat A,PetscInt row,PetscInt *nz,PetscInt **idx,PetscScalar **v) 138b97cf49bSBarry Smith { 1393eda8832SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 140b24ad042SBarry Smith PetscInt *itmp; 141b97cf49bSBarry Smith 142433994e6SBarry Smith PetscFunctionBegin; 143d0f46423SBarry Smith row -= A->rmap->rstart; 1440752156aSBarry Smith 145e32f2f54SBarry Smith if (row < 0 || row >= A->rmap->n) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_OUTOFRANGE,"Row out of range"); 146b97cf49bSBarry Smith 147b97cf49bSBarry Smith *nz = a->i[row+1] - a->i[row]; 1480298fd71SBarry Smith if (v) *v = NULL; 149b97cf49bSBarry Smith if (idx) { 150b97cf49bSBarry Smith itmp = a->j + a->i[row]; 151b97cf49bSBarry Smith if (*nz) { 152b97cf49bSBarry Smith *idx = itmp; 153b97cf49bSBarry Smith } 154b97cf49bSBarry Smith else *idx = 0; 155b97cf49bSBarry Smith } 1563a40ed3dSBarry Smith PetscFunctionReturn(0); 157b97cf49bSBarry Smith } 158b97cf49bSBarry Smith 1594a2ae208SSatish Balay #undef __FUNCT__ 1604a2ae208SSatish Balay #define __FUNCT__ "MatRestoreRow_MPIAdj" 161b24ad042SBarry Smith PetscErrorCode MatRestoreRow_MPIAdj(Mat A,PetscInt row,PetscInt *nz,PetscInt **idx,PetscScalar **v) 162b97cf49bSBarry Smith { 163433994e6SBarry Smith PetscFunctionBegin; 1643a40ed3dSBarry Smith PetscFunctionReturn(0); 165b97cf49bSBarry Smith } 166b97cf49bSBarry Smith 1674a2ae208SSatish Balay #undef __FUNCT__ 1684a2ae208SSatish Balay #define __FUNCT__ "MatEqual_MPIAdj" 169ace3abfcSBarry Smith PetscErrorCode MatEqual_MPIAdj(Mat A,Mat B,PetscBool * flg) 170b97cf49bSBarry Smith { 1713eda8832SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data,*b = (Mat_MPIAdj*)B->data; 172dfbe8321SBarry Smith PetscErrorCode ierr; 173ace3abfcSBarry Smith PetscBool flag; 174b97cf49bSBarry Smith 175433994e6SBarry Smith PetscFunctionBegin; 176b97cf49bSBarry Smith /* If the matrix dimensions are not equal,or no of nonzeros */ 177d0f46423SBarry Smith if ((A->rmap->n != B->rmap->n) ||(a->nz != b->nz)) { 1780f5bd95cSBarry Smith flag = PETSC_FALSE; 179b97cf49bSBarry Smith } 180b97cf49bSBarry Smith 181b97cf49bSBarry Smith /* if the a->i are the same */ 182d0f46423SBarry Smith ierr = PetscMemcmp(a->i,b->i,(A->rmap->n+1)*sizeof(PetscInt),&flag);CHKERRQ(ierr); 183b97cf49bSBarry Smith 184b97cf49bSBarry Smith /* if a->j are the same */ 185b24ad042SBarry Smith ierr = PetscMemcmp(a->j,b->j,(a->nz)*sizeof(PetscInt),&flag);CHKERRQ(ierr); 186b97cf49bSBarry Smith 187ce94432eSBarry Smith ierr = MPI_Allreduce(&flag,flg,1,MPIU_BOOL,MPI_LAND,PetscObjectComm((PetscObject)A));CHKERRQ(ierr); 1883a40ed3dSBarry Smith PetscFunctionReturn(0); 189b97cf49bSBarry Smith } 190b97cf49bSBarry Smith 1914a2ae208SSatish Balay #undef __FUNCT__ 1924a2ae208SSatish Balay #define __FUNCT__ "MatGetRowIJ_MPIAdj" 1931a83f524SJed Brown PetscErrorCode MatGetRowIJ_MPIAdj(Mat A,PetscInt oshift,PetscBool symmetric,PetscBool blockcompressed,PetscInt *m,const PetscInt *inia[],const PetscInt *inja[],PetscBool *done) 1946cd91f64SBarry Smith { 195b24ad042SBarry Smith PetscInt i; 1966cd91f64SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 1971a83f524SJed Brown PetscInt **ia = (PetscInt**)inia,**ja = (PetscInt**)inja; 1986cd91f64SBarry Smith 1996cd91f64SBarry Smith PetscFunctionBegin; 200d0f46423SBarry Smith *m = A->rmap->n; 2016cd91f64SBarry Smith *ia = a->i; 2026cd91f64SBarry Smith *ja = a->j; 2036cd91f64SBarry Smith *done = PETSC_TRUE; 204d42735a1SBarry Smith if (oshift) { 205d42735a1SBarry Smith for (i=0; i<(*ia)[*m]; i++) { 206d42735a1SBarry Smith (*ja)[i]++; 207d42735a1SBarry Smith } 208d42735a1SBarry Smith for (i=0; i<=(*m); i++) (*ia)[i]++; 209d42735a1SBarry Smith } 210d42735a1SBarry Smith PetscFunctionReturn(0); 211d42735a1SBarry Smith } 212d42735a1SBarry Smith 2134a2ae208SSatish Balay #undef __FUNCT__ 2144a2ae208SSatish Balay #define __FUNCT__ "MatRestoreRowIJ_MPIAdj" 2151a83f524SJed Brown PetscErrorCode MatRestoreRowIJ_MPIAdj(Mat A,PetscInt oshift,PetscBool symmetric,PetscBool blockcompressed,PetscInt *m,const PetscInt *inia[],const PetscInt *inja[],PetscBool *done) 216d42735a1SBarry Smith { 217b24ad042SBarry Smith PetscInt i; 218d42735a1SBarry Smith Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 2191a83f524SJed Brown PetscInt **ia = (PetscInt**)inia,**ja = (PetscInt**)inja; 220d42735a1SBarry Smith 221d42735a1SBarry Smith PetscFunctionBegin; 222e32f2f54SBarry Smith if (ia && a->i != *ia) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_WRONGSTATE,"ia passed back is not one obtained with MatGetRowIJ()"); 223e32f2f54SBarry Smith if (ja && a->j != *ja) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_WRONGSTATE,"ja passed back is not one obtained with MatGetRowIJ()"); 224d42735a1SBarry Smith if (oshift) { 225d42735a1SBarry Smith for (i=0; i<=(*m); i++) (*ia)[i]--; 226d42735a1SBarry Smith for (i=0; i<(*ia)[*m]; i++) { 227d42735a1SBarry Smith (*ja)[i]--; 228d42735a1SBarry Smith } 229d42735a1SBarry Smith } 2306cd91f64SBarry Smith PetscFunctionReturn(0); 2316cd91f64SBarry Smith } 232b97cf49bSBarry Smith 23317667f90SBarry Smith #undef __FUNCT__ 23417667f90SBarry Smith #define __FUNCT__ "MatConvertFrom_MPIAdj" 23519fd82e9SBarry Smith PetscErrorCode MatConvertFrom_MPIAdj(Mat A,MatType type,MatReuse reuse,Mat *newmat) 23617667f90SBarry Smith { 23717667f90SBarry Smith Mat B; 23817667f90SBarry Smith PetscErrorCode ierr; 23917667f90SBarry Smith PetscInt i,m,N,nzeros = 0,*ia,*ja,len,rstart,cnt,j,*a; 24017667f90SBarry Smith const PetscInt *rj; 24117667f90SBarry Smith const PetscScalar *ra; 24217667f90SBarry Smith MPI_Comm comm; 24317667f90SBarry Smith 24417667f90SBarry Smith PetscFunctionBegin; 2450298fd71SBarry Smith ierr = MatGetSize(A,NULL,&N);CHKERRQ(ierr); 2460298fd71SBarry Smith ierr = MatGetLocalSize(A,&m,NULL);CHKERRQ(ierr); 2470298fd71SBarry Smith ierr = MatGetOwnershipRange(A,&rstart,NULL);CHKERRQ(ierr); 24817667f90SBarry Smith 24917667f90SBarry Smith /* count the number of nonzeros per row */ 25017667f90SBarry Smith for (i=0; i<m; i++) { 2510298fd71SBarry Smith ierr = MatGetRow(A,i+rstart,&len,&rj,NULL);CHKERRQ(ierr); 2525ee9ba1cSJed Brown for (j=0; j<len; j++) { 2535ee9ba1cSJed Brown if (rj[j] == i+rstart) {len--; break;} /* don't count diagonal */ 2545ee9ba1cSJed Brown } 25517667f90SBarry Smith nzeros += len; 2560f2063bfSTobin Isaac ierr = MatRestoreRow(A,i+rstart,&len,&rj,NULL);CHKERRQ(ierr); 25717667f90SBarry Smith } 25817667f90SBarry Smith 25917667f90SBarry Smith /* malloc space for nonzeros */ 26017667f90SBarry Smith ierr = PetscMalloc((nzeros+1)*sizeof(PetscInt),&a);CHKERRQ(ierr); 26117667f90SBarry Smith ierr = PetscMalloc((N+1)*sizeof(PetscInt),&ia);CHKERRQ(ierr); 26217667f90SBarry Smith ierr = PetscMalloc((nzeros+1)*sizeof(PetscInt),&ja);CHKERRQ(ierr); 26317667f90SBarry Smith 26417667f90SBarry Smith nzeros = 0; 26517667f90SBarry Smith ia[0] = 0; 26617667f90SBarry Smith for (i=0; i<m; i++) { 26717667f90SBarry Smith ierr = MatGetRow(A,i+rstart,&len,&rj,&ra);CHKERRQ(ierr); 26817667f90SBarry Smith cnt = 0; 26917667f90SBarry Smith for (j=0; j<len; j++) { 2705ee9ba1cSJed Brown if (rj[j] != i+rstart) { /* if not diagonal */ 27117667f90SBarry Smith a[nzeros+cnt] = (PetscInt) PetscAbsScalar(ra[j]); 27217667f90SBarry Smith ja[nzeros+cnt++] = rj[j]; 27317667f90SBarry Smith } 2745ee9ba1cSJed Brown } 27517667f90SBarry Smith ierr = MatRestoreRow(A,i+rstart,&len,&rj,&ra);CHKERRQ(ierr); 27617667f90SBarry Smith nzeros += cnt; 27717667f90SBarry Smith ia[i+1] = nzeros; 27817667f90SBarry Smith } 27917667f90SBarry Smith 28017667f90SBarry Smith ierr = PetscObjectGetComm((PetscObject)A,&comm);CHKERRQ(ierr); 28117667f90SBarry Smith ierr = MatCreate(comm,&B);CHKERRQ(ierr); 28258ec18a5SLisandro Dalcin ierr = MatSetSizes(B,m,PETSC_DETERMINE,PETSC_DETERMINE,N);CHKERRQ(ierr); 28317667f90SBarry Smith ierr = MatSetType(B,type);CHKERRQ(ierr); 28417667f90SBarry Smith ierr = MatMPIAdjSetPreallocation(B,ia,ja,a);CHKERRQ(ierr); 28517667f90SBarry Smith 28617667f90SBarry Smith if (reuse == MAT_REUSE_MATRIX) { 28717667f90SBarry Smith ierr = MatHeaderReplace(A,B);CHKERRQ(ierr); 28817667f90SBarry Smith } else { 28917667f90SBarry Smith *newmat = B; 29017667f90SBarry Smith } 29117667f90SBarry Smith PetscFunctionReturn(0); 29217667f90SBarry Smith } 29317667f90SBarry Smith 294b97cf49bSBarry Smith /* -------------------------------------------------------------------*/ 2950b3b1487SBarry Smith static struct _MatOps MatOps_Values = {0, 2963eda8832SBarry Smith MatGetRow_MPIAdj, 2973eda8832SBarry Smith MatRestoreRow_MPIAdj, 298b97cf49bSBarry Smith 0, 29997304618SKris Buschelman /* 4*/ 0, 300b97cf49bSBarry Smith 0, 301b97cf49bSBarry Smith 0, 302b97cf49bSBarry Smith 0, 3030b3b1487SBarry Smith 0, 3040b3b1487SBarry Smith 0, 30597304618SKris Buschelman /*10*/ 0, 3060b3b1487SBarry Smith 0, 3070b3b1487SBarry Smith 0, 3080b3b1487SBarry Smith 0, 3090b3b1487SBarry Smith 0, 31097304618SKris Buschelman /*15*/ 0, 3113eda8832SBarry Smith MatEqual_MPIAdj, 3120b3b1487SBarry Smith 0, 3130b3b1487SBarry Smith 0, 3140b3b1487SBarry Smith 0, 31597304618SKris Buschelman /*20*/ 0, 3160b3b1487SBarry Smith 0, 3173eda8832SBarry Smith MatSetOption_MPIAdj, 3180b3b1487SBarry Smith 0, 319d519adbfSMatthew Knepley /*24*/ 0, 3200b3b1487SBarry Smith 0, 3210b3b1487SBarry Smith 0, 3220b3b1487SBarry Smith 0, 3230b3b1487SBarry Smith 0, 324d519adbfSMatthew Knepley /*29*/ 0, 3250b3b1487SBarry Smith 0, 326273d9f13SBarry Smith 0, 327273d9f13SBarry Smith 0, 3280b3b1487SBarry Smith 0, 329d519adbfSMatthew Knepley /*34*/ 0, 3300b3b1487SBarry Smith 0, 3310b3b1487SBarry Smith 0, 3320b3b1487SBarry Smith 0, 3330b3b1487SBarry Smith 0, 334d519adbfSMatthew Knepley /*39*/ 0, 3350b3b1487SBarry Smith 0, 3360b3b1487SBarry Smith 0, 3370b3b1487SBarry Smith 0, 3380b3b1487SBarry Smith 0, 339d519adbfSMatthew Knepley /*44*/ 0, 3400b3b1487SBarry Smith 0, 3410b3b1487SBarry Smith 0, 3420b3b1487SBarry Smith 0, 3430b3b1487SBarry Smith 0, 344d519adbfSMatthew Knepley /*49*/ 0, 3456cd91f64SBarry Smith MatGetRowIJ_MPIAdj, 346d42735a1SBarry Smith MatRestoreRowIJ_MPIAdj, 347b97cf49bSBarry Smith 0, 348b97cf49bSBarry Smith 0, 349d519adbfSMatthew Knepley /*54*/ 0, 350b97cf49bSBarry Smith 0, 3510752156aSBarry Smith 0, 3520752156aSBarry Smith 0, 3530b3b1487SBarry Smith 0, 354d519adbfSMatthew Knepley /*59*/ 0, 355b9b97703SBarry Smith MatDestroy_MPIAdj, 356b9b97703SBarry Smith MatView_MPIAdj, 35717667f90SBarry Smith MatConvertFrom_MPIAdj, 35897304618SKris Buschelman 0, 359d519adbfSMatthew Knepley /*64*/ 0, 36097304618SKris Buschelman 0, 36197304618SKris Buschelman 0, 36297304618SKris Buschelman 0, 36397304618SKris Buschelman 0, 364d519adbfSMatthew Knepley /*69*/ 0, 36597304618SKris Buschelman 0, 36697304618SKris Buschelman 0, 36797304618SKris Buschelman 0, 36897304618SKris Buschelman 0, 369d519adbfSMatthew Knepley /*74*/ 0, 37097304618SKris Buschelman 0, 37197304618SKris Buschelman 0, 37297304618SKris Buschelman 0, 37397304618SKris Buschelman 0, 374d519adbfSMatthew Knepley /*79*/ 0, 37597304618SKris Buschelman 0, 37697304618SKris Buschelman 0, 37797304618SKris Buschelman 0, 378865e5f61SKris Buschelman 0, 379d519adbfSMatthew Knepley /*84*/ 0, 380865e5f61SKris Buschelman 0, 381865e5f61SKris Buschelman 0, 382865e5f61SKris Buschelman 0, 383865e5f61SKris Buschelman 0, 384d519adbfSMatthew Knepley /*89*/ 0, 385865e5f61SKris Buschelman 0, 386865e5f61SKris Buschelman 0, 387865e5f61SKris Buschelman 0, 388865e5f61SKris Buschelman 0, 389d519adbfSMatthew Knepley /*94*/ 0, 390865e5f61SKris Buschelman 0, 391865e5f61SKris Buschelman 0, 3923964eb88SJed Brown 0, 3933964eb88SJed Brown 0, 3943964eb88SJed Brown /*99*/ 0, 3953964eb88SJed Brown 0, 3963964eb88SJed Brown 0, 3973964eb88SJed Brown 0, 3983964eb88SJed Brown 0, 3993964eb88SJed Brown /*104*/ 0, 4003964eb88SJed Brown 0, 4013964eb88SJed Brown 0, 4023964eb88SJed Brown 0, 4033964eb88SJed Brown 0, 4043964eb88SJed Brown /*109*/ 0, 4053964eb88SJed Brown 0, 4063964eb88SJed Brown 0, 4073964eb88SJed Brown 0, 4083964eb88SJed Brown 0, 4093964eb88SJed Brown /*114*/ 0, 4103964eb88SJed Brown 0, 4113964eb88SJed Brown 0, 4123964eb88SJed Brown 0, 4133964eb88SJed Brown 0, 4143964eb88SJed Brown /*119*/ 0, 4153964eb88SJed Brown 0, 4163964eb88SJed Brown 0, 4173964eb88SJed Brown 0, 4183964eb88SJed Brown 0, 4193964eb88SJed Brown /*124*/ 0, 4203964eb88SJed Brown 0, 4213964eb88SJed Brown 0, 4223964eb88SJed Brown 0, 4233964eb88SJed Brown 0, 4243964eb88SJed Brown /*129*/ 0, 4253964eb88SJed Brown 0, 4263964eb88SJed Brown 0, 4273964eb88SJed Brown 0, 4283964eb88SJed Brown 0, 4293964eb88SJed Brown /*134*/ 0, 4303964eb88SJed Brown 0, 4313964eb88SJed Brown 0, 4323964eb88SJed Brown 0, 4333964eb88SJed Brown 0, 4343964eb88SJed Brown /*139*/ 0, 4353964eb88SJed Brown 0 4363964eb88SJed Brown }; 437b97cf49bSBarry Smith 438a23d5eceSKris Buschelman #undef __FUNCT__ 439a23d5eceSKris Buschelman #define __FUNCT__ "MatMPIAdjSetPreallocation_MPIAdj" 440f7a08781SBarry Smith static PetscErrorCode MatMPIAdjSetPreallocation_MPIAdj(Mat B,PetscInt *i,PetscInt *j,PetscInt *values) 441a23d5eceSKris Buschelman { 442a23d5eceSKris Buschelman Mat_MPIAdj *b = (Mat_MPIAdj*)B->data; 443dfbe8321SBarry Smith PetscErrorCode ierr; 4442515c552SBarry Smith #if defined(PETSC_USE_DEBUG) 445b24ad042SBarry Smith PetscInt ii; 446a23d5eceSKris Buschelman #endif 447a23d5eceSKris Buschelman 448a23d5eceSKris Buschelman PetscFunctionBegin; 44926283091SBarry Smith ierr = PetscLayoutSetUp(B->rmap);CHKERRQ(ierr); 45026283091SBarry Smith ierr = PetscLayoutSetUp(B->cmap);CHKERRQ(ierr); 45158ec18a5SLisandro Dalcin 4522515c552SBarry Smith #if defined(PETSC_USE_DEBUG) 453e32f2f54SBarry Smith if (i[0] != 0) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_ARG_OUTOFRANGE,"First i[] index must be zero, instead it is %D\n",i[0]); 454d0f46423SBarry Smith for (ii=1; ii<B->rmap->n; ii++) { 455e02043d6SBarry Smith if (i[ii] < 0 || i[ii] < i[ii-1]) SETERRQ4(PETSC_COMM_SELF,PETSC_ERR_ARG_OUTOFRANGE,"i[%D]=%D index is out of range: i[%D]=%D",ii,i[ii],ii-1,i[ii-1]); 456a23d5eceSKris Buschelman } 457d0f46423SBarry Smith for (ii=0; ii<i[B->rmap->n]; ii++) { 458e02043d6SBarry Smith if (j[ii] < 0 || j[ii] >= B->cmap->N) SETERRQ2(PETSC_COMM_SELF,PETSC_ERR_ARG_OUTOFRANGE,"Column index %D out of range %D\n",ii,j[ii]); 459a23d5eceSKris Buschelman } 460a23d5eceSKris Buschelman #endif 46158ec18a5SLisandro Dalcin B->preallocated = PETSC_TRUE; 462a23d5eceSKris Buschelman 463a23d5eceSKris Buschelman b->j = j; 464a23d5eceSKris Buschelman b->i = i; 465a23d5eceSKris Buschelman b->values = values; 466a23d5eceSKris Buschelman 467d0f46423SBarry Smith b->nz = i[B->rmap->n]; 468a23d5eceSKris Buschelman b->diag = 0; 469a23d5eceSKris Buschelman b->symmetric = PETSC_FALSE; 470a23d5eceSKris Buschelman b->freeaij = PETSC_TRUE; 471a23d5eceSKris Buschelman 472a23d5eceSKris Buschelman ierr = MatAssemblyBegin(B,MAT_FINAL_ASSEMBLY);CHKERRQ(ierr); 473a23d5eceSKris Buschelman ierr = MatAssemblyEnd(B,MAT_FINAL_ASSEMBLY);CHKERRQ(ierr); 474a23d5eceSKris Buschelman PetscFunctionReturn(0); 475a23d5eceSKris Buschelman } 476b97cf49bSBarry Smith 4779a3665c6SJed Brown #undef __FUNCT__ 4789a3665c6SJed Brown #define __FUNCT__ "MatMPIAdjCreateNonemptySubcommMat_MPIAdj" 479f7a08781SBarry Smith static PetscErrorCode MatMPIAdjCreateNonemptySubcommMat_MPIAdj(Mat A,Mat *B) 4809a3665c6SJed Brown { 4819a3665c6SJed Brown Mat_MPIAdj *a = (Mat_MPIAdj*)A->data; 4829a3665c6SJed Brown PetscErrorCode ierr; 4839a3665c6SJed Brown const PetscInt *ranges; 4849a3665c6SJed Brown MPI_Comm acomm,bcomm; 4859a3665c6SJed Brown MPI_Group agroup,bgroup; 4869a3665c6SJed Brown PetscMPIInt i,rank,size,nranks,*ranks; 4879a3665c6SJed Brown 4889a3665c6SJed Brown PetscFunctionBegin; 4890298fd71SBarry Smith *B = NULL; 490ce94432eSBarry Smith ierr = PetscObjectGetComm((PetscObject)A,&acomm);CHKERRQ(ierr); 4919a3665c6SJed Brown ierr = MPI_Comm_size(acomm,&size);CHKERRQ(ierr); 4929a3665c6SJed Brown ierr = MPI_Comm_size(acomm,&rank);CHKERRQ(ierr); 4939a3665c6SJed Brown ierr = MatGetOwnershipRanges(A,&ranges);CHKERRQ(ierr); 4949a3665c6SJed Brown for (i=0,nranks=0; i<size; i++) { 4959a3665c6SJed Brown if (ranges[i+1] - ranges[i] > 0) nranks++; 4969a3665c6SJed Brown } 4979a3665c6SJed Brown if (nranks == size) { /* All ranks have a positive number of rows, so we do not need to create a subcomm; */ 4989a3665c6SJed Brown ierr = PetscObjectReference((PetscObject)A);CHKERRQ(ierr); 4999a3665c6SJed Brown *B = A; 5009a3665c6SJed Brown PetscFunctionReturn(0); 5019a3665c6SJed Brown } 5029a3665c6SJed Brown 5039a3665c6SJed Brown ierr = PetscMalloc(nranks*sizeof(PetscMPIInt),&ranks);CHKERRQ(ierr); 5049a3665c6SJed Brown for (i=0,nranks=0; i<size; i++) { 5059a3665c6SJed Brown if (ranges[i+1] - ranges[i] > 0) ranks[nranks++] = i; 5069a3665c6SJed Brown } 5079a3665c6SJed Brown ierr = MPI_Comm_group(acomm,&agroup);CHKERRQ(ierr); 5089a3665c6SJed Brown ierr = MPI_Group_incl(agroup,nranks,ranks,&bgroup);CHKERRQ(ierr); 5099a3665c6SJed Brown ierr = PetscFree(ranks);CHKERRQ(ierr); 5109a3665c6SJed Brown ierr = MPI_Comm_create(acomm,bgroup,&bcomm);CHKERRQ(ierr); 5119a3665c6SJed Brown ierr = MPI_Group_free(&agroup);CHKERRQ(ierr); 5129a3665c6SJed Brown ierr = MPI_Group_free(&bgroup);CHKERRQ(ierr); 5139a3665c6SJed Brown if (bcomm != MPI_COMM_NULL) { 5149a3665c6SJed Brown PetscInt m,N; 5159a3665c6SJed Brown Mat_MPIAdj *b; 5160298fd71SBarry Smith ierr = MatGetLocalSize(A,&m,NULL);CHKERRQ(ierr); 5170298fd71SBarry Smith ierr = MatGetSize(A,NULL,&N);CHKERRQ(ierr); 5189a3665c6SJed Brown ierr = MatCreateMPIAdj(bcomm,m,N,a->i,a->j,a->values,B);CHKERRQ(ierr); 5199a3665c6SJed Brown b = (Mat_MPIAdj*)(*B)->data; 5209a3665c6SJed Brown b->freeaij = PETSC_FALSE; 5219a3665c6SJed Brown ierr = MPI_Comm_free(&bcomm);CHKERRQ(ierr); 5229a3665c6SJed Brown } 5239a3665c6SJed Brown PetscFunctionReturn(0); 5249a3665c6SJed Brown } 5259a3665c6SJed Brown 5269a3665c6SJed Brown #undef __FUNCT__ 5279a3665c6SJed Brown #define __FUNCT__ "MatMPIAdjCreateNonemptySubcommMat" 5289a3665c6SJed Brown /*@ 5299a3665c6SJed Brown MatMPIAdjCreateNonemptySubcommMat - create the same MPIAdj matrix on a subcommunicator containing only processes owning a positive number of rows 5309a3665c6SJed Brown 5319a3665c6SJed Brown Collective 5329a3665c6SJed Brown 5339a3665c6SJed Brown Input Arguments: 5349a3665c6SJed Brown . A - original MPIAdj matrix 5359a3665c6SJed Brown 5369a3665c6SJed Brown Output Arguments: 5370298fd71SBarry Smith . B - matrix on subcommunicator, NULL on ranks that owned zero rows of A 5389a3665c6SJed Brown 5399a3665c6SJed Brown Level: developer 5409a3665c6SJed Brown 5419a3665c6SJed Brown Note: 5429a3665c6SJed Brown This function is mostly useful for internal use by mesh partitioning packages that require that every process owns at least one row. 5439a3665c6SJed Brown 5449a3665c6SJed Brown The matrix B should be destroyed with MatDestroy(). The arrays are not copied, so B should be destroyed before A is destroyed. 5459a3665c6SJed Brown 5469a3665c6SJed Brown .seealso: MatCreateMPIAdj() 5479a3665c6SJed Brown @*/ 5489a3665c6SJed Brown PetscErrorCode MatMPIAdjCreateNonemptySubcommMat(Mat A,Mat *B) 5499a3665c6SJed Brown { 5509a3665c6SJed Brown PetscErrorCode ierr; 5519a3665c6SJed Brown 5529a3665c6SJed Brown PetscFunctionBegin; 5539a3665c6SJed Brown PetscValidHeaderSpecific(A,MAT_CLASSID,1); 5549a3665c6SJed Brown ierr = PetscUseMethod(A,"MatMPIAdjCreateNonemptySubcommMat_C",(Mat,Mat*),(A,B));CHKERRQ(ierr); 5559a3665c6SJed Brown PetscFunctionReturn(0); 5569a3665c6SJed Brown } 5579a3665c6SJed Brown 5580bad9183SKris Buschelman /*MC 559fafad747SKris Buschelman MATMPIADJ - MATMPIADJ = "mpiadj" - A matrix type to be used for distributed adjacency matrices, 5600bad9183SKris Buschelman intended for use constructing orderings and partitionings. 5610bad9183SKris Buschelman 5620bad9183SKris Buschelman Level: beginner 5630bad9183SKris Buschelman 5640bad9183SKris Buschelman .seealso: MatCreateMPIAdj 5650bad9183SKris Buschelman M*/ 5660bad9183SKris Buschelman 5674a2ae208SSatish Balay #undef __FUNCT__ 5684a2ae208SSatish Balay #define __FUNCT__ "MatCreate_MPIAdj" 5698cc058d9SJed Brown PETSC_EXTERN PetscErrorCode MatCreate_MPIAdj(Mat B) 570273d9f13SBarry Smith { 571273d9f13SBarry Smith Mat_MPIAdj *b; 5726849ba73SBarry Smith PetscErrorCode ierr; 573273d9f13SBarry Smith 574273d9f13SBarry Smith PetscFunctionBegin; 57538f2d2fdSLisandro Dalcin ierr = PetscNewLog(B,Mat_MPIAdj,&b);CHKERRQ(ierr); 576b0a32e0cSBarry Smith B->data = (void*)b; 577273d9f13SBarry Smith ierr = PetscMemcpy(B->ops,&MatOps_Values,sizeof(struct _MatOps));CHKERRQ(ierr); 578273d9f13SBarry Smith B->assembled = PETSC_FALSE; 579273d9f13SBarry Smith 580bdf89e91SBarry Smith ierr = PetscObjectComposeFunction((PetscObject)B,"MatMPIAdjSetPreallocation_C",MatMPIAdjSetPreallocation_MPIAdj);CHKERRQ(ierr); 581bdf89e91SBarry Smith ierr = PetscObjectComposeFunction((PetscObject)B,"MatMPIAdjCreateNonemptySubcommMat_C",MatMPIAdjCreateNonemptySubcommMat_MPIAdj);CHKERRQ(ierr); 58217667f90SBarry Smith ierr = PetscObjectChangeTypeName((PetscObject)B,MATMPIADJ);CHKERRQ(ierr); 583273d9f13SBarry Smith PetscFunctionReturn(0); 584273d9f13SBarry Smith } 585273d9f13SBarry Smith 5864a2ae208SSatish Balay #undef __FUNCT__ 5874a2ae208SSatish Balay #define __FUNCT__ "MatMPIAdjSetPreallocation" 588a23d5eceSKris Buschelman /*@C 589a23d5eceSKris Buschelman MatMPIAdjSetPreallocation - Sets the array used for storing the matrix elements 590a23d5eceSKris Buschelman 5913f9fe445SBarry Smith Logically Collective on MPI_Comm 592a23d5eceSKris Buschelman 593a23d5eceSKris Buschelman Input Parameters: 594a23d5eceSKris Buschelman + A - the matrix 595a23d5eceSKris Buschelman . i - the indices into j for the start of each row 596a23d5eceSKris Buschelman . j - the column indices for each row (sorted for each row). 597a23d5eceSKris Buschelman The indices in i and j start with zero (NOT with one). 598a23d5eceSKris Buschelman - values - [optional] edge weights 599a23d5eceSKris Buschelman 600a23d5eceSKris Buschelman Level: intermediate 601a23d5eceSKris Buschelman 602a23d5eceSKris Buschelman .seealso: MatCreate(), MatCreateMPIAdj(), MatSetValues() 603a23d5eceSKris Buschelman @*/ 6047087cfbeSBarry Smith PetscErrorCode MatMPIAdjSetPreallocation(Mat B,PetscInt *i,PetscInt *j,PetscInt *values) 605273d9f13SBarry Smith { 6064ac538c5SBarry Smith PetscErrorCode ierr; 607273d9f13SBarry Smith 608273d9f13SBarry Smith PetscFunctionBegin; 6094ac538c5SBarry Smith ierr = PetscTryMethod(B,"MatMPIAdjSetPreallocation_C",(Mat,PetscInt*,PetscInt*,PetscInt*),(B,i,j,values));CHKERRQ(ierr); 610273d9f13SBarry Smith PetscFunctionReturn(0); 611273d9f13SBarry Smith } 612273d9f13SBarry Smith 6134a2ae208SSatish Balay #undef __FUNCT__ 6144a2ae208SSatish Balay #define __FUNCT__ "MatCreateMPIAdj" 615b97cf49bSBarry Smith /*@C 6163eda8832SBarry Smith MatCreateMPIAdj - Creates a sparse matrix representing an adjacency list. 617b97cf49bSBarry Smith The matrix does not have numerical values associated with it, but is 618b97cf49bSBarry Smith intended for ordering (to reduce bandwidth etc) and partitioning. 619b97cf49bSBarry Smith 620ef5ee4d1SLois Curfman McInnes Collective on MPI_Comm 621ef5ee4d1SLois Curfman McInnes 622b97cf49bSBarry Smith Input Parameters: 623c2e958feSBarry Smith + comm - MPI communicator 6240752156aSBarry Smith . m - number of local rows 62558ec18a5SLisandro Dalcin . N - number of global columns 626b97cf49bSBarry Smith . i - the indices into j for the start of each row 627329f5518SBarry Smith . j - the column indices for each row (sorted for each row). 628ef5ee4d1SLois Curfman McInnes The indices in i and j start with zero (NOT with one). 629329f5518SBarry Smith - values -[optional] edge weights 630b97cf49bSBarry Smith 631b97cf49bSBarry Smith Output Parameter: 632b97cf49bSBarry Smith . A - the matrix 633b97cf49bSBarry Smith 63415091d37SBarry Smith Level: intermediate 63515091d37SBarry Smith 6364bc6d8c0SBarry Smith Notes: This matrix object does not support most matrix operations, include 6374bc6d8c0SBarry Smith MatSetValues(). 638c2e958feSBarry Smith You must NOT free the ii, values and jj arrays yourself. PETSc will free them 639ededeb1aSvictorle when the matrix is destroyed; you must allocate them with PetscMalloc(). If you 6401198db28SBarry Smith call from Fortran you need not create the arrays with PetscMalloc(). 641327e1a73SBarry Smith Should not include the matrix diagonals. 642b97cf49bSBarry Smith 643e3f7e1d6Svictorle If you already have a matrix, you can create its adjacency matrix by a call 644ededeb1aSvictorle to MatConvert, specifying a type of MATMPIADJ. 645ededeb1aSvictorle 646ef5ee4d1SLois Curfman McInnes Possible values for MatSetOption() - MAT_STRUCTURALLY_SYMMETRIC 647b97cf49bSBarry Smith 648e3f7e1d6Svictorle .seealso: MatCreate(), MatConvert(), MatGetOrdering() 649b97cf49bSBarry Smith @*/ 6507087cfbeSBarry Smith PetscErrorCode MatCreateMPIAdj(MPI_Comm comm,PetscInt m,PetscInt N,PetscInt *i,PetscInt *j,PetscInt *values,Mat *A) 651b97cf49bSBarry Smith { 652dfbe8321SBarry Smith PetscErrorCode ierr; 653b97cf49bSBarry Smith 654433994e6SBarry Smith PetscFunctionBegin; 655f69a0ea3SMatthew Knepley ierr = MatCreate(comm,A);CHKERRQ(ierr); 65658ec18a5SLisandro Dalcin ierr = MatSetSizes(*A,m,PETSC_DETERMINE,PETSC_DETERMINE,N);CHKERRQ(ierr); 657273d9f13SBarry Smith ierr = MatSetType(*A,MATMPIADJ);CHKERRQ(ierr); 658273d9f13SBarry Smith ierr = MatMPIAdjSetPreallocation(*A,i,j,values);CHKERRQ(ierr); 6593a40ed3dSBarry Smith PetscFunctionReturn(0); 660b97cf49bSBarry Smith } 661b97cf49bSBarry Smith 662c2e958feSBarry Smith 663433994e6SBarry Smith 664433994e6SBarry Smith 665433994e6SBarry Smith 666433994e6SBarry Smith 667433994e6SBarry Smith 668