1632d0f97SHong Zhang /*$Id: sbaijov.c,v 1.65 2001/08/06 21:15:42 bsmith Exp $*/ 2632d0f97SHong Zhang 3632d0f97SHong Zhang /* 4632d0f97SHong Zhang Routines to compute overlapping regions of a parallel MPI matrix. 5632d0f97SHong Zhang Used for finding submatrices that were shared across processors. 6632d0f97SHong Zhang */ 7632d0f97SHong Zhang #include "src/mat/impls/sbaij/mpi/mpisbaij.h" 8632d0f97SHong Zhang #include "petscbt.h" 9632d0f97SHong Zhang 10632d0f97SHong Zhang static int MatIncreaseOverlap_MPISBAIJ_Once(Mat,int,IS *); 11*dc008846SHong Zhang static int MatIncreaseOverlap_MPISBAIJ_Local(Mat,int *,int **); 12632d0f97SHong Zhang static int MatIncreaseOverlap_MPISBAIJ_Receive(Mat,int,int **,int**,int*); 13632d0f97SHong Zhang 14632d0f97SHong Zhang /* this function is sasme as MatCompressIndicesGeneral_MPIBAIJ -- should be removed! */ 15632d0f97SHong Zhang #undef __FUNCT__ 16632d0f97SHong Zhang #define __FUNCT__ "MatCompressIndicesGeneral_MPISBAIJ" 17632d0f97SHong Zhang static int MatCompressIndicesGeneral_MPISBAIJ(Mat C,int imax,const IS is_in[],IS is_out[]) 18632d0f97SHong Zhang { 19632d0f97SHong Zhang Mat_MPISBAIJ *baij = (Mat_MPISBAIJ*)C->data; 20632d0f97SHong Zhang int ierr,isz,bs = baij->bs,n,i,j,*idx,ival; 21632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 22632d0f97SHong Zhang PetscTable gid1_lid1; 23632d0f97SHong Zhang int tt, gid1, *nidx; 24632d0f97SHong Zhang PetscTablePosition tpos; 25632d0f97SHong Zhang #else 26632d0f97SHong Zhang int Nbs,*nidx; 27632d0f97SHong Zhang PetscBT table; 28632d0f97SHong Zhang #endif 29632d0f97SHong Zhang 30632d0f97SHong Zhang PetscFunctionBegin; 31632d0f97SHong Zhang /* printf(" ...MatCompressIndicesGeneral_MPISBAIJ is called ...\n"); */ 32632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 33632d0f97SHong Zhang ierr = PetscTableCreate(baij->mbs,&gid1_lid1);CHKERRQ(ierr); 34632d0f97SHong Zhang #else 35632d0f97SHong Zhang Nbs = baij->Nbs; 36632d0f97SHong Zhang ierr = PetscMalloc((Nbs+1)*sizeof(int),&nidx);CHKERRQ(ierr); 37632d0f97SHong Zhang ierr = PetscBTCreate(Nbs,table);CHKERRQ(ierr); 38632d0f97SHong Zhang #endif 39632d0f97SHong Zhang for (i=0; i<imax; i++) { 40632d0f97SHong Zhang isz = 0; 41632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 42632d0f97SHong Zhang ierr = PetscTableRemoveAll(gid1_lid1);CHKERRQ(ierr); 43632d0f97SHong Zhang #else 44632d0f97SHong Zhang ierr = PetscBTMemzero(Nbs,table);CHKERRQ(ierr); 45632d0f97SHong Zhang #endif 46632d0f97SHong Zhang ierr = ISGetIndices(is_in[i],&idx);CHKERRQ(ierr); 47632d0f97SHong Zhang ierr = ISGetLocalSize(is_in[i],&n);CHKERRQ(ierr); 48632d0f97SHong Zhang for (j=0; j<n ; j++) { 49632d0f97SHong Zhang ival = idx[j]/bs; /* convert the indices into block indices */ 50632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 51632d0f97SHong Zhang ierr = PetscTableFind(gid1_lid1,ival+1,&tt);CHKERRQ(ierr); 52632d0f97SHong Zhang if (!tt) { 53632d0f97SHong Zhang ierr = PetscTableAdd(gid1_lid1,ival+1,isz+1);CHKERRQ(ierr); 54632d0f97SHong Zhang isz++; 55632d0f97SHong Zhang } 56632d0f97SHong Zhang #else 57632d0f97SHong Zhang if (ival>Nbs) SETERRQ(PETSC_ERR_ARG_OUTOFRANGE,"index greater than mat-dim"); 58632d0f97SHong Zhang if(!PetscBTLookupSet(table,ival)) { nidx[isz++] = ival;} 59632d0f97SHong Zhang #endif 60632d0f97SHong Zhang } 61632d0f97SHong Zhang ierr = ISRestoreIndices(is_in[i],&idx);CHKERRQ(ierr); 62632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 63632d0f97SHong Zhang ierr = PetscMalloc((isz+1)*sizeof(int),&nidx);CHKERRQ(ierr); 64632d0f97SHong Zhang ierr = PetscTableGetHeadPosition(gid1_lid1,&tpos);CHKERRQ(ierr); 65632d0f97SHong Zhang j = 0; 66632d0f97SHong Zhang while (tpos) { 67632d0f97SHong Zhang ierr = PetscTableGetNext(gid1_lid1,&tpos,&gid1,&tt);CHKERRQ(ierr); 68632d0f97SHong Zhang if (tt-- > isz) { SETERRQ(PETSC_ERR_ARG_OUTOFRANGE,"index greater than array-dim"); } 69632d0f97SHong Zhang nidx[tt] = gid1 - 1; 70632d0f97SHong Zhang j++; 71632d0f97SHong Zhang } 72632d0f97SHong Zhang if (j != isz) { SETERRQ(PETSC_ERR_ARG_OUTOFRANGE,"table error: jj != isz"); } 73632d0f97SHong Zhang ierr = ISCreateGeneral(PETSC_COMM_SELF,isz,nidx,(is_out+i));CHKERRQ(ierr); 74632d0f97SHong Zhang ierr = PetscFree(nidx);CHKERRQ(ierr); 75632d0f97SHong Zhang #else 76632d0f97SHong Zhang ierr = ISCreateGeneral(PETSC_COMM_SELF,isz,nidx,(is_out+i));CHKERRQ(ierr); 77632d0f97SHong Zhang #endif 78632d0f97SHong Zhang } 79632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 80632d0f97SHong Zhang ierr = PetscTableDelete(gid1_lid1);CHKERRQ(ierr); 81632d0f97SHong Zhang #else 82632d0f97SHong Zhang ierr = PetscBTDestroy(table);CHKERRQ(ierr); 83632d0f97SHong Zhang ierr = PetscFree(nidx);CHKERRQ(ierr); 84632d0f97SHong Zhang #endif 85632d0f97SHong Zhang PetscFunctionReturn(0); 86632d0f97SHong Zhang } 87632d0f97SHong Zhang 88632d0f97SHong Zhang #undef __FUNCT__ 89632d0f97SHong Zhang #define __FUNCT__ "MatCompressIndicesSorted_MPISBAIJ" 90632d0f97SHong Zhang static int MatCompressIndicesSorted_MPISBAIJ(Mat C,int imax,const IS is_in[],IS is_out[]) 91632d0f97SHong Zhang { 92632d0f97SHong Zhang Mat_MPISBAIJ *baij = (Mat_MPISBAIJ*)C->data; 93632d0f97SHong Zhang int ierr,bs=baij->bs,i,j,k,val,n,*idx,*nidx,*idx_local; 94632d0f97SHong Zhang PetscTruth flg; 95632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 96632d0f97SHong Zhang int maxsz; 97632d0f97SHong Zhang #else 98632d0f97SHong Zhang int Nbs=baij->Nbs; 99632d0f97SHong Zhang #endif 100632d0f97SHong Zhang PetscFunctionBegin; 101632d0f97SHong Zhang printf(" ... MatCompressIndicesSorted_MPISBAIJ is called ...\n"); 102632d0f97SHong Zhang for (i=0; i<imax; i++) { 103632d0f97SHong Zhang ierr = ISSorted(is_in[i],&flg);CHKERRQ(ierr); 104632d0f97SHong Zhang if (!flg) SETERRQ(PETSC_ERR_ARG_WRONGSTATE,"Indices are not sorted"); 105632d0f97SHong Zhang } 106632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 107632d0f97SHong Zhang /* Now check max size */ 108632d0f97SHong Zhang for (i=0,maxsz=0; i<imax; i++) { 109632d0f97SHong Zhang ierr = ISGetIndices(is_in[i],&idx);CHKERRQ(ierr); 110632d0f97SHong Zhang ierr = ISGetLocalSize(is_in[i],&n);CHKERRQ(ierr); 111632d0f97SHong Zhang if (n%bs !=0) SETERRQ(1,"Indices are not block ordered"); 112632d0f97SHong Zhang n = n/bs; /* The reduced index size */ 113632d0f97SHong Zhang if (n > maxsz) maxsz = n; 114632d0f97SHong Zhang } 115632d0f97SHong Zhang ierr = PetscMalloc((maxsz+1)*sizeof(int),&nidx);CHKERRQ(ierr); 116632d0f97SHong Zhang #else 117632d0f97SHong Zhang ierr = PetscMalloc((Nbs+1)*sizeof(int),&nidx);CHKERRQ(ierr); 118632d0f97SHong Zhang #endif 119632d0f97SHong Zhang /* Now check if the indices are in block order */ 120632d0f97SHong Zhang for (i=0; i<imax; i++) { 121632d0f97SHong Zhang ierr = ISGetIndices(is_in[i],&idx);CHKERRQ(ierr); 122632d0f97SHong Zhang ierr = ISGetLocalSize(is_in[i],&n);CHKERRQ(ierr); 123632d0f97SHong Zhang if (n%bs !=0) SETERRQ(1,"Indices are not block ordered"); 124632d0f97SHong Zhang 125632d0f97SHong Zhang n = n/bs; /* The reduced index size */ 126632d0f97SHong Zhang idx_local = idx; 127632d0f97SHong Zhang for (j=0; j<n ; j++) { 128632d0f97SHong Zhang val = idx_local[0]; 129632d0f97SHong Zhang if (val%bs != 0) SETERRQ(1,"Indices are not block ordered"); 130632d0f97SHong Zhang for (k=0; k<bs; k++) { 131632d0f97SHong Zhang if (val+k != idx_local[k]) SETERRQ(1,"Indices are not block ordered"); 132632d0f97SHong Zhang } 133632d0f97SHong Zhang nidx[j] = val/bs; 134632d0f97SHong Zhang idx_local +=bs; 135632d0f97SHong Zhang } 136632d0f97SHong Zhang ierr = ISRestoreIndices(is_in[i],&idx);CHKERRQ(ierr); 137632d0f97SHong Zhang ierr = ISCreateGeneral(PETSC_COMM_SELF,n,nidx,(is_out+i));CHKERRQ(ierr); 138632d0f97SHong Zhang } 139632d0f97SHong Zhang ierr = PetscFree(nidx);CHKERRQ(ierr); 140632d0f97SHong Zhang 141632d0f97SHong Zhang PetscFunctionReturn(0); 142632d0f97SHong Zhang } 143632d0f97SHong Zhang 144632d0f97SHong Zhang #undef __FUNCT__ 145632d0f97SHong Zhang #define __FUNCT__ "MatExpandIndices_MPISBAIJ" 146632d0f97SHong Zhang static int MatExpandIndices_MPISBAIJ(Mat C,int imax,const IS is_in[],IS is_out[]) 147632d0f97SHong Zhang { 148632d0f97SHong Zhang Mat_MPISBAIJ *baij = (Mat_MPISBAIJ*)C->data; 149632d0f97SHong Zhang int ierr,bs = baij->bs,n,i,j,k,*idx,*nidx; 150632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 151632d0f97SHong Zhang int maxsz; 152632d0f97SHong Zhang #else 153632d0f97SHong Zhang int Nbs = baij->Nbs; 154632d0f97SHong Zhang #endif 155632d0f97SHong Zhang 156632d0f97SHong Zhang PetscFunctionBegin; 157632d0f97SHong Zhang /* printf(" ... MatExpandIndices_MPISBAIJ is called ...\n"); */ 158632d0f97SHong Zhang #if defined (PETSC_USE_CTABLE) 159632d0f97SHong Zhang /* Now check max size */ 160632d0f97SHong Zhang for (i=0,maxsz=0; i<imax; i++) { 161632d0f97SHong Zhang ierr = ISGetIndices(is_in[i],&idx);CHKERRQ(ierr); 162632d0f97SHong Zhang ierr = ISGetLocalSize(is_in[i],&n);CHKERRQ(ierr); 163632d0f97SHong Zhang if (n*bs > maxsz) maxsz = n*bs; 164632d0f97SHong Zhang } 165632d0f97SHong Zhang ierr = PetscMalloc((maxsz+1)*sizeof(int),&nidx);CHKERRQ(ierr); 166632d0f97SHong Zhang #else 167632d0f97SHong Zhang ierr = PetscMalloc((Nbs*bs+1)*sizeof(int),&nidx);CHKERRQ(ierr); 168632d0f97SHong Zhang #endif 169632d0f97SHong Zhang 170632d0f97SHong Zhang for (i=0; i<imax; i++) { 171632d0f97SHong Zhang ierr = ISGetIndices(is_in[i],&idx);CHKERRQ(ierr); 172632d0f97SHong Zhang ierr = ISGetLocalSize(is_in[i],&n);CHKERRQ(ierr); 173632d0f97SHong Zhang for (j=0; j<n ; ++j){ 174632d0f97SHong Zhang for (k=0; k<bs; k++) 175632d0f97SHong Zhang nidx[j*bs+k] = idx[j]*bs+k; 176632d0f97SHong Zhang } 177632d0f97SHong Zhang ierr = ISRestoreIndices(is_in[i],&idx);CHKERRQ(ierr); 178632d0f97SHong Zhang ierr = ISCreateGeneral(PETSC_COMM_SELF,n*bs,nidx,is_out+i);CHKERRQ(ierr); 179632d0f97SHong Zhang } 180632d0f97SHong Zhang ierr = PetscFree(nidx);CHKERRQ(ierr); 181632d0f97SHong Zhang PetscFunctionReturn(0); 182632d0f97SHong Zhang } 183632d0f97SHong Zhang 184632d0f97SHong Zhang 185632d0f97SHong Zhang #undef __FUNCT__ 186632d0f97SHong Zhang #define __FUNCT__ "MatIncreaseOverlap_MPISBAIJ" 187c910923dSHong Zhang int MatIncreaseOverlap_MPISBAIJ(Mat C,int is_max,IS is[],int ov) 188632d0f97SHong Zhang { 189632d0f97SHong Zhang int i,ierr; 190632d0f97SHong Zhang IS *is_new; 191632d0f97SHong Zhang 192632d0f97SHong Zhang PetscFunctionBegin; 193c910923dSHong Zhang ierr = PetscMalloc(is_max*sizeof(IS),&is_new);CHKERRQ(ierr); 194632d0f97SHong Zhang /* Convert the indices into block format */ 195c910923dSHong Zhang ierr = MatCompressIndicesGeneral_MPISBAIJ(C,is_max,is,is_new);CHKERRQ(ierr); 196632d0f97SHong Zhang if (ov < 0){ SETERRQ(PETSC_ERR_ARG_OUTOFRANGE,"Negative overlap specified\n");} 197632d0f97SHong Zhang for (i=0; i<ov; ++i) { 198c910923dSHong Zhang ierr = MatIncreaseOverlap_MPISBAIJ_Once(C,is_max,is_new);CHKERRQ(ierr); 199632d0f97SHong Zhang } 200c910923dSHong Zhang for (i=0; i<is_max; i++) {ierr = ISDestroy(is[i]);CHKERRQ(ierr);} 201c910923dSHong Zhang ierr = MatExpandIndices_MPISBAIJ(C,is_max,is_new,is);CHKERRQ(ierr); 202c910923dSHong Zhang for (i=0; i<is_max; i++) {ierr = ISDestroy(is_new[i]);CHKERRQ(ierr);} 203632d0f97SHong Zhang ierr = PetscFree(is_new);CHKERRQ(ierr); 204632d0f97SHong Zhang PetscFunctionReturn(0); 205632d0f97SHong Zhang } 206632d0f97SHong Zhang 207632d0f97SHong Zhang #undef __FUNCT__ 208632d0f97SHong Zhang #define __FUNCT__ "MatIncreaseOverlap_MPISBAIJ_Once" 209c910923dSHong Zhang static int MatIncreaseOverlap_MPISBAIJ_Once(Mat C,int is_max,IS is[]) 210632d0f97SHong Zhang { 211632d0f97SHong Zhang Mat_MPISBAIJ *c = (Mat_MPISBAIJ*)C->data; 212632d0f97SHong Zhang int **idx,*n,len,*idx_i; 213*dc008846SHong Zhang int size,rank,Mbs,i,j,k,ierr,nrqs,msz,*outdat,*indat; 214*dc008846SHong Zhang int tag1,tag2,flag,proc_id; 215632d0f97SHong Zhang MPI_Comm comm; 216c910923dSHong Zhang MPI_Request *s_waits1,*s_waits2,r_req; 217632d0f97SHong Zhang MPI_Status *s_status,r_status; 218632d0f97SHong Zhang 219632d0f97SHong Zhang PetscFunctionBegin; 220632d0f97SHong Zhang 221632d0f97SHong Zhang comm = C->comm; 222632d0f97SHong Zhang size = c->size; 223632d0f97SHong Zhang rank = c->rank; 224632d0f97SHong Zhang Mbs = c->Mbs; 225632d0f97SHong Zhang 226632d0f97SHong Zhang /* 1. Send is[] to all other processors */ 227632d0f97SHong Zhang /*--------------------------------------*/ 228632d0f97SHong Zhang /* This processor sends its is[] to all other processors in the format: 229632d0f97SHong Zhang outdat[0] = is_max, no of is in this processor 230632d0f97SHong Zhang outdat[1] = n[0], size of is[0] 231632d0f97SHong Zhang ... 232632d0f97SHong Zhang outdat[is_max] = n[is_max-1], size of is[is_max-1] 233632d0f97SHong Zhang outdat[is_max + 1] = data(is[0]) 234632d0f97SHong Zhang ... 235*dc008846SHong Zhang outdat[is_max+1+sum(n[k]), k=0,...,i-1] = data(is[i]) 236632d0f97SHong Zhang ... 237632d0f97SHong Zhang */ 238c910923dSHong Zhang ierr = PetscObjectGetNewTag((PetscObject)C,&tag1);CHKERRQ(ierr); 239c910923dSHong Zhang ierr = PetscObjectGetNewTag((PetscObject)C,&tag2);CHKERRQ(ierr); 240c910923dSHong Zhang printf(" [%d] tags: %d, %d\n",rank,tag1,tag2); 241c910923dSHong Zhang 242c910923dSHong Zhang len = (is_max+1)*sizeof(int*)+ (is_max)*sizeof(int); 243632d0f97SHong Zhang ierr = PetscMalloc(len,&idx);CHKERRQ(ierr); 244c910923dSHong Zhang n = (int*)(idx + is_max); 245632d0f97SHong Zhang 246632d0f97SHong Zhang /* Allocate Memory for outgoing messages */ 247c910923dSHong Zhang len = 1 + is_max; 248c910923dSHong Zhang for (i=0; i<is_max; i++) { 249632d0f97SHong Zhang ierr = ISGetIndices(is[i],&idx[i]);CHKERRQ(ierr); 250632d0f97SHong Zhang ierr = ISGetLocalSize(is[i],&n[i]);CHKERRQ(ierr); 251632d0f97SHong Zhang len += n[i]; 252632d0f97SHong Zhang } 253632d0f97SHong Zhang ierr = PetscMalloc(len*sizeof(int),&outdat);CHKERRQ(ierr); 254632d0f97SHong Zhang 255632d0f97SHong Zhang /* Form the outgoing messages */ 256c910923dSHong Zhang outdat[0] = is_max; 257c910923dSHong Zhang for (i=0; i<is_max; i++) { 258632d0f97SHong Zhang outdat[i+1] = n[i]; 259632d0f97SHong Zhang } 260c910923dSHong Zhang k = is_max + 1; 261c910923dSHong Zhang for (i=0; i<is_max; i++) { /* for is[i] */ 262632d0f97SHong Zhang idx_i = idx[i]; 263632d0f97SHong Zhang for (j=0; j<n[i]; j++){ 264632d0f97SHong Zhang outdat[k] = *(idx_i); 265632d0f97SHong Zhang /* if (!rank) printf(" outdat[%d] = %d\n",k,outdat[k] ); */ 266632d0f97SHong Zhang k++; idx_i++; 267632d0f97SHong Zhang } 268632d0f97SHong Zhang /* printf(" [%d] n[%d]=%d, k: %d, \n",rank,i,n[i],k); */ 269632d0f97SHong Zhang } 270632d0f97SHong Zhang if (k != len) SETERRQ3(1,"[%d] Error on forming the outgoing messages: k %d != len %d",rank,k,len); 271632d0f97SHong Zhang 272632d0f97SHong Zhang /* Now post the sends */ 273632d0f97SHong Zhang ierr = PetscMalloc(size*sizeof(MPI_Request),&s_waits1);CHKERRQ(ierr); 274632d0f97SHong Zhang 275632d0f97SHong Zhang k = 0; 276c910923dSHong Zhang for (proc_id=0; proc_id<size; ++proc_id) { /* send outdat to processor [proc_id] */ 277c910923dSHong Zhang if (proc_id != rank){ 278c910923dSHong Zhang ierr = MPI_Isend(outdat,len,MPI_INT,proc_id,tag1,comm,s_waits1+k);CHKERRQ(ierr); 279c910923dSHong Zhang printf(" [%d] send %d msg to [%d] \n",rank,len,proc_id); 280632d0f97SHong Zhang k++; 281632d0f97SHong Zhang } 282632d0f97SHong Zhang } 283632d0f97SHong Zhang 284*dc008846SHong Zhang /* 2. Do local work on this processor's is[] */ 285*dc008846SHong Zhang /*-------------------------------------------*/ 286*dc008846SHong Zhang int *nidx,*nidx_i; 287*dc008846SHong Zhang ierr = MatIncreaseOverlap_MPISBAIJ_Local(C,outdat,&nidx);CHKERRQ(ierr); 288632d0f97SHong Zhang 289*dc008846SHong Zhang for (i=0; i<is_max; i++){ 290c910923dSHong Zhang ierr = ISRestoreIndices(is[i],idx+i);CHKERRQ(ierr); 291c910923dSHong Zhang ierr = ISDestroy(is[i]);CHKERRQ(ierr); 292*dc008846SHong Zhang } 293632d0f97SHong Zhang 294632d0f97SHong Zhang /* 3. Receive other's is[] and process. Then send back */ 295632d0f97SHong Zhang /*----------------------------------------------------*/ 296632d0f97SHong Zhang /* Send is done */ 297632d0f97SHong Zhang nrqs = size-1; 298632d0f97SHong Zhang ierr = PetscMalloc(size*sizeof(MPI_Status),&s_status);CHKERRQ(ierr); 299632d0f97SHong Zhang ierr = MPI_Waitall(nrqs,s_waits1,s_status);CHKERRQ(ierr); 300*dc008846SHong Zhang 301*dc008846SHong Zhang /* save n[i] */ 302*dc008846SHong Zhang for (i=0; i<is_max; i++){ 303*dc008846SHong Zhang n[i] = outdat[1+i]; 304*dc008846SHong Zhang } 305632d0f97SHong Zhang ierr = PetscFree(outdat);CHKERRQ(ierr); 306632d0f97SHong Zhang ierr = PetscMalloc(size*sizeof(MPI_Request),&s_waits2);CHKERRQ(ierr); 307632d0f97SHong Zhang k = 0; 308632d0f97SHong Zhang do { 309632d0f97SHong Zhang /* Receive messages */ 310c910923dSHong Zhang ierr = MPI_Iprobe(MPI_ANY_SOURCE,tag1,comm,&flag,&r_status); 311632d0f97SHong Zhang if (flag){ 312632d0f97SHong Zhang ierr = MPI_Get_count(&r_status,MPI_INT,&len); 313632d0f97SHong Zhang proc_id = r_status.MPI_SOURCE; 314c910923dSHong Zhang ierr = PetscMalloc(len*sizeof(int),&indat);CHKERRQ(ierr); 315c910923dSHong Zhang ierr = MPI_Irecv(indat,len,MPI_INT,proc_id,r_status.MPI_TAG,comm,&r_req); 316632d0f97SHong Zhang printf(" [%d] recv %d msg from [%d]\n",rank,len,proc_id); 317632d0f97SHong Zhang 318632d0f97SHong Zhang /* Process messages -- not done yet */ 319632d0f97SHong Zhang len = indat[0]; 320632d0f97SHong Zhang ierr = PetscMalloc(len*sizeof(int),&outdat);CHKERRQ(ierr); 321632d0f97SHong Zhang for (i=0; i<len; i++){outdat[i] = indat[i+1];} 322632d0f97SHong Zhang 323632d0f97SHong Zhang /* Send messages back */ 324632d0f97SHong Zhang printf(" [%d] send %d msg back to [%d] \n",rank,len,proc_id); 325c910923dSHong Zhang ierr = MPI_Isend(outdat,len,MPI_INT,proc_id,tag2,comm,&s_waits2[k]);CHKERRQ(ierr); 326632d0f97SHong Zhang 327632d0f97SHong Zhang k++; 328632d0f97SHong Zhang ierr = PetscFree(outdat);CHKERRQ(ierr); 329632d0f97SHong Zhang ierr = PetscFree(indat);CHKERRQ(ierr); 330632d0f97SHong Zhang } 331632d0f97SHong Zhang } while (k < nrqs); 332632d0f97SHong Zhang 333632d0f97SHong Zhang /* 4. Receive work done on other processors, then process */ 334632d0f97SHong Zhang /*--------------------------------------------------------*/ 335632d0f97SHong Zhang ierr = MPI_Waitall(nrqs,s_waits2,s_status);CHKERRQ(ierr); 336632d0f97SHong Zhang k = 0; 337632d0f97SHong Zhang do { 338632d0f97SHong Zhang /* Receive messages */ 339c910923dSHong Zhang ierr = MPI_Iprobe(MPI_ANY_SOURCE,tag2,comm,&flag,&r_status); 340632d0f97SHong Zhang if (flag){ 341632d0f97SHong Zhang ierr = MPI_Get_count(&r_status,MPI_INT,&len); 342632d0f97SHong Zhang proc_id = r_status.MPI_SOURCE; 343632d0f97SHong Zhang ierr = ierr = PetscMalloc(len*sizeof(int),&indat);CHKERRQ(ierr); 344c910923dSHong Zhang ierr = MPI_Irecv(indat,len,MPI_INT,proc_id,r_status.MPI_TAG,comm,&r_req); 345632d0f97SHong Zhang printf(" [%d] recv %d msg from [%d]\n",rank,len,proc_id); 346632d0f97SHong Zhang 347632d0f97SHong Zhang /* Process messages -- not done yet */ 348632d0f97SHong Zhang 349632d0f97SHong Zhang 350632d0f97SHong Zhang k++; 351632d0f97SHong Zhang ierr = PetscFree(indat);CHKERRQ(ierr); 352632d0f97SHong Zhang } 353632d0f97SHong Zhang } while (k < nrqs); 354632d0f97SHong Zhang 355c910923dSHong Zhang /* 5. Create new is[] */ 356c910923dSHong Zhang /*--------------------*/ 357c910923dSHong Zhang for (i=0; i<is_max; i++) { 358c910923dSHong Zhang nidx_i = nidx+i*Mbs; 359c910923dSHong Zhang ierr = ISCreateGeneral(PETSC_COMM_SELF,n[i],nidx_i,is+i);CHKERRQ(ierr); 360632d0f97SHong Zhang } 361c910923dSHong Zhang ierr = PetscFree(nidx);CHKERRQ(ierr); 362c910923dSHong Zhang ierr = PetscFree(idx);CHKERRQ(ierr); 363632d0f97SHong Zhang ierr = PetscFree(s_waits1);CHKERRQ(ierr); 364632d0f97SHong Zhang ierr = PetscFree(s_waits2);CHKERRQ(ierr); 365632d0f97SHong Zhang ierr = PetscFree(s_status);CHKERRQ(ierr); 366632d0f97SHong Zhang PetscFunctionReturn(0); 367632d0f97SHong Zhang } 368632d0f97SHong Zhang 369632d0f97SHong Zhang #undef __FUNCT__ 370632d0f97SHong Zhang #define __FUNCT__ "MatIncreaseOverlap_MPISBAIJ_Local" 371632d0f97SHong Zhang /* 372*dc008846SHong Zhang MatIncreaseOverlap_MPISBAIJ_Local - Called by MatIncreaseOverlap, to do 373632d0f97SHong Zhang the work on the local processor. 374632d0f97SHong Zhang 375632d0f97SHong Zhang Inputs: 376632d0f97SHong Zhang C - MAT_MPISBAIJ; 377*dc008846SHong Zhang data - holds is[] in the format: 378*dc008846SHong Zhang data[0] = is_max, no of is 379*dc008846SHong Zhang data[1] = size of is[0] 380*dc008846SHong Zhang ... 381*dc008846SHong Zhang data[is_max] = size of is[is_max-1] 382*dc008846SHong Zhang data[is_max + 1] = is[0] array 383*dc008846SHong Zhang ... 384*dc008846SHong Zhang data[is_max+1+sum(n[k]), k=0,...,i-1] = is[i] array 385*dc008846SHong Zhang ... 386632d0f97SHong Zhang 387632d0f97SHong Zhang Output: 388*dc008846SHong Zhang data_new - holds new is[] in the same format as data 389632d0f97SHong Zhang */ 390*dc008846SHong Zhang static int MatIncreaseOverlap_MPISBAIJ_Local(Mat C,int *data,int **data_new) 391632d0f97SHong Zhang { 392632d0f97SHong Zhang Mat_MPISBAIJ *c = (Mat_MPISBAIJ*)C->data; 393*dc008846SHong Zhang Mat_SeqSBAIJ *a = (Mat_SeqSBAIJ*)(c->A)->data; 394*dc008846SHong Zhang Mat_SeqBAIJ *b = (Mat_SeqBAIJ*)(c->B)->data; 395*dc008846SHong Zhang int ierr,row,mbs,Mbs,*nidx,*nidx_i,col,isz,isz0,*ai,*aj,bs,*bi,*bj,*garray,rstart,l; 396*dc008846SHong Zhang int a_start,a_end,b_start,b_end,i,j,k,is_max,*idx_i,n; 397*dc008846SHong Zhang PetscBT table; 398*dc008846SHong Zhang PetscBT table0; 399632d0f97SHong Zhang 400632d0f97SHong Zhang PetscFunctionBegin; 401*dc008846SHong Zhang Mbs = c->Mbs; mbs = a->mbs; bs = a->bs; 402*dc008846SHong Zhang ai = a->i; aj = a->j; 403*dc008846SHong Zhang bi = b->i; bj = b->j; 404632d0f97SHong Zhang garray = c->garray; 405*dc008846SHong Zhang rstart = c->rstart; 406*dc008846SHong Zhang is_max = data[0]; 407632d0f97SHong Zhang 408*dc008846SHong Zhang ierr = PetscMalloc(is_max*Mbs*sizeof(int),&nidx);CHKERRQ(ierr); 409*dc008846SHong Zhang ierr = PetscBTCreate(Mbs,table0);CHKERRQ(ierr); 410*dc008846SHong Zhang ierr = PetscBTCreate(Mbs,table);CHKERRQ(ierr); 411632d0f97SHong Zhang 412*dc008846SHong Zhang idx_i = data + is_max + 1; /* ptr to is[0] array */ 413*dc008846SHong Zhang for (i=0; i<is_max; i++) { /* for each is */ 414*dc008846SHong Zhang isz = 0; 415*dc008846SHong Zhang ierr = PetscBTMemzero(Mbs,table);CHKERRQ(ierr); 416*dc008846SHong Zhang nidx_i = nidx+i*Mbs; /* holds new is[i] array */ 417*dc008846SHong Zhang n = data[1+i]; /* size of is[i] */ 418*dc008846SHong Zhang 419*dc008846SHong Zhang /* Enter these into the temp arrays i.e mark table[row], enter row into new index */ 420*dc008846SHong Zhang for (j=0; j<n; j++){ 421*dc008846SHong Zhang col = idx_i[j]; 422*dc008846SHong Zhang if (col >= Mbs) SETERRQ2(PETSC_ERR_ARG_OUTOFRANGE,"index col %d >= Mbs %d",col,Mbs); 423*dc008846SHong Zhang if(!PetscBTLookupSet(table,col)) { nidx_i[isz++] = col;} 424632d0f97SHong Zhang } 425*dc008846SHong Zhang 426*dc008846SHong Zhang k = 0; 427*dc008846SHong Zhang /* set table0 for lookup */ 428*dc008846SHong Zhang ierr = PetscBTMemzero(mbs,table0);CHKERRQ(ierr); 429*dc008846SHong Zhang for (l=k; l<isz; l++) PetscBTSet(table0,nidx_i[l]); 430*dc008846SHong Zhang 431*dc008846SHong Zhang isz0 = isz; /* length of nidx_i[] before updating */ 432*dc008846SHong Zhang for (row=0; row<mbs; row++){ 433*dc008846SHong Zhang a_start = ai[row]; a_end = ai[row+1]; 434*dc008846SHong Zhang b_start = bi[row]; b_end = bi[row+1]; 435*dc008846SHong Zhang if (PetscBTLookup(table0,row+rstart)){ /* row is on nidx_i - row search: collect all col in this row */ 436*dc008846SHong Zhang /* printf(" [%d] is[%d] row %d is on nidx_i\n",rank,i,row+rstart); */ 437*dc008846SHong Zhang for (l = a_start; l<a_end ; l++){ /* Amat */ 438*dc008846SHong Zhang col = aj[l] + rstart; 439*dc008846SHong Zhang if (!PetscBTLookupSet(table,col)) {nidx_i[isz++] = col;} 440*dc008846SHong Zhang } 441*dc008846SHong Zhang for (l = b_start; l<b_end ; l++){ /* Bmat */ 442*dc008846SHong Zhang col = garray[bj[l]]; 443*dc008846SHong Zhang if (!PetscBTLookupSet(table,col)) {nidx_i[isz++] = col;} 444*dc008846SHong Zhang } 445*dc008846SHong Zhang k++; 446*dc008846SHong Zhang if (k >= isz0) break; /* for (row=0; row<mbs; row++) */ 447*dc008846SHong Zhang } else { /* row is not on nidx_i - col serach: add row onto nidx_i if there is a col in nidx_i */ 448*dc008846SHong Zhang for (l = a_start; l<a_end ; l++){ /* Amat */ 449*dc008846SHong Zhang col = aj[l] + rstart; 450*dc008846SHong Zhang if (PetscBTLookup(table0,col)){ 451*dc008846SHong Zhang if (!PetscBTLookupSet(table,row+rstart)) {nidx_i[isz++] = row+rstart;} 452*dc008846SHong Zhang break; /* for l = start; l<end ; l++) */ 453632d0f97SHong Zhang } 454632d0f97SHong Zhang } 455*dc008846SHong Zhang for (l = b_start; l<b_end ; l++){ /* Bmat */ 456*dc008846SHong Zhang col = garray[bj[l]]; 457*dc008846SHong Zhang if (PetscBTLookup(table0,col)){ 458*dc008846SHong Zhang if (!PetscBTLookupSet(table,row+rstart)) {nidx_i[isz++] = row+rstart;} 459*dc008846SHong Zhang break; /* for l = start; l<end ; l++) */ 460632d0f97SHong Zhang } 461*dc008846SHong Zhang } 462*dc008846SHong Zhang } 463*dc008846SHong Zhang } /* for (row=0; row<mbs; row++) */ 464*dc008846SHong Zhang 465*dc008846SHong Zhang if (i < is_max - 1){ 466*dc008846SHong Zhang idx_i += n; /* ptr to is[i+1] array */ 467*dc008846SHong Zhang } 468*dc008846SHong Zhang data[1+i] = isz; 469*dc008846SHong Zhang } /* /* for each is */ 470*dc008846SHong Zhang *data_new = nidx; 471*dc008846SHong Zhang ierr = PetscBTDestroy(table);CHKERRQ(ierr); 472*dc008846SHong Zhang ierr = PetscBTDestroy(table0);CHKERRQ(ierr); 473632d0f97SHong Zhang PetscFunctionReturn(0); 474632d0f97SHong Zhang } 475632d0f97SHong Zhang #undef __FUNCT__ 476632d0f97SHong Zhang #define __FUNCT__ "MatIncreaseOverlap_MPISBAIJ_Receive" 477632d0f97SHong Zhang /* 478632d0f97SHong Zhang MatIncreaseOverlap_MPISBAIJ_Receive - Process the recieved messages, 479632d0f97SHong Zhang and return the output 480632d0f97SHong Zhang 481632d0f97SHong Zhang Input: 482632d0f97SHong Zhang C - the matrix 483632d0f97SHong Zhang nrqr - no of messages being processed. 484632d0f97SHong Zhang rbuf - an array of pointers to the recieved requests 485632d0f97SHong Zhang 486632d0f97SHong Zhang Output: 487632d0f97SHong Zhang xdata - array of messages to be sent back 488632d0f97SHong Zhang isz1 - size of each message 489632d0f97SHong Zhang 490632d0f97SHong Zhang For better efficiency perhaps we should malloc seperately each xdata[i], 491632d0f97SHong Zhang then if a remalloc is required we need only copy the data for that one row 492632d0f97SHong Zhang rather then all previous rows as it is now where a single large chunck of 493632d0f97SHong Zhang memory is used. 494632d0f97SHong Zhang 495632d0f97SHong Zhang */ 496632d0f97SHong Zhang static int MatIncreaseOverlap_MPISBAIJ_Receive(Mat C,int nrqr,int **rbuf,int **xdata,int * isz1) 497632d0f97SHong Zhang { 498632d0f97SHong Zhang Mat_MPISBAIJ *c = (Mat_MPISBAIJ*)C->data; 499632d0f97SHong Zhang Mat A = c->A,B = c->B; 500632d0f97SHong Zhang Mat_SeqSBAIJ *a = (Mat_SeqSBAIJ*)A->data; 501632d0f97SHong Zhang Mat_SeqBAIJ *b = (Mat_SeqBAIJ*)B->data; 502632d0f97SHong Zhang int rstart,cstart,*ai,*aj,*bi,*bj,*garray,i,j,k; 503632d0f97SHong Zhang int row,total_sz,ct,ct1,ct2,ct3,mem_estimate,oct2,l,start,end; 504632d0f97SHong Zhang int val,max1,max2,rank,Mbs,no_malloc =0,*tmp,new_estimate,ctr; 505632d0f97SHong Zhang int *rbuf_i,kmax,rbuf_0,ierr; 506632d0f97SHong Zhang PetscBT xtable; 507632d0f97SHong Zhang 508632d0f97SHong Zhang PetscFunctionBegin; 509632d0f97SHong Zhang rank = c->rank; 510632d0f97SHong Zhang Mbs = c->Mbs; 511632d0f97SHong Zhang rstart = c->rstart; 512632d0f97SHong Zhang cstart = c->cstart; 513632d0f97SHong Zhang ai = a->i; 514632d0f97SHong Zhang aj = a->j; 515632d0f97SHong Zhang bi = b->i; 516632d0f97SHong Zhang bj = b->j; 517632d0f97SHong Zhang garray = c->garray; 518632d0f97SHong Zhang 519632d0f97SHong Zhang 520632d0f97SHong Zhang for (i=0,ct=0,total_sz=0; i<nrqr; ++i) { 521632d0f97SHong Zhang rbuf_i = rbuf[i]; 522632d0f97SHong Zhang rbuf_0 = rbuf_i[0]; 523632d0f97SHong Zhang ct += rbuf_0; 524632d0f97SHong Zhang for (j=1; j<=rbuf_0; j++) { total_sz += rbuf_i[2*j]; } 525632d0f97SHong Zhang } 526632d0f97SHong Zhang 527632d0f97SHong Zhang if (c->Mbs) max1 = ct*(a->nz +b->nz)/c->Mbs; 528632d0f97SHong Zhang else max1 = 1; 529632d0f97SHong Zhang mem_estimate = 3*((total_sz > max1 ? total_sz : max1)+1); 530632d0f97SHong Zhang ierr = PetscMalloc(mem_estimate*sizeof(int),&xdata[0]);CHKERRQ(ierr); 531632d0f97SHong Zhang ++no_malloc; 532632d0f97SHong Zhang ierr = PetscBTCreate(Mbs,xtable);CHKERRQ(ierr); 533632d0f97SHong Zhang ierr = PetscMemzero(isz1,nrqr*sizeof(int));CHKERRQ(ierr); 534632d0f97SHong Zhang 535632d0f97SHong Zhang ct3 = 0; 536632d0f97SHong Zhang for (i=0; i<nrqr; i++) { /* for easch mesg from proc i */ 537632d0f97SHong Zhang rbuf_i = rbuf[i]; 538632d0f97SHong Zhang rbuf_0 = rbuf_i[0]; 539632d0f97SHong Zhang ct1 = 2*rbuf_0+1; 540632d0f97SHong Zhang ct2 = ct1; 541632d0f97SHong Zhang ct3 += ct1; 542632d0f97SHong Zhang for (j=1; j<=rbuf_0; j++) { /* for each IS from proc i*/ 543632d0f97SHong Zhang ierr = PetscBTMemzero(Mbs,xtable);CHKERRQ(ierr); 544632d0f97SHong Zhang oct2 = ct2; 545632d0f97SHong Zhang kmax = rbuf_i[2*j]; 546632d0f97SHong Zhang for (k=0; k<kmax; k++,ct1++) { 547632d0f97SHong Zhang row = rbuf_i[ct1]; 548632d0f97SHong Zhang if (!PetscBTLookupSet(xtable,row)) { 549632d0f97SHong Zhang if (!(ct3 < mem_estimate)) { 550632d0f97SHong Zhang new_estimate = (int)(1.5*mem_estimate)+1; 551632d0f97SHong Zhang ierr = PetscMalloc(new_estimate * sizeof(int),&tmp);CHKERRQ(ierr); 552632d0f97SHong Zhang ierr = PetscMemcpy(tmp,xdata[0],mem_estimate*sizeof(int));CHKERRQ(ierr); 553632d0f97SHong Zhang ierr = PetscFree(xdata[0]);CHKERRQ(ierr); 554632d0f97SHong Zhang xdata[0] = tmp; 555632d0f97SHong Zhang mem_estimate = new_estimate; ++no_malloc; 556632d0f97SHong Zhang for (ctr=1; ctr<=i; ctr++) { xdata[ctr] = xdata[ctr-1] + isz1[ctr-1];} 557632d0f97SHong Zhang } 558632d0f97SHong Zhang xdata[i][ct2++] = row; 559632d0f97SHong Zhang ct3++; 560632d0f97SHong Zhang } 561632d0f97SHong Zhang } 562632d0f97SHong Zhang for (k=oct2,max2=ct2; k<max2; k++) { 563632d0f97SHong Zhang row = xdata[i][k] - rstart; 564632d0f97SHong Zhang start = ai[row]; 565632d0f97SHong Zhang end = ai[row+1]; 566632d0f97SHong Zhang for (l=start; l<end; l++) { 567632d0f97SHong Zhang val = aj[l] + cstart; 568632d0f97SHong Zhang if (!PetscBTLookupSet(xtable,val)) { 569632d0f97SHong Zhang if (!(ct3 < mem_estimate)) { 570632d0f97SHong Zhang new_estimate = (int)(1.5*mem_estimate)+1; 571632d0f97SHong Zhang ierr = PetscMalloc(new_estimate * sizeof(int),&tmp);CHKERRQ(ierr); 572632d0f97SHong Zhang ierr = PetscMemcpy(tmp,xdata[0],mem_estimate*sizeof(int));CHKERRQ(ierr); 573632d0f97SHong Zhang ierr = PetscFree(xdata[0]);CHKERRQ(ierr); 574632d0f97SHong Zhang xdata[0] = tmp; 575632d0f97SHong Zhang mem_estimate = new_estimate; ++no_malloc; 576632d0f97SHong Zhang for (ctr=1; ctr<=i; ctr++) { xdata[ctr] = xdata[ctr-1] + isz1[ctr-1];} 577632d0f97SHong Zhang } 578632d0f97SHong Zhang xdata[i][ct2++] = val; 579632d0f97SHong Zhang ct3++; 580632d0f97SHong Zhang } 581632d0f97SHong Zhang } 582632d0f97SHong Zhang start = bi[row]; 583632d0f97SHong Zhang end = bi[row+1]; 584632d0f97SHong Zhang for (l=start; l<end; l++) { 585632d0f97SHong Zhang val = garray[bj[l]]; 586632d0f97SHong Zhang if (!PetscBTLookupSet(xtable,val)) { 587632d0f97SHong Zhang if (!(ct3 < mem_estimate)) { 588632d0f97SHong Zhang new_estimate = (int)(1.5*mem_estimate)+1; 589632d0f97SHong Zhang ierr = PetscMalloc(new_estimate * sizeof(int),&tmp);CHKERRQ(ierr); 590632d0f97SHong Zhang ierr = PetscMemcpy(tmp,xdata[0],mem_estimate*sizeof(int));CHKERRQ(ierr); 591632d0f97SHong Zhang ierr = PetscFree(xdata[0]);CHKERRQ(ierr); 592632d0f97SHong Zhang xdata[0] = tmp; 593632d0f97SHong Zhang mem_estimate = new_estimate; ++no_malloc; 594632d0f97SHong Zhang for (ctr =1; ctr <=i; ctr++) { xdata[ctr] = xdata[ctr-1] + isz1[ctr-1];} 595632d0f97SHong Zhang } 596632d0f97SHong Zhang xdata[i][ct2++] = val; 597632d0f97SHong Zhang ct3++; 598632d0f97SHong Zhang } 599632d0f97SHong Zhang } 600632d0f97SHong Zhang } 601632d0f97SHong Zhang /* Update the header*/ 602632d0f97SHong Zhang xdata[i][2*j] = ct2 - oct2; /* Undo the vector isz1 and use only a var*/ 603632d0f97SHong Zhang xdata[i][2*j-1] = rbuf_i[2*j-1]; 604632d0f97SHong Zhang } 605632d0f97SHong Zhang xdata[i][0] = rbuf_0; 606632d0f97SHong Zhang xdata[i+1] = xdata[i] + ct2; 607632d0f97SHong Zhang isz1[i] = ct2; /* size of each message */ 608632d0f97SHong Zhang } 609632d0f97SHong Zhang ierr = PetscBTDestroy(xtable);CHKERRQ(ierr); 610632d0f97SHong Zhang PetscLogInfo(0,"MatIncreaseOverlap_MPISBAIJ:[%d] Allocated %d bytes, required %d, no of mallocs = %d\n",rank,mem_estimate,ct3,no_malloc); 611632d0f97SHong Zhang PetscFunctionReturn(0); 612632d0f97SHong Zhang } 613632d0f97SHong Zhang 614632d0f97SHong Zhang 615