1 2 /* 3 This file defines the initialization of PETSc, including PetscInitialize() 4 */ 5 #define PETSC_DESIRE_COMPLEX 6 #include <petsc-private/petscimpl.h> /*I "petscsys.h" I*/ 7 #include <petscviewer.h> 8 9 #if defined(PETSC_HAVE_CUDA) 10 #include <cublas.h> 11 #endif 12 13 #include <petscthreadcomm.h> 14 15 #if defined(PETSC_USE_LOG) 16 extern PetscErrorCode PetscLogBegin_Private(void); 17 #endif 18 extern PetscBool PetscHMPIWorker; 19 20 #if defined(PETSC_SERIALIZE_FUNCTIONS) 21 PetscFPT PetscFPTData = 0; 22 #endif 23 24 #if defined(PETSC_HAVE_SAWS) 25 #include <petscviewersaws.h> 26 #endif 27 /* -----------------------------------------------------------------------------------------*/ 28 29 extern FILE *petsc_history; 30 31 extern PetscErrorCode PetscInitialize_DynamicLibraries(void); 32 extern PetscErrorCode PetscFinalize_DynamicLibraries(void); 33 extern PetscErrorCode PetscFunctionListPrintAll(void); 34 extern PetscErrorCode PetscSequentialPhaseBegin_Private(MPI_Comm,int); 35 extern PetscErrorCode PetscSequentialPhaseEnd_Private(MPI_Comm,int); 36 extern PetscErrorCode PetscCloseHistoryFile(FILE**); 37 38 /* user may set this BEFORE calling PetscInitialize() */ 39 MPI_Comm PETSC_COMM_WORLD = MPI_COMM_NULL; 40 41 PetscMPIInt Petsc_Counter_keyval = MPI_KEYVAL_INVALID; 42 PetscMPIInt Petsc_InnerComm_keyval = MPI_KEYVAL_INVALID; 43 PetscMPIInt Petsc_OuterComm_keyval = MPI_KEYVAL_INVALID; 44 45 /* 46 Declare and set all the string names of the PETSc enums 47 */ 48 const char *const PetscBools[] = {"FALSE","TRUE","PetscBool","PETSC_",0}; 49 const char *const PetscCopyModes[] = {"COPY_VALUES","OWN_POINTER","USE_POINTER","PetscCopyMode","PETSC_",0}; 50 const char *const PetscDataTypes[] = {"INT","DOUBLE","COMPLEX","LONG","SHORT","FLOAT", 51 "CHAR","LOGICAL","ENUM","BOOL","LONGDOUBLE","OBJECT","FUNCTION","PetscDataType","PETSC_",0}; 52 53 PetscBool PetscPreLoadingUsed = PETSC_FALSE; 54 PetscBool PetscPreLoadingOn = PETSC_FALSE; 55 56 /* 57 Checks the options database for initializations related to the 58 PETSc components 59 */ 60 #undef __FUNCT__ 61 #define __FUNCT__ "PetscOptionsCheckInitial_Components" 62 PetscErrorCode PetscOptionsCheckInitial_Components(void) 63 { 64 PetscBool flg1; 65 PetscErrorCode ierr; 66 67 PetscFunctionBegin; 68 ierr = PetscOptionsHasName(NULL,"-help",&flg1);CHKERRQ(ierr); 69 if (flg1) { 70 #if defined(PETSC_USE_LOG) 71 MPI_Comm comm = PETSC_COMM_WORLD; 72 ierr = (*PetscHelpPrintf)(comm,"------Additional PETSc component options--------\n");CHKERRQ(ierr); 73 ierr = (*PetscHelpPrintf)(comm," -log_summary_exclude: <vec,mat,pc.ksp,snes>\n");CHKERRQ(ierr); 74 ierr = (*PetscHelpPrintf)(comm," -info_exclude: <null,vec,mat,pc,ksp,snes,ts>\n");CHKERRQ(ierr); 75 ierr = (*PetscHelpPrintf)(comm,"-----------------------------------------------\n");CHKERRQ(ierr); 76 #endif 77 } 78 PetscFunctionReturn(0); 79 } 80 81 #undef __FUNCT__ 82 #define __FUNCT__ "PetscInitializeNoPointers" 83 /* 84 PetscInitializeNoPointers - Calls PetscInitialize() from C/C++ without the pointers to argc and args 85 86 Collective 87 88 Level: advanced 89 90 Notes: this is called only by the PETSc MATLAB and Julia interface. Even though it might start MPI it sets the flag to 91 indicate that it did NOT start MPI so that the PetscFinalize() does not end MPI, thus allowing PetscInitialize() to 92 be called multiple times from MATLAB and Julia without the problem of trying to initialize MPI more than once. 93 94 Turns off PETSc signal handling because that can interact with MATLAB's signal handling causing random crashes. 95 96 .seealso: PetscInitialize(), PetscInitializeFortran(), PetscInitializeNoArguments() 97 */ 98 PetscErrorCode PetscInitializeNoPointers(int argc,char **args,const char *filename,const char *help) 99 { 100 PetscErrorCode ierr; 101 int myargc = argc; 102 char **myargs = args; 103 104 PetscFunctionBegin; 105 ierr = PetscInitialize(&myargc,&myargs,filename,help);CHKERRQ(ierr); 106 ierr = PetscPopSignalHandler();CHKERRQ(ierr); 107 PetscBeganMPI = PETSC_FALSE; 108 PetscFunctionReturn(ierr); 109 } 110 111 #undef __FUNCT__ 112 #define __FUNCT__ "PetscGetPETSC_COMM_SELF" 113 /* 114 Used by MATLAB and Julia interface to get communicator 115 */ 116 PetscErrorCode PetscGetPETSC_COMM_SELF(MPI_Comm *comm) 117 { 118 PetscFunctionBegin; 119 *comm = PETSC_COMM_SELF; 120 PetscFunctionReturn(0); 121 } 122 123 #undef __FUNCT__ 124 #define __FUNCT__ "PetscInitializeNoArguments" 125 /*@C 126 PetscInitializeNoArguments - Calls PetscInitialize() from C/C++ without 127 the command line arguments. 128 129 Collective 130 131 Level: advanced 132 133 .seealso: PetscInitialize(), PetscInitializeFortran() 134 @*/ 135 PetscErrorCode PetscInitializeNoArguments(void) 136 { 137 PetscErrorCode ierr; 138 int argc = 0; 139 char **args = 0; 140 141 PetscFunctionBegin; 142 ierr = PetscInitialize(&argc,&args,NULL,NULL); 143 PetscFunctionReturn(ierr); 144 } 145 146 #undef __FUNCT__ 147 #define __FUNCT__ "PetscInitialized" 148 /*@ 149 PetscInitialized - Determine whether PETSc is initialized. 150 151 Level: beginner 152 153 .seealso: PetscInitialize(), PetscInitializeNoArguments(), PetscInitializeFortran() 154 @*/ 155 PetscErrorCode PetscInitialized(PetscBool *isInitialized) 156 { 157 *isInitialized = PetscInitializeCalled; 158 return 0; 159 } 160 161 #undef __FUNCT__ 162 #define __FUNCT__ "PetscFinalized" 163 /*@ 164 PetscFinalized - Determine whether PetscFinalize() has been called yet 165 166 Level: developer 167 168 .seealso: PetscInitialize(), PetscInitializeNoArguments(), PetscInitializeFortran() 169 @*/ 170 PetscErrorCode PetscFinalized(PetscBool *isFinalized) 171 { 172 *isFinalized = PetscFinalizeCalled; 173 return 0; 174 } 175 176 extern PetscErrorCode PetscOptionsCheckInitial_Private(void); 177 178 /* 179 This function is the MPI reduction operation used to compute the sum of the 180 first half of the datatype and the max of the second half. 181 */ 182 MPI_Op PetscMaxSum_Op = 0; 183 184 #undef __FUNCT__ 185 #define __FUNCT__ "PetscMaxSum_Local" 186 PETSC_EXTERN void MPIAPI PetscMaxSum_Local(void *in,void *out,int *cnt,MPI_Datatype *datatype) 187 { 188 PetscInt *xin = (PetscInt*)in,*xout = (PetscInt*)out,i,count = *cnt; 189 190 PetscFunctionBegin; 191 if (*datatype != MPIU_2INT) { 192 (*PetscErrorPrintf)("Can only handle MPIU_2INT data types"); 193 MPI_Abort(MPI_COMM_WORLD,1); 194 } 195 196 for (i=0; i<count; i++) { 197 xout[2*i] = PetscMax(xout[2*i],xin[2*i]); 198 xout[2*i+1] += xin[2*i+1]; 199 } 200 PetscFunctionReturnVoid(); 201 } 202 203 /* 204 Returns the max of the first entry owned by this processor and the 205 sum of the second entry. 206 207 The reason nprocs[2*i] contains lengths nprocs[2*i+1] contains flag of 1 if length is nonzero 208 is so that the PetscMaxSum_Op() can set TWO values, if we passed in only nprocs[i] with lengths 209 there would be no place to store the both needed results. 210 */ 211 #undef __FUNCT__ 212 #define __FUNCT__ "PetscMaxSum" 213 PetscErrorCode PetscMaxSum(MPI_Comm comm,const PetscInt nprocs[],PetscInt *max,PetscInt *sum) 214 { 215 PetscMPIInt size,rank; 216 struct {PetscInt max,sum;} *work; 217 PetscErrorCode ierr; 218 219 PetscFunctionBegin; 220 ierr = MPI_Comm_size(comm,&size);CHKERRQ(ierr); 221 ierr = MPI_Comm_rank(comm,&rank);CHKERRQ(ierr); 222 ierr = PetscMalloc(size*sizeof(*work),&work);CHKERRQ(ierr); 223 ierr = MPI_Allreduce((void*)nprocs,work,size,MPIU_2INT,PetscMaxSum_Op,comm);CHKERRQ(ierr); 224 *max = work[rank].max; 225 *sum = work[rank].sum; 226 ierr = PetscFree(work);CHKERRQ(ierr); 227 PetscFunctionReturn(0); 228 } 229 230 /* ----------------------------------------------------------------------------*/ 231 MPI_Op PetscADMax_Op = 0; 232 233 #undef __FUNCT__ 234 #define __FUNCT__ "PetscADMax_Local" 235 PETSC_EXTERN void MPIAPI PetscADMax_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 236 { 237 PetscScalar *xin = (PetscScalar*)in,*xout = (PetscScalar*)out; 238 PetscInt i,count = *cnt; 239 240 PetscFunctionBegin; 241 if (*datatype != MPIU_2SCALAR) { 242 (*PetscErrorPrintf)("Can only handle MPIU_2SCALAR data (i.e. double or complex) types"); 243 MPI_Abort(MPI_COMM_WORLD,1); 244 } 245 246 for (i=0; i<count; i++) { 247 if (PetscRealPart(xout[2*i]) < PetscRealPart(xin[2*i])) { 248 xout[2*i] = xin[2*i]; 249 xout[2*i+1] = xin[2*i+1]; 250 } 251 } 252 PetscFunctionReturnVoid(); 253 } 254 255 MPI_Op PetscADMin_Op = 0; 256 257 #undef __FUNCT__ 258 #define __FUNCT__ "PetscADMin_Local" 259 PETSC_EXTERN void MPIAPI PetscADMin_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 260 { 261 PetscScalar *xin = (PetscScalar*)in,*xout = (PetscScalar*)out; 262 PetscInt i,count = *cnt; 263 264 PetscFunctionBegin; 265 if (*datatype != MPIU_2SCALAR) { 266 (*PetscErrorPrintf)("Can only handle MPIU_2SCALAR data (i.e. double or complex) types"); 267 MPI_Abort(MPI_COMM_WORLD,1); 268 } 269 270 for (i=0; i<count; i++) { 271 if (PetscRealPart(xout[2*i]) > PetscRealPart(xin[2*i])) { 272 xout[2*i] = xin[2*i]; 273 xout[2*i+1] = xin[2*i+1]; 274 } 275 } 276 PetscFunctionReturnVoid(); 277 } 278 /* ---------------------------------------------------------------------------------------*/ 279 280 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128) 281 MPI_Op MPIU_SUM = 0; 282 283 #undef __FUNCT__ 284 #define __FUNCT__ "PetscSum_Local" 285 PETSC_EXTERN void PetscSum_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 286 { 287 PetscInt i,count = *cnt; 288 289 PetscFunctionBegin; 290 if (*datatype == MPIU_REAL) { 291 PetscReal *xin = (PetscReal*)in,*xout = (PetscReal*)out; 292 for (i=0; i<count; i++) xout[i] += xin[i]; 293 } 294 #if defined(PETSC_HAVE_COMPLEX) 295 else if (*datatype == MPIU_COMPLEX) { 296 PetscComplex *xin = (PetscComplex*)in,*xout = (PetscComplex*)out; 297 for (i=0; i<count; i++) xout[i] += xin[i]; 298 } 299 #endif 300 else { 301 (*PetscErrorPrintf)("Can only handle MPIU_REAL or MPIU_COMPLEX data types"); 302 MPI_Abort(MPI_COMM_WORLD,1); 303 } 304 PetscFunctionReturnVoid(); 305 } 306 #endif 307 308 #if defined(PETSC_USE_REAL___FLOAT128) 309 MPI_Op MPIU_MAX = 0; 310 MPI_Op MPIU_MIN = 0; 311 312 #undef __FUNCT__ 313 #define __FUNCT__ "PetscMax_Local" 314 PETSC_EXTERN void PetscMax_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 315 { 316 PetscInt i,count = *cnt; 317 318 PetscFunctionBegin; 319 if (*datatype == MPIU_REAL) { 320 PetscReal *xin = (PetscReal*)in,*xout = (PetscReal*)out; 321 for (i=0; i<count; i++) xout[i] = PetscMax(xout[i],xin[i]); 322 } 323 #if defined(PETSC_HAVE_COMPLEX) 324 else if (*datatype == MPIU_COMPLEX) { 325 PetscComplex *xin = (PetscComplex*)in,*xout = (PetscComplex*)out; 326 for (i=0; i<count; i++) { 327 xout[i] = PetscRealPartComplex(xout[i])<PetscRealPartComplex(xin[i]) ? xin[i] : xout[i]; 328 } 329 } 330 #endif 331 else { 332 (*PetscErrorPrintf)("Can only handle MPIU_REAL or MPIU_COMPLEX data types"); 333 MPI_Abort(MPI_COMM_WORLD,1); 334 } 335 PetscFunctionReturnVoid(); 336 } 337 338 #undef __FUNCT__ 339 #define __FUNCT__ "PetscMin_Local" 340 PETSC_EXTERN void PetscMin_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 341 { 342 PetscInt i,count = *cnt; 343 344 PetscFunctionBegin; 345 if (*datatype == MPIU_REAL) { 346 PetscReal *xin = (PetscReal*)in,*xout = (PetscReal*)out; 347 for (i=0; i<count; i++) xout[i] = PetscMin(xout[i],xin[i]); 348 } 349 #if defined(PETSC_HAVE_COMPLEX) 350 else if (*datatype == MPIU_COMPLEX) { 351 PetscComplex *xin = (PetscComplex*)in,*xout = (PetscComplex*)out; 352 for (i=0; i<count; i++) { 353 xout[i] = PetscRealPartComplex(xout[i])>PetscRealPartComplex(xin[i]) ? xin[i] : xout[i]; 354 } 355 } 356 #endif 357 else { 358 (*PetscErrorPrintf)("Can only handle MPIU_REAL or MPIU_SCALAR data (i.e. double or complex) types"); 359 MPI_Abort(MPI_COMM_WORLD,1); 360 } 361 PetscFunctionReturnVoid(); 362 } 363 #endif 364 365 #undef __FUNCT__ 366 #define __FUNCT__ "Petsc_DelCounter" 367 /* 368 Private routine to delete internal tag/name counter storage when a communicator is freed. 369 370 This is called by MPI, not by users. This is called by MPI_Comm_free() when the communicator that has this data as an attribute is freed. 371 372 Note: this is declared extern "C" because it is passed to MPI_Keyval_create() 373 374 */ 375 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_DelCounter(MPI_Comm comm,PetscMPIInt keyval,void *count_val,void *extra_state) 376 { 377 PetscErrorCode ierr; 378 379 PetscFunctionBegin; 380 ierr = PetscInfo1(0,"Deleting counter data in an MPI_Comm %ld\n",(long)comm);if (ierr) PetscFunctionReturn((PetscMPIInt)ierr); 381 ierr = PetscFree(count_val);if (ierr) PetscFunctionReturn((PetscMPIInt)ierr); 382 PetscFunctionReturn(MPI_SUCCESS); 383 } 384 385 #undef __FUNCT__ 386 #define __FUNCT__ "Petsc_DelComm_Outer" 387 /* 388 This is invoked on the outer comm as a result of either PetscCommDestroy() (via MPI_Attr_delete) or when the user 389 calls MPI_Comm_free(). 390 391 This is the only entry point for breaking the links between inner and outer comms. 392 393 This is called by MPI, not by users. This is called when MPI_Comm_free() is called on the communicator. 394 395 Note: this is declared extern "C" because it is passed to MPI_Keyval_create() 396 397 */ 398 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_DelComm_Outer(MPI_Comm comm,PetscMPIInt keyval,void *attr_val,void *extra_state) 399 { 400 PetscErrorCode ierr; 401 PetscMPIInt flg; 402 union {MPI_Comm comm; void *ptr;} icomm,ocomm; 403 404 PetscFunctionBegin; 405 if (keyval != Petsc_InnerComm_keyval) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Unexpected keyval"); 406 icomm.ptr = attr_val; 407 408 ierr = MPI_Attr_get(icomm.comm,Petsc_OuterComm_keyval,&ocomm,&flg);CHKERRQ(ierr); 409 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected reference to outer comm"); 410 if (ocomm.comm != comm) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm has reference to non-matching outer comm"); 411 ierr = MPI_Attr_delete(icomm.comm,Petsc_OuterComm_keyval);CHKERRQ(ierr); /* Calls Petsc_DelComm_Inner */ 412 ierr = PetscInfo1(0,"User MPI_Comm %ld is being freed after removing reference from inner PETSc comm to this outer comm\n",(long)comm);if (ierr) PetscFunctionReturn((PetscMPIInt)ierr); 413 PetscFunctionReturn(MPI_SUCCESS); 414 } 415 416 #undef __FUNCT__ 417 #define __FUNCT__ "Petsc_DelComm_Inner" 418 /* 419 * This is invoked on the inner comm when Petsc_DelComm_Outer calls MPI_Attr_delete. It should not be reached any other way. 420 */ 421 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_DelComm_Inner(MPI_Comm comm,PetscMPIInt keyval,void *attr_val,void *extra_state) 422 { 423 PetscErrorCode ierr; 424 425 PetscFunctionBegin; 426 ierr = PetscInfo1(0,"Removing reference to PETSc communicator embedded in a user MPI_Comm %ld\n",(long)comm);if (ierr) PetscFunctionReturn((PetscMPIInt)ierr); 427 PetscFunctionReturn(MPI_SUCCESS); 428 } 429 430 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32) 431 #if !defined(PETSC_WORDS_BIGENDIAN) 432 PETSC_EXTERN PetscMPIInt PetscDataRep_extent_fn(MPI_Datatype,MPI_Aint*,void*); 433 PETSC_EXTERN PetscMPIInt PetscDataRep_read_conv_fn(void*, MPI_Datatype,PetscMPIInt,void*,MPI_Offset,void*); 434 PETSC_EXTERN PetscMPIInt PetscDataRep_write_conv_fn(void*, MPI_Datatype,PetscMPIInt,void*,MPI_Offset,void*); 435 #endif 436 #endif 437 438 int PetscGlobalArgc = 0; 439 char **PetscGlobalArgs = 0; 440 PetscSegBuffer PetscCitationsList; 441 442 #undef __FUNCT__ 443 #define __FUNCT__ "PetscCitationsInitialize" 444 PetscErrorCode PetscCitationsInitialize() 445 { 446 PetscErrorCode ierr; 447 448 PetscFunctionBegin; 449 ierr = PetscSegBufferCreate(1,10000,&PetscCitationsList);CHKERRQ(ierr); 450 ierr = PetscCitationsRegister("@TechReport{petsc-user-ref,\n Author = {Satish Balay and Jed Brown and and Kris Buschelman and Victor Eijkhout\n and William D. Gropp and Dinesh Kaushik and Matthew G. Knepley\n and Lois Curfman McInnes and Barry F. Smith and Hong Zhang},\n Title = {{PETS}c Users Manual},\n Number = {ANL-95/11 - Revision 3.4},\n Institution = {Argonne National Laboratory},\n Year = {2013}\n}\n",NULL);CHKERRQ(ierr); 451 ierr = PetscCitationsRegister("@InProceedings{petsc-efficient,\n Author = {Satish Balay and William D. Gropp and Lois Curfman McInnes and Barry F. Smith},\n Title = {Efficient Management of Parallelism in Object Oriented Numerical Software Libraries},\n Booktitle = {Modern Software Tools in Scientific Computing},\n Editor = {E. Arge and A. M. Bruaset and H. P. Langtangen},\n Pages = {163--202},\n Publisher = {Birkh{\\\"{a}}user Press},\n Year = {1997}\n}\n",NULL);CHKERRQ(ierr); 452 PetscFunctionReturn(0); 453 } 454 455 #undef __FUNCT__ 456 #define __FUNCT__ "PetscGetArgs" 457 /*@C 458 PetscGetArgs - Allows you to access the raw command line arguments anywhere 459 after PetscInitialize() is called but before PetscFinalize(). 460 461 Not Collective 462 463 Output Parameters: 464 + argc - count of number of command line arguments 465 - args - the command line arguments 466 467 Level: intermediate 468 469 Notes: 470 This is usually used to pass the command line arguments into other libraries 471 that are called internally deep in PETSc or the application. 472 473 The first argument contains the program name as is normal for C arguments. 474 475 Concepts: command line arguments 476 477 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArguments() 478 479 @*/ 480 PetscErrorCode PetscGetArgs(int *argc,char ***args) 481 { 482 PetscFunctionBegin; 483 if (!PetscInitializeCalled && PetscFinalizeCalled) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ORDER,"You must call after PetscInitialize() but before PetscFinalize()"); 484 *argc = PetscGlobalArgc; 485 *args = PetscGlobalArgs; 486 PetscFunctionReturn(0); 487 } 488 489 #undef __FUNCT__ 490 #define __FUNCT__ "PetscGetArguments" 491 /*@C 492 PetscGetArguments - Allows you to access the command line arguments anywhere 493 after PetscInitialize() is called but before PetscFinalize(). 494 495 Not Collective 496 497 Output Parameters: 498 . args - the command line arguments 499 500 Level: intermediate 501 502 Notes: 503 This does NOT start with the program name and IS null terminated (final arg is void) 504 505 Concepts: command line arguments 506 507 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscFreeArguments() 508 509 @*/ 510 PetscErrorCode PetscGetArguments(char ***args) 511 { 512 PetscInt i,argc = PetscGlobalArgc; 513 PetscErrorCode ierr; 514 515 PetscFunctionBegin; 516 if (!PetscInitializeCalled && PetscFinalizeCalled) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ORDER,"You must call after PetscInitialize() but before PetscFinalize()"); 517 if (!argc) {*args = 0; PetscFunctionReturn(0);} 518 ierr = PetscMalloc(argc*sizeof(char*),args);CHKERRQ(ierr); 519 for (i=0; i<argc-1; i++) { 520 ierr = PetscStrallocpy(PetscGlobalArgs[i+1],&(*args)[i]);CHKERRQ(ierr); 521 } 522 (*args)[argc-1] = 0; 523 PetscFunctionReturn(0); 524 } 525 526 #undef __FUNCT__ 527 #define __FUNCT__ "PetscFreeArguments" 528 /*@C 529 PetscFreeArguments - Frees the memory obtained with PetscGetArguments() 530 531 Not Collective 532 533 Output Parameters: 534 . args - the command line arguments 535 536 Level: intermediate 537 538 Concepts: command line arguments 539 540 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscGetArguments() 541 542 @*/ 543 PetscErrorCode PetscFreeArguments(char **args) 544 { 545 PetscInt i = 0; 546 PetscErrorCode ierr; 547 548 PetscFunctionBegin; 549 if (!args) PetscFunctionReturn(0); 550 while (args[i]) { 551 ierr = PetscFree(args[i]);CHKERRQ(ierr); 552 i++; 553 } 554 ierr = PetscFree(args);CHKERRQ(ierr); 555 PetscFunctionReturn(0); 556 } 557 558 #undef __FUNCT__ 559 #define __FUNCT__ "PetscInitialize" 560 /*@C 561 PetscInitialize - Initializes the PETSc database and MPI. 562 PetscInitialize() calls MPI_Init() if that has yet to be called, 563 so this routine should always be called near the beginning of 564 your program -- usually the very first line! 565 566 Collective on MPI_COMM_WORLD or PETSC_COMM_WORLD if it has been set 567 568 Input Parameters: 569 + argc - count of number of command line arguments 570 . args - the command line arguments 571 . file - [optional] PETSc database file, also checks ~username/.petscrc and .petscrc use NULL to not check for 572 code specific file. Use -skip_petscrc in the code specific file to skip the .petscrc files 573 - help - [optional] Help message to print, use NULL for no message 574 575 If you wish PETSc code to run ONLY on a subcommunicator of MPI_COMM_WORLD, create that 576 communicator first and assign it to PETSC_COMM_WORLD BEFORE calling PetscInitialize(). Thus if you are running a 577 four process job and two processes will run PETSc and have PetscInitialize() and PetscFinalize() and two process will not, 578 then do this. If ALL processes in the job are using PetscInitialize() and PetscFinalize() then you don't need to do this, even 579 if different subcommunicators of the job are doing different things with PETSc. 580 581 Options Database Keys: 582 + -start_in_debugger [noxterm,dbx,xdb,gdb,...] - Starts program in debugger 583 . -on_error_attach_debugger [noxterm,dbx,xdb,gdb,...] - Starts debugger when error detected 584 . -on_error_emacs <machinename> causes emacsclient to jump to error file 585 . -on_error_abort calls abort() when error detected (no traceback) 586 . -on_error_mpiabort calls MPI_abort() when error detected 587 . -error_output_stderr prints error messages to stderr instead of the default stdout 588 . -error_output_none does not print the error messages (but handles errors in the same way as if this was not called) 589 . -debugger_nodes [node1,node2,...] - Indicates nodes to start in debugger 590 . -debugger_pause [sleeptime] (in seconds) - Pauses debugger 591 . -stop_for_debugger - Print message on how to attach debugger manually to 592 process and wait (-debugger_pause) seconds for attachment 593 . -malloc - Indicates use of PETSc error-checking malloc (on by default for debug version of libraries) 594 . -malloc no - Indicates not to use error-checking malloc 595 . -malloc_debug - check for memory corruption at EVERY malloc or free 596 . -malloc_dump - prints a list of all unfreed memory at the end of the run 597 . -malloc_test - like -malloc_dump -malloc_debug, but only active for debugging builds 598 . -fp_trap - Stops on floating point exceptions (Note that on the 599 IBM RS6000 this slows code by at least a factor of 10.) 600 . -no_signal_handler - Indicates not to trap error signals 601 . -shared_tmp - indicates /tmp directory is shared by all processors 602 . -not_shared_tmp - each processor has own /tmp 603 . -tmp - alternative name of /tmp directory 604 . -get_total_flops - returns total flops done by all processors 605 . -memory_info - Print memory usage at end of run 606 - -server <port> - start PETSc webserver (default port is 8080) 607 608 Options Database Keys for Profiling: 609 See the <a href="../../docs/manual.pdf#nameddest=ch_profiling">profiling chapter of the users manual</a> for details. 610 + -info <optional filename> - Prints verbose information to the screen 611 . -info_exclude <null,vec,mat,pc,ksp,snes,ts> - Excludes some of the verbose messages 612 . -log_sync - Log the synchronization in scatters, inner products and norms 613 . -log_trace [filename] - Print traces of all PETSc calls to the screen (useful to determine where a program 614 hangs without running in the debugger). See PetscLogTraceBegin(). 615 . -log_summary [filename] - Prints summary of flop and timing information to screen. If the filename is specified the 616 summary is written to the file. See PetscLogView(). 617 . -log_summary_python [filename] - Prints data on of flop and timing usage to a file or screen. See PetscLogPrintSViewPython(). 618 . -log_all [filename] - Logs extensive profiling information See PetscLogDump(). 619 . -log [filename] - Logs basic profiline information See PetscLogDump(). 620 - -log_mpe [filename] - Creates a logfile viewable by the utility Jumpshot (in MPICH distribution) 621 622 Only one of -log_trace, -log_summary, -log_all, -log, or -log_mpe may be used at a time 623 624 Environmental Variables: 625 + PETSC_TMP - alternative tmp directory 626 . PETSC_SHARED_TMP - tmp is shared by all processes 627 . PETSC_NOT_SHARED_TMP - each process has its own private tmp 628 . PETSC_VIEWER_SOCKET_PORT - socket number to use for socket viewer 629 - PETSC_VIEWER_SOCKET_MACHINE - machine to use for socket viewer to connect to 630 631 632 Level: beginner 633 634 Notes: 635 If for some reason you must call MPI_Init() separately, call 636 it before PetscInitialize(). 637 638 Fortran Version: 639 In Fortran this routine has the format 640 $ call PetscInitialize(file,ierr) 641 642 + ierr - error return code 643 - file - [optional] PETSc database file, also checks ~username/.petscrc and .petscrc use NULL_CHARACTER to not check for 644 code specific file. Use -skip_petscrc in the code specific file to skip the .petscrc files 645 646 Important Fortran Note: 647 In Fortran, you MUST use NULL_CHARACTER to indicate a 648 null character string; you CANNOT just use NULL as 649 in the C version. See the <a href="../../docs/manual.pdf">users manual</a> for details. 650 651 If your main program is C but you call Fortran code that also uses PETSc you need to call PetscInitializeFortran() soon after 652 calling PetscInitialize(). 653 654 Concepts: initializing PETSc 655 656 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscInitializeNoArguments() 657 658 @*/ 659 PetscErrorCode PetscInitialize(int *argc,char ***args,const char file[],const char help[]) 660 { 661 PetscErrorCode ierr; 662 PetscMPIInt flag, size; 663 PetscInt nodesize; 664 PetscBool flg; 665 char hostname[256]; 666 667 PetscFunctionBegin; 668 if (PetscInitializeCalled) PetscFunctionReturn(0); 669 670 /* these must be initialized in a routine, not as a constant declaration*/ 671 PETSC_STDOUT = stdout; 672 PETSC_STDERR = stderr; 673 674 ierr = PetscOptionsCreate();CHKERRQ(ierr); 675 676 /* 677 We initialize the program name here (before MPI_Init()) because MPICH has a bug in 678 it that it sets args[0] on all processors to be args[0] on the first processor. 679 */ 680 if (argc && *argc) { 681 ierr = PetscSetProgramName(**args);CHKERRQ(ierr); 682 } else { 683 ierr = PetscSetProgramName("Unknown Name");CHKERRQ(ierr); 684 } 685 686 ierr = MPI_Initialized(&flag);CHKERRQ(ierr); 687 if (!flag) { 688 if (PETSC_COMM_WORLD != MPI_COMM_NULL) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"You cannot set PETSC_COMM_WORLD if you have not initialized MPI first"); 689 #if defined(PETSC_HAVE_MPI_INIT_THREAD) 690 { 691 PetscMPIInt provided; 692 ierr = MPI_Init_thread(argc,args,MPI_THREAD_FUNNELED,&provided);CHKERRQ(ierr); 693 } 694 #else 695 ierr = MPI_Init(argc,args);CHKERRQ(ierr); 696 #endif 697 PetscBeganMPI = PETSC_TRUE; 698 } 699 if (argc && args) { 700 PetscGlobalArgc = *argc; 701 PetscGlobalArgs = *args; 702 } 703 PetscFinalizeCalled = PETSC_FALSE; 704 705 if (PETSC_COMM_WORLD == MPI_COMM_NULL) PETSC_COMM_WORLD = MPI_COMM_WORLD; 706 ierr = MPI_Comm_set_errhandler(PETSC_COMM_WORLD,MPI_ERRORS_RETURN);CHKERRQ(ierr); 707 708 /* Done after init due to a bug in MPICH-GM? */ 709 ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr); 710 711 ierr = MPI_Comm_rank(MPI_COMM_WORLD,&PetscGlobalRank);CHKERRQ(ierr); 712 ierr = MPI_Comm_size(MPI_COMM_WORLD,&PetscGlobalSize);CHKERRQ(ierr); 713 714 MPIU_BOOL = MPI_INT; 715 MPIU_ENUM = MPI_INT; 716 717 /* 718 Initialized the global complex variable; this is because with 719 shared libraries the constructors for global variables 720 are not called; at least on IRIX. 721 */ 722 #if defined(PETSC_HAVE_COMPLEX) 723 { 724 #if defined(PETSC_CLANGUAGE_CXX) 725 PetscComplex ic(0.0,1.0); 726 PETSC_i = ic; 727 #elif defined(PETSC_CLANGUAGE_C) 728 PETSC_i = _Complex_I; 729 #endif 730 } 731 732 #if !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX) 733 ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr); 734 ierr = MPI_Type_commit(&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr); 735 ierr = MPI_Type_contiguous(2,MPI_FLOAT,&MPIU_C_COMPLEX);CHKERRQ(ierr); 736 ierr = MPI_Type_commit(&MPIU_C_COMPLEX);CHKERRQ(ierr); 737 #endif 738 #endif /* PETSC_HAVE_COMPLEX */ 739 740 /* 741 Create the PETSc MPI reduction operator that sums of the first 742 half of the entries and maxes the second half. 743 */ 744 ierr = MPI_Op_create(PetscMaxSum_Local,1,&PetscMaxSum_Op);CHKERRQ(ierr); 745 746 #if defined(PETSC_USE_REAL___FLOAT128) 747 ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU___FLOAT128);CHKERRQ(ierr); 748 ierr = MPI_Type_commit(&MPIU___FLOAT128);CHKERRQ(ierr); 749 #if defined(PETSC_HAVE_COMPLEX) 750 ierr = MPI_Type_contiguous(4,MPI_DOUBLE,&MPIU___COMPLEX128);CHKERRQ(ierr); 751 ierr = MPI_Type_commit(&MPIU___COMPLEX128);CHKERRQ(ierr); 752 #endif 753 ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRQ(ierr); 754 ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRQ(ierr); 755 #endif 756 757 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128) 758 ierr = MPI_Op_create(PetscSum_Local,1,&MPIU_SUM);CHKERRQ(ierr); 759 #endif 760 761 ierr = MPI_Type_contiguous(2,MPIU_SCALAR,&MPIU_2SCALAR);CHKERRQ(ierr); 762 ierr = MPI_Type_commit(&MPIU_2SCALAR);CHKERRQ(ierr); 763 ierr = MPI_Op_create(PetscADMax_Local,1,&PetscADMax_Op);CHKERRQ(ierr); 764 ierr = MPI_Op_create(PetscADMin_Local,1,&PetscADMin_Op);CHKERRQ(ierr); 765 766 #if defined(PETSC_USE_64BIT_INDICES) || !defined(MPI_2INT) 767 ierr = MPI_Type_contiguous(2,MPIU_INT,&MPIU_2INT);CHKERRQ(ierr); 768 ierr = MPI_Type_commit(&MPIU_2INT);CHKERRQ(ierr); 769 #endif 770 771 772 /* 773 Attributes to be set on PETSc communicators 774 */ 775 ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelCounter,&Petsc_Counter_keyval,(void*)0);CHKERRQ(ierr); 776 ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelComm_Outer,&Petsc_InnerComm_keyval,(void*)0);CHKERRQ(ierr); 777 ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelComm_Inner,&Petsc_OuterComm_keyval,(void*)0);CHKERRQ(ierr); 778 779 /* 780 Build the options database 781 */ 782 ierr = PetscOptionsInsert(argc,args,file);CHKERRQ(ierr); 783 784 785 /* 786 Print main application help message 787 */ 788 ierr = PetscOptionsHasName(NULL,"-help",&flg);CHKERRQ(ierr); 789 if (help && flg) { 790 ierr = PetscPrintf(PETSC_COMM_WORLD,help);CHKERRQ(ierr); 791 } 792 ierr = PetscOptionsCheckInitial_Private();CHKERRQ(ierr); 793 794 ierr = PetscCitationsInitialize();CHKERRQ(ierr); 795 796 #if defined(PETSC_HAVE_SAWS) 797 if (!PetscGlobalRank) { 798 char cert[PETSC_MAX_PATH_LEN],root[PETSC_MAX_PATH_LEN],intro[4024],programname[64],appline[256]; 799 int port; 800 PetscBool rootlocal = PETSC_FALSE,flg2; 801 802 ierr = PetscOptionsHasName(NULL,"-saws_log",&flg);CHKERRQ(ierr); 803 if (flg) { 804 char sawslog[PETSC_MAX_PATH_LEN]; 805 806 ierr = PetscOptionsGetString(NULL,"-saws_log",sawslog,PETSC_MAX_PATH_LEN,NULL);CHKERRQ(ierr); 807 if (sawslog[0]) { 808 PetscStackCallSAWs(SAWs_Set_Use_Logfile,(sawslog)); 809 } else { 810 PetscStackCallSAWs(SAWs_Set_Use_Logfile,(NULL)); 811 } 812 } 813 ierr = PetscOptionsGetString(NULL,"-saws_https",cert,PETSC_MAX_PATH_LEN,&flg);CHKERRQ(ierr); 814 if (flg) { 815 PetscStackCallSAWs(SAWs_Set_Use_HTTPS,(cert)); 816 } 817 ierr = PetscOptionsGetInt(NULL,"-saws_port",&port,&flg);CHKERRQ(ierr); 818 if (flg) { 819 PetscStackCallSAWs(SAWs_Set_Port,(port)); 820 } 821 ierr = PetscOptionsGetString(NULL,"-saws_root",root,PETSC_MAX_PATH_LEN,&flg);CHKERRQ(ierr); 822 if (flg) { 823 PetscStackCallSAWs(SAWs_Set_Document_Root,(root));CHKERRQ(ierr); 824 ierr = PetscStrcmp(root,".",&rootlocal);CHKERRQ(ierr); 825 } 826 ierr = PetscOptionsHasName(NULL,"-saws_local",&flg2);CHKERRQ(ierr); 827 if (flg2) { 828 char jsdir[PETSC_MAX_PATH_LEN]; 829 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"-saws_local option requires -saws_root option"); 830 ierr = PetscSNPrintf(jsdir,PETSC_MAX_PATH_LEN,"%s/js",root);CHKERRQ(ierr); 831 ierr = PetscTestDirectory(jsdir,'r',&flg);CHKERRQ(ierr); 832 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_FILE_READ,"-saws_local option requires js directory in root directory"); 833 PetscStackCallSAWs(SAWs_Set_Local_JSHeader,());CHKERRQ(ierr); 834 } 835 ierr = PetscGetProgramName(programname,64);CHKERRQ(ierr); 836 if (rootlocal) { 837 ierr = PetscSNPrintf(appline,256,"%s.c.html",programname);CHKERRQ(ierr); 838 ierr = PetscTestFile(appline,'r',&rootlocal);CHKERRQ(ierr); 839 } 840 if (rootlocal && help) { 841 ierr = PetscSNPrintf(appline,256,"<center> Running <a href=\"%s.c.html\">%s</a> which %s </center><br>\n",programname,programname,help); 842 } else if (help) { 843 ierr = PetscSNPrintf(appline,256,"<center> Running %s which %s </center><br>\n",programname,help); 844 } else { 845 ierr = PetscSNPrintf(appline,256,"<center> Running %s</center><br>\n",programname); 846 } 847 848 ierr = PetscSNPrintf(intro,4024,"<body>\n" 849 "<center><h2> <a href=\"http://www.mcs.anl.gov/petsc\">PETSc</a> Application Web server powered by <a href=\"https://bitbucket.org/saws/saws\">SAWs</a> </h2></center>\n" 850 "%s" 851 "<center>This is the default PETSc application dashboard, from it you can access any published PETSc objects or logging data</center><br>\n",appline); 852 PetscStackCallSAWs(SAWs_Set_Body,("index.html",0,intro)); 853 PetscStackCallSAWs(SAWs_Initialize,()); 854 ierr = PetscCitationsRegister("@TechReport{ saws," 855 "Author = {Matt Otten and Jed Brown and Barry Smith}," 856 "Title = {Scientific Application Web Server (SAWs) Users Manual}," 857 "Institution = {Argonne National Laboratory}," 858 "Year = 2013}",NULL);CHKERRQ(ierr); 859 } 860 861 #endif 862 863 /* SHOULD PUT IN GUARDS: Make sure logging is initialized, even if we do not print it out */ 864 #if defined(PETSC_USE_LOG) 865 ierr = PetscLogBegin_Private();CHKERRQ(ierr); 866 #endif 867 868 /* 869 Load the dynamic libraries (on machines that support them), this registers all 870 the solvers etc. (On non-dynamic machines this initializes the PetscDraw and PetscViewer classes) 871 */ 872 ierr = PetscInitialize_DynamicLibraries();CHKERRQ(ierr); 873 874 ierr = MPI_Comm_size(PETSC_COMM_WORLD,&size);CHKERRQ(ierr); 875 ierr = PetscInfo1(0,"PETSc successfully started: number of processors = %d\n",size);CHKERRQ(ierr); 876 ierr = PetscGetHostName(hostname,256);CHKERRQ(ierr); 877 ierr = PetscInfo1(0,"Running on machine: %s\n",hostname);CHKERRQ(ierr); 878 879 ierr = PetscOptionsCheckInitial_Components();CHKERRQ(ierr); 880 /* Check the options database for options related to the options database itself */ 881 ierr = PetscOptionsSetFromOptions();CHKERRQ(ierr); 882 883 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32) 884 /* 885 Tell MPI about our own data representation converter, this would/should be used if extern32 is not supported by the MPI 886 887 Currently not used because it is not supported by MPICH. 888 */ 889 #if !defined(PETSC_WORDS_BIGENDIAN) 890 ierr = MPI_Register_datarep((char*)"petsc",PetscDataRep_read_conv_fn,PetscDataRep_write_conv_fn,PetscDataRep_extent_fn,NULL);CHKERRQ(ierr); 891 #endif 892 #endif 893 894 ierr = PetscOptionsGetInt(NULL,"-hmpi_spawn_size",&nodesize,&flg);CHKERRQ(ierr); 895 if (flg) { 896 #if defined(PETSC_HAVE_MPI_COMM_SPAWN) 897 ierr = PetscHMPISpawn((PetscMPIInt) nodesize);CHKERRQ(ierr); /* worker nodes never return from here; they go directly to PetscEnd() */ 898 #else 899 SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"PETSc built without MPI 2 (MPI_Comm_spawn) support, use -hmpi_merge_size instead"); 900 #endif 901 } else { 902 ierr = PetscOptionsGetInt(NULL,"-hmpi_merge_size",&nodesize,&flg);CHKERRQ(ierr); 903 if (flg) { 904 ierr = PetscHMPIMerge((PetscMPIInt) nodesize,NULL,NULL);CHKERRQ(ierr); 905 if (PetscHMPIWorker) { /* if worker then never enter user code */ 906 PetscInitializeCalled = PETSC_TRUE; 907 PetscEnd(); 908 } 909 } 910 } 911 912 #if defined(PETSC_HAVE_CUDA) 913 { 914 PetscMPIInt p; 915 for (p = 0; p < PetscGlobalSize; ++p) { 916 if (p == PetscGlobalRank) cublasInit(); 917 ierr = MPI_Barrier(PETSC_COMM_WORLD);CHKERRQ(ierr); 918 } 919 } 920 #endif 921 922 ierr = PetscOptionsHasName(NULL,"-python",&flg);CHKERRQ(ierr); 923 if (flg) { 924 PetscInitializeCalled = PETSC_TRUE; 925 ierr = PetscPythonInitialize(NULL,NULL);CHKERRQ(ierr); 926 } 927 928 ierr = PetscThreadCommInitializePackage();CHKERRQ(ierr); 929 930 /* 931 Setup building of stack frames for all function calls 932 */ 933 PetscThreadLocalRegister((PetscThreadKey*)&petscstack); /* Creates pthread_key */ 934 #if defined(PETSC_USE_DEBUG) 935 ierr = PetscStackCreate();CHKERRQ(ierr); 936 #endif 937 938 #if defined(PETSC_SERIALIZE_FUNCTIONS) 939 ierr = PetscFPTCreate(10000);CHKERRQ(ierr); 940 #endif 941 942 943 /* 944 Once we are completedly initialized then we can set this variables 945 */ 946 PetscInitializeCalled = PETSC_TRUE; 947 PetscFunctionReturn(0); 948 } 949 950 extern PetscObject *PetscObjects; 951 extern PetscInt PetscObjectsCounts, PetscObjectsMaxCounts; 952 953 #undef __FUNCT__ 954 #define __FUNCT__ "PetscFinalize" 955 /*@C 956 PetscFinalize - Checks for options to be called at the conclusion 957 of the program. MPI_Finalize() is called only if the user had not 958 called MPI_Init() before calling PetscInitialize(). 959 960 Collective on PETSC_COMM_WORLD 961 962 Options Database Keys: 963 + -options_table - Calls PetscOptionsView() 964 . -options_left - Prints unused options that remain in the database 965 . -objects_dump [all] - Prints list of objects allocated by the user that have not been freed, the option all cause all outstanding objects to be listed 966 . -mpidump - Calls PetscMPIDump() 967 . -malloc_dump - Calls PetscMallocDump() 968 . -malloc_info - Prints total memory usage 969 - -malloc_log - Prints summary of memory usage 970 971 Level: beginner 972 973 Note: 974 See PetscInitialize() for more general runtime options. 975 976 .seealso: PetscInitialize(), PetscOptionsView(), PetscMallocDump(), PetscMPIDump(), PetscEnd() 977 @*/ 978 PetscErrorCode PetscFinalize(void) 979 { 980 PetscErrorCode ierr; 981 PetscMPIInt rank; 982 PetscInt nopt; 983 PetscBool flg1 = PETSC_FALSE,flg2 = PETSC_FALSE,flg3 = PETSC_FALSE; 984 PetscBool flg; 985 #if defined(PETSC_USE_LOG) 986 char mname[PETSC_MAX_PATH_LEN]; 987 #endif 988 989 PetscFunctionBegin; 990 if (!PetscInitializeCalled) { 991 printf("PetscInitialize() must be called before PetscFinalize()\n"); 992 PetscFunctionReturn(PETSC_ERR_ARG_WRONGSTATE); 993 } 994 ierr = PetscInfo(NULL,"PetscFinalize() called\n");CHKERRQ(ierr); 995 996 ierr = MPI_Comm_rank(PETSC_COMM_WORLD,&rank);CHKERRQ(ierr); 997 998 ierr = PetscOptionsHasName(NULL,"-citations",&flg);CHKERRQ(ierr); 999 if (flg) { 1000 char *cits, filename[PETSC_MAX_PATH_LEN]; 1001 FILE *fd = PETSC_STDOUT; 1002 1003 ierr = PetscOptionsGetString(NULL,"-citations",filename,PETSC_MAX_PATH_LEN,NULL);CHKERRQ(ierr); 1004 if (filename[0]) { 1005 ierr = PetscFOpen(PETSC_COMM_WORLD,filename,"w",&fd);CHKERRQ(ierr); 1006 } 1007 ierr = PetscSegBufferGet(PetscCitationsList,1,&cits);CHKERRQ(ierr); 1008 cits[0] = 0; 1009 ierr = PetscSegBufferExtractAlloc(PetscCitationsList,&cits);CHKERRQ(ierr); 1010 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"If you publish results based on this computation please cite the following:\n");CHKERRQ(ierr); 1011 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr); 1012 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"%s",cits);CHKERRQ(ierr); 1013 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr); 1014 ierr = PetscFClose(PETSC_COMM_WORLD,fd);CHKERRQ(ierr); 1015 ierr = PetscFree(cits);CHKERRQ(ierr); 1016 } 1017 ierr = PetscSegBufferDestroy(&PetscCitationsList);CHKERRQ(ierr); 1018 1019 #if defined(PETSC_SERIALIZE_FUNCTIONS) 1020 ierr = PetscFPTDestroy();CHKERRQ(ierr); 1021 #endif 1022 1023 1024 #if defined(PETSC_HAVE_SAWS) 1025 flg = PETSC_FALSE; 1026 ierr = PetscOptionsGetBool(NULL,"-options_gui",&flg,NULL);CHKERRQ(ierr); 1027 if (flg) { 1028 ierr = PetscOptionsSAWsDestroy();CHKERRQ(ierr); 1029 } 1030 #endif 1031 1032 #if defined(PETSC_HAVE_SERVER) 1033 flg1 = PETSC_FALSE; 1034 ierr = PetscOptionsGetBool(NULL,"-server",&flg1,NULL);CHKERRQ(ierr); 1035 if (flg1) { 1036 /* this is a crude hack, but better than nothing */ 1037 ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 petscwebserver","r",NULL);CHKERRQ(ierr); 1038 } 1039 #endif 1040 1041 #if defined(PETSC_HAVE_X) 1042 flg1 = PETSC_FALSE; 1043 ierr = PetscOptionsGetBool(NULL,"-x_virtual",&flg1,NULL);CHKERRQ(ierr); 1044 if (flg1) { 1045 /* this is a crude hack, but better than nothing */ 1046 ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 Xvfb","r",NULL);CHKERRQ(ierr); 1047 } 1048 #endif 1049 1050 ierr = PetscHMPIFinalize();CHKERRQ(ierr); 1051 1052 ierr = PetscOptionsGetBool(NULL,"-malloc_info",&flg2,NULL);CHKERRQ(ierr); 1053 if (!flg2) { 1054 flg2 = PETSC_FALSE; 1055 ierr = PetscOptionsGetBool(NULL,"-memory_info",&flg2,NULL);CHKERRQ(ierr); 1056 } 1057 if (flg2) { 1058 ierr = PetscMemoryShowUsage(PETSC_VIEWER_STDOUT_WORLD,"Summary of Memory Usage in PETSc\n");CHKERRQ(ierr); 1059 } 1060 1061 #if defined(PETSC_USE_LOG) 1062 flg1 = PETSC_FALSE; 1063 ierr = PetscOptionsGetBool(NULL,"-get_total_flops",&flg1,NULL);CHKERRQ(ierr); 1064 if (flg1) { 1065 PetscLogDouble flops = 0; 1066 ierr = MPI_Reduce(&petsc_TotalFlops,&flops,1,MPI_DOUBLE,MPI_SUM,0,PETSC_COMM_WORLD);CHKERRQ(ierr); 1067 ierr = PetscPrintf(PETSC_COMM_WORLD,"Total flops over all processors %g\n",flops);CHKERRQ(ierr); 1068 } 1069 #endif 1070 1071 1072 #if defined(PETSC_USE_LOG) 1073 #if defined(PETSC_HAVE_MPE) 1074 mname[0] = 0; 1075 1076 ierr = PetscOptionsGetString(NULL,"-log_mpe",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr); 1077 if (flg1) { 1078 if (mname[0]) {ierr = PetscLogMPEDump(mname);CHKERRQ(ierr);} 1079 else {ierr = PetscLogMPEDump(0);CHKERRQ(ierr);} 1080 } 1081 #endif 1082 mname[0] = 0; 1083 1084 ierr = PetscOptionsGetString(NULL,"-log_summary",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr); 1085 if (flg1) { 1086 PetscViewer viewer; 1087 if (mname[0]) { 1088 ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr); 1089 ierr = PetscLogView(viewer);CHKERRQ(ierr); 1090 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1091 } else { 1092 viewer = PETSC_VIEWER_STDOUT_WORLD; 1093 ierr = PetscLogView(viewer);CHKERRQ(ierr); 1094 } 1095 } 1096 1097 mname[0] = 0; 1098 1099 ierr = PetscOptionsGetString(NULL,"-log_summary_python",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr); 1100 if (flg1) { 1101 PetscViewer viewer; 1102 if (mname[0]) { 1103 ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr); 1104 ierr = PetscLogViewPython(viewer);CHKERRQ(ierr); 1105 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1106 } else { 1107 viewer = PETSC_VIEWER_STDOUT_WORLD; 1108 ierr = PetscLogViewPython(viewer);CHKERRQ(ierr); 1109 } 1110 } 1111 1112 ierr = PetscOptionsGetString(NULL,"-log_detailed",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr); 1113 if (flg1) { 1114 if (mname[0]) {ierr = PetscLogPrintDetailed(PETSC_COMM_WORLD,mname);CHKERRQ(ierr);} 1115 else {ierr = PetscLogPrintDetailed(PETSC_COMM_WORLD,0);CHKERRQ(ierr);} 1116 } 1117 1118 mname[0] = 0; 1119 1120 ierr = PetscOptionsGetString(NULL,"-log_all",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr); 1121 ierr = PetscOptionsGetString(NULL,"-log",mname,PETSC_MAX_PATH_LEN,&flg2);CHKERRQ(ierr); 1122 if (flg1 || flg2) { 1123 if (mname[0]) PetscLogDump(mname); 1124 else PetscLogDump(0); 1125 } 1126 #endif 1127 1128 /* 1129 Free all objects registered with PetscObjectRegisterDestroy() such as PETSC_VIEWER_XXX_(). 1130 */ 1131 ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr); 1132 1133 ierr = PetscStackDestroy();CHKERRQ(ierr); 1134 PetscThreadLocalDestroy((PetscThreadKey)petscstack); /* Deletes pthread_key */ 1135 1136 flg1 = PETSC_FALSE; 1137 ierr = PetscOptionsGetBool(NULL,"-no_signal_handler",&flg1,NULL);CHKERRQ(ierr); 1138 if (!flg1) { ierr = PetscPopSignalHandler();CHKERRQ(ierr);} 1139 flg1 = PETSC_FALSE; 1140 ierr = PetscOptionsGetBool(NULL,"-mpidump",&flg1,NULL);CHKERRQ(ierr); 1141 if (flg1) { 1142 ierr = PetscMPIDump(stdout);CHKERRQ(ierr); 1143 } 1144 flg1 = PETSC_FALSE; 1145 flg2 = PETSC_FALSE; 1146 /* preemptive call to avoid listing this option in options table as unused */ 1147 ierr = PetscOptionsHasName(NULL,"-malloc_dump",&flg1);CHKERRQ(ierr); 1148 ierr = PetscOptionsHasName(NULL,"-objects_dump",&flg1);CHKERRQ(ierr); 1149 ierr = PetscOptionsGetBool(NULL,"-options_table",&flg2,NULL);CHKERRQ(ierr); 1150 1151 if (flg2) { 1152 PetscViewer viewer; 1153 ierr = PetscViewerASCIIGetStdout(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr); 1154 ierr = PetscOptionsView(viewer);CHKERRQ(ierr); 1155 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1156 } 1157 1158 /* to prevent PETSc -options_left from warning */ 1159 ierr = PetscOptionsHasName(NULL,"-nox",&flg1);CHKERRQ(ierr); 1160 ierr = PetscOptionsHasName(NULL,"-nox_warning",&flg1);CHKERRQ(ierr); 1161 1162 if (!PetscHMPIWorker) { /* worker processes skip this because they do not usually process options */ 1163 flg3 = PETSC_FALSE; /* default value is required */ 1164 ierr = PetscOptionsGetBool(NULL,"-options_left",&flg3,&flg1);CHKERRQ(ierr); 1165 ierr = PetscOptionsAllUsed(&nopt);CHKERRQ(ierr); 1166 if (flg3) { 1167 if (!flg2) { /* have not yet printed the options */ 1168 PetscViewer viewer; 1169 ierr = PetscViewerASCIIGetStdout(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr); 1170 ierr = PetscOptionsView(viewer);CHKERRQ(ierr); 1171 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1172 } 1173 if (!nopt) { 1174 ierr = PetscPrintf(PETSC_COMM_WORLD,"There are no unused options.\n");CHKERRQ(ierr); 1175 } else if (nopt == 1) { 1176 ierr = PetscPrintf(PETSC_COMM_WORLD,"There is one unused database option. It is:\n");CHKERRQ(ierr); 1177 } else { 1178 ierr = PetscPrintf(PETSC_COMM_WORLD,"There are %D unused database options. They are:\n",nopt);CHKERRQ(ierr); 1179 } 1180 } 1181 #if defined(PETSC_USE_DEBUG) 1182 if (nopt && !flg3 && !flg1) { 1183 ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! There are options you set that were not used!\n");CHKERRQ(ierr); 1184 ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! could be spelling mistake, etc!\n");CHKERRQ(ierr); 1185 ierr = PetscOptionsLeft();CHKERRQ(ierr); 1186 } else if (nopt && flg3) { 1187 #else 1188 if (nopt && flg3) { 1189 #endif 1190 ierr = PetscOptionsLeft();CHKERRQ(ierr); 1191 } 1192 } 1193 1194 #if defined(PETSC_HAVE_SAWS) 1195 if (!PetscGlobalRank) { 1196 ierr = PetscStackSAWsViewOff();CHKERRQ(ierr); 1197 PetscStackCallSAWs(SAWs_Finalize,()); 1198 } 1199 #endif 1200 1201 { 1202 PetscThreadComm tcomm_world; 1203 ierr = PetscGetThreadCommWorld(&tcomm_world);CHKERRQ(ierr); 1204 /* Free global thread communicator */ 1205 ierr = PetscThreadCommDestroy(&tcomm_world);CHKERRQ(ierr); 1206 } 1207 1208 /* 1209 List all objects the user may have forgot to free 1210 */ 1211 ierr = PetscOptionsHasName(NULL,"-objects_dump",&flg1);CHKERRQ(ierr); 1212 if (flg1) { 1213 MPI_Comm local_comm; 1214 char string[64]; 1215 1216 ierr = PetscOptionsGetString(NULL,"-objects_dump",string,64,NULL);CHKERRQ(ierr); 1217 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRQ(ierr); 1218 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1219 ierr = PetscObjectsDump(stdout,(string[0] == 'a') ? PETSC_TRUE : PETSC_FALSE);CHKERRQ(ierr); 1220 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1221 ierr = MPI_Comm_free(&local_comm);CHKERRQ(ierr); 1222 } 1223 PetscObjectsCounts = 0; 1224 PetscObjectsMaxCounts = 0; 1225 1226 ierr = PetscFree(PetscObjects);CHKERRQ(ierr); 1227 1228 #if defined(PETSC_USE_LOG) 1229 ierr = PetscLogDestroy();CHKERRQ(ierr); 1230 #endif 1231 1232 /* 1233 Destroy any packages that registered a finalize 1234 */ 1235 ierr = PetscRegisterFinalizeAll();CHKERRQ(ierr); 1236 1237 /* 1238 Destroy all the function registration lists created 1239 */ 1240 ierr = PetscFinalize_DynamicLibraries();CHKERRQ(ierr); 1241 1242 /* 1243 Print PetscFunctionLists that have not been properly freed 1244 1245 ierr = PetscFunctionListPrintAll();CHKERRQ(ierr); 1246 */ 1247 1248 if (petsc_history) { 1249 ierr = PetscCloseHistoryFile(&petsc_history);CHKERRQ(ierr); 1250 petsc_history = 0; 1251 } 1252 1253 ierr = PetscInfoAllow(PETSC_FALSE,NULL);CHKERRQ(ierr); 1254 1255 { 1256 char fname[PETSC_MAX_PATH_LEN]; 1257 FILE *fd; 1258 int err; 1259 1260 fname[0] = 0; 1261 1262 ierr = PetscOptionsGetString(NULL,"-malloc_dump",fname,250,&flg1);CHKERRQ(ierr); 1263 flg2 = PETSC_FALSE; 1264 ierr = PetscOptionsGetBool(NULL,"-malloc_test",&flg2,NULL);CHKERRQ(ierr); 1265 #if defined(PETSC_USE_DEBUG) 1266 if (PETSC_RUNNING_ON_VALGRIND) flg2 = PETSC_FALSE; 1267 #else 1268 flg2 = PETSC_FALSE; /* Skip reporting for optimized builds regardless of -malloc_test */ 1269 #endif 1270 if (flg1 && fname[0]) { 1271 char sname[PETSC_MAX_PATH_LEN]; 1272 1273 sprintf(sname,"%s_%d",fname,rank); 1274 fd = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname); 1275 ierr = PetscMallocDump(fd);CHKERRQ(ierr); 1276 err = fclose(fd); 1277 if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file"); 1278 } else if (flg1 || flg2) { 1279 MPI_Comm local_comm; 1280 1281 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRQ(ierr); 1282 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1283 ierr = PetscMallocDump(stdout);CHKERRQ(ierr); 1284 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1285 ierr = MPI_Comm_free(&local_comm);CHKERRQ(ierr); 1286 } 1287 } 1288 1289 { 1290 char fname[PETSC_MAX_PATH_LEN]; 1291 FILE *fd = NULL; 1292 1293 fname[0] = 0; 1294 1295 ierr = PetscOptionsGetString(NULL,"-malloc_log",fname,250,&flg1);CHKERRQ(ierr); 1296 ierr = PetscOptionsHasName(NULL,"-malloc_log_threshold",&flg2);CHKERRQ(ierr); 1297 if (flg1 && fname[0]) { 1298 int err; 1299 1300 if (!rank) { 1301 fd = fopen(fname,"w"); 1302 if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",fname); 1303 } 1304 ierr = PetscMallocDumpLog(fd);CHKERRQ(ierr); 1305 if (fd) { 1306 err = fclose(fd); 1307 if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file"); 1308 } 1309 } else if (flg1 || flg2) { 1310 ierr = PetscMallocDumpLog(stdout);CHKERRQ(ierr); 1311 } 1312 } 1313 /* Can be destroyed only after all the options are used */ 1314 ierr = PetscOptionsDestroy();CHKERRQ(ierr); 1315 1316 PetscGlobalArgc = 0; 1317 PetscGlobalArgs = 0; 1318 1319 #if defined(PETSC_USE_REAL___FLOAT128) 1320 ierr = MPI_Type_free(&MPIU___FLOAT128);CHKERRQ(ierr); 1321 #if defined(PETSC_HAVE_COMPLEX) 1322 ierr = MPI_Type_free(&MPIU___COMPLEX128);CHKERRQ(ierr); 1323 #endif 1324 ierr = MPI_Op_free(&MPIU_MAX);CHKERRQ(ierr); 1325 ierr = MPI_Op_free(&MPIU_MIN);CHKERRQ(ierr); 1326 #endif 1327 1328 #if defined(PETSC_HAVE_COMPLEX) 1329 #if !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX) 1330 ierr = MPI_Type_free(&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr); 1331 ierr = MPI_Type_free(&MPIU_C_COMPLEX);CHKERRQ(ierr); 1332 #endif 1333 #endif 1334 1335 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128) 1336 ierr = MPI_Op_free(&MPIU_SUM);CHKERRQ(ierr); 1337 #endif 1338 1339 ierr = MPI_Type_free(&MPIU_2SCALAR);CHKERRQ(ierr); 1340 #if defined(PETSC_USE_64BIT_INDICES) || !defined(MPI_2INT) 1341 ierr = MPI_Type_free(&MPIU_2INT);CHKERRQ(ierr); 1342 #endif 1343 ierr = MPI_Op_free(&PetscMaxSum_Op);CHKERRQ(ierr); 1344 ierr = MPI_Op_free(&PetscADMax_Op);CHKERRQ(ierr); 1345 ierr = MPI_Op_free(&PetscADMin_Op);CHKERRQ(ierr); 1346 1347 /* 1348 Destroy any known inner MPI_Comm's and attributes pointing to them 1349 Note this will not destroy any new communicators the user has created. 1350 1351 If all PETSc objects were not destroyed those left over objects will have hanging references to 1352 the MPI_Comms that were freed; but that is ok because those PETSc objects will never be used again 1353 */ 1354 { 1355 PetscCommCounter *counter; 1356 PetscMPIInt flg; 1357 MPI_Comm icomm; 1358 union {MPI_Comm comm; void *ptr;} ucomm; 1359 ierr = MPI_Attr_get(PETSC_COMM_SELF,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRQ(ierr); 1360 if (flg) { 1361 icomm = ucomm.comm; 1362 ierr = MPI_Attr_get(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRQ(ierr); 1363 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory"); 1364 1365 ierr = MPI_Attr_delete(PETSC_COMM_SELF,Petsc_InnerComm_keyval);CHKERRQ(ierr); 1366 ierr = MPI_Attr_delete(icomm,Petsc_Counter_keyval);CHKERRQ(ierr); 1367 ierr = MPI_Comm_free(&icomm);CHKERRQ(ierr); 1368 } 1369 ierr = MPI_Attr_get(PETSC_COMM_WORLD,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRQ(ierr); 1370 if (flg) { 1371 icomm = ucomm.comm; 1372 ierr = MPI_Attr_get(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRQ(ierr); 1373 if (!flg) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory"); 1374 1375 ierr = MPI_Attr_delete(PETSC_COMM_WORLD,Petsc_InnerComm_keyval);CHKERRQ(ierr); 1376 ierr = MPI_Attr_delete(icomm,Petsc_Counter_keyval);CHKERRQ(ierr); 1377 ierr = MPI_Comm_free(&icomm);CHKERRQ(ierr); 1378 } 1379 } 1380 1381 ierr = MPI_Keyval_free(&Petsc_Counter_keyval);CHKERRQ(ierr); 1382 ierr = MPI_Keyval_free(&Petsc_InnerComm_keyval);CHKERRQ(ierr); 1383 ierr = MPI_Keyval_free(&Petsc_OuterComm_keyval);CHKERRQ(ierr); 1384 1385 #if defined(PETSC_HAVE_CUDA) 1386 { 1387 PetscInt p; 1388 for (p = 0; p < PetscGlobalSize; ++p) { 1389 if (p == PetscGlobalRank) cublasShutdown(); 1390 ierr = MPI_Barrier(PETSC_COMM_WORLD);CHKERRQ(ierr); 1391 } 1392 } 1393 #endif 1394 1395 if (PetscBeganMPI) { 1396 #if defined(PETSC_HAVE_MPI_FINALIZED) 1397 PetscMPIInt flag; 1398 ierr = MPI_Finalized(&flag);CHKERRQ(ierr); 1399 if (flag) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_LIB,"MPI_Finalize() has already been called, even though MPI_Init() was called by PetscInitialize()"); 1400 #endif 1401 ierr = MPI_Finalize();CHKERRQ(ierr); 1402 } 1403 /* 1404 1405 Note: In certain cases PETSC_COMM_WORLD is never MPI_Comm_free()ed because 1406 the communicator has some outstanding requests on it. Specifically if the 1407 flag PETSC_HAVE_BROKEN_REQUEST_FREE is set (for IBM MPI implementation). See 1408 src/vec/utils/vpscat.c. Due to this the memory allocated in PetscCommDuplicate() 1409 is never freed as it should be. Thus one may obtain messages of the form 1410 [ 1] 8 bytes PetscCommDuplicate() line 645 in src/sys/mpiu.c indicating the 1411 memory was not freed. 1412 1413 */ 1414 ierr = PetscMallocClear();CHKERRQ(ierr); 1415 1416 PetscInitializeCalled = PETSC_FALSE; 1417 PetscFinalizeCalled = PETSC_TRUE; 1418 PetscFunctionReturn(ierr); 1419 } 1420 1421 #if defined(PETSC_MISSING_LAPACK_lsame_) 1422 PETSC_EXTERN int lsame_(char *a,char *b) 1423 { 1424 if (*a == *b) return 1; 1425 if (*a + 32 == *b) return 1; 1426 if (*a - 32 == *b) return 1; 1427 return 0; 1428 } 1429 #endif 1430 1431 #if defined(PETSC_MISSING_LAPACK_lsame) 1432 PETSC_EXTERN int lsame(char *a,char *b) 1433 { 1434 if (*a == *b) return 1; 1435 if (*a + 32 == *b) return 1; 1436 if (*a - 32 == *b) return 1; 1437 return 0; 1438 } 1439 #endif 1440