1 #define PETSC_DESIRE_FEATURE_TEST_MACROS 2 /* 3 This file defines the initialization of PETSc, including PetscInitialize() 4 */ 5 #include <petsc/private/petscimpl.h> /*I "petscsys.h" I*/ 6 #include <petscvalgrind.h> 7 #include <petscviewer.h> 8 9 #if defined(PETSC_HAVE_CUDA) 10 #include <petsccublas.h> 11 PETSC_EXTERN cudaEvent_t petsc_gputimer_begin; 12 PETSC_EXTERN cudaEvent_t petsc_gputimer_end; 13 #endif 14 15 #if defined(PETSC_HAVE_HIP) 16 #include <petschipblas.h> 17 PETSC_EXTERN hipEvent_t petsc_gputimer_begin; 18 PETSC_EXTERN hipEvent_t petsc_gputimer_end; 19 #endif 20 21 #if defined(PETSC_USE_GCOV) 22 EXTERN_C_BEGIN 23 void __gcov_flush(void); 24 EXTERN_C_END 25 #endif 26 27 #if defined(PETSC_USE_LOG) 28 PETSC_INTERN PetscErrorCode PetscLogFinalize(void); 29 #endif 30 31 #if defined(PETSC_SERIALIZE_FUNCTIONS) 32 PETSC_INTERN PetscFPT PetscFPTData; 33 PetscFPT PetscFPTData = 0; 34 #endif 35 36 #if defined(PETSC_HAVE_SAWS) 37 #include <petscviewersaws.h> 38 #endif 39 40 /* -----------------------------------------------------------------------------------------*/ 41 42 PETSC_INTERN FILE *petsc_history; 43 44 PETSC_INTERN PetscErrorCode PetscInitialize_DynamicLibraries(void); 45 PETSC_INTERN PetscErrorCode PetscFinalize_DynamicLibraries(void); 46 PETSC_INTERN PetscErrorCode PetscFunctionListPrintAll(void); 47 PETSC_INTERN PetscErrorCode PetscSequentialPhaseBegin_Private(MPI_Comm,int); 48 PETSC_INTERN PetscErrorCode PetscSequentialPhaseEnd_Private(MPI_Comm,int); 49 PETSC_INTERN PetscErrorCode PetscCloseHistoryFile(FILE**); 50 51 /* user may set these BEFORE calling PetscInitialize() */ 52 MPI_Comm PETSC_COMM_WORLD = MPI_COMM_NULL; 53 #if defined(PETSC_HAVE_MPI_INIT_THREAD) 54 PetscMPIInt PETSC_MPI_THREAD_REQUIRED = MPI_THREAD_FUNNELED; 55 #else 56 PetscMPIInt PETSC_MPI_THREAD_REQUIRED = 0; 57 #endif 58 59 PetscMPIInt Petsc_Counter_keyval = MPI_KEYVAL_INVALID; 60 PetscMPIInt Petsc_InnerComm_keyval = MPI_KEYVAL_INVALID; 61 PetscMPIInt Petsc_OuterComm_keyval = MPI_KEYVAL_INVALID; 62 PetscMPIInt Petsc_ShmComm_keyval = MPI_KEYVAL_INVALID; 63 64 /* 65 Declare and set all the string names of the PETSc enums 66 */ 67 const char *const PetscBools[] = {"FALSE","TRUE","PetscBool","PETSC_",NULL}; 68 const char *const PetscCopyModes[] = {"COPY_VALUES","OWN_POINTER","USE_POINTER","PetscCopyMode","PETSC_",NULL}; 69 70 PetscBool PetscPreLoadingUsed = PETSC_FALSE; 71 PetscBool PetscPreLoadingOn = PETSC_FALSE; 72 73 PetscInt PetscHotRegionDepth; 74 75 #if defined(PETSC_HAVE_THREADSAFETY) 76 PetscSpinlock PetscViewerASCIISpinLockOpen; 77 PetscSpinlock PetscViewerASCIISpinLockStdout; 78 PetscSpinlock PetscViewerASCIISpinLockStderr; 79 PetscSpinlock PetscCommSpinLock; 80 #endif 81 82 /* 83 PetscInitializeNoPointers - Calls PetscInitialize() from C/C++ without the pointers to argc and args 84 85 Collective 86 87 Level: advanced 88 89 Notes: 90 this is called only by the PETSc 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 Julia without the problem of trying to initialize MPI more than once. 93 94 Developer Note: Turns off PETSc signal handling to allow Julia to manage signals 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);if (ierr) return ierr; 106 ierr = PetscPopSignalHandler();CHKERRQ(ierr); 107 PetscBeganMPI = PETSC_FALSE; 108 PetscFunctionReturn(ierr); 109 } 110 111 /* 112 Used by Julia interface to get communicator 113 */ 114 PetscErrorCode PetscGetPETSC_COMM_SELF(MPI_Comm *comm) 115 { 116 PetscFunctionBegin; 117 *comm = PETSC_COMM_SELF; 118 PetscFunctionReturn(0); 119 } 120 121 /*@C 122 PetscInitializeNoArguments - Calls PetscInitialize() from C/C++ without 123 the command line arguments. 124 125 Collective 126 127 Level: advanced 128 129 .seealso: PetscInitialize(), PetscInitializeFortran() 130 @*/ 131 PetscErrorCode PetscInitializeNoArguments(void) 132 { 133 PetscErrorCode ierr; 134 int argc = 0; 135 char **args = NULL; 136 137 PetscFunctionBegin; 138 ierr = PetscInitialize(&argc,&args,NULL,NULL); 139 PetscFunctionReturn(ierr); 140 } 141 142 /*@ 143 PetscInitialized - Determine whether PETSc is initialized. 144 145 Level: beginner 146 147 .seealso: PetscInitialize(), PetscInitializeNoArguments(), PetscInitializeFortran() 148 @*/ 149 PetscErrorCode PetscInitialized(PetscBool *isInitialized) 150 { 151 *isInitialized = PetscInitializeCalled; 152 return 0; 153 } 154 155 /*@ 156 PetscFinalized - Determine whether PetscFinalize() has been called yet 157 158 Level: developer 159 160 .seealso: PetscInitialize(), PetscInitializeNoArguments(), PetscInitializeFortran() 161 @*/ 162 PetscErrorCode PetscFinalized(PetscBool *isFinalized) 163 { 164 *isFinalized = PetscFinalizeCalled; 165 return 0; 166 } 167 168 PETSC_INTERN PetscErrorCode PetscOptionsCheckInitial_Private(const char []); 169 170 /* 171 This function is the MPI reduction operation used to compute the sum of the 172 first half of the datatype and the max of the second half. 173 */ 174 MPI_Op MPIU_MAXSUM_OP = 0; 175 176 PETSC_INTERN void MPIAPI MPIU_MaxSum_Local(void *in,void *out,int *cnt,MPI_Datatype *datatype) 177 { 178 PetscInt *xin = (PetscInt*)in,*xout = (PetscInt*)out,i,count = *cnt; 179 180 PetscFunctionBegin; 181 if (*datatype != MPIU_2INT) { 182 (*PetscErrorPrintf)("Can only handle MPIU_2INT data types"); 183 PETSCABORT(MPI_COMM_SELF,PETSC_ERR_ARG_WRONG); 184 } 185 186 for (i=0; i<count; i++) { 187 xout[2*i] = PetscMax(xout[2*i],xin[2*i]); 188 xout[2*i+1] += xin[2*i+1]; 189 } 190 PetscFunctionReturnVoid(); 191 } 192 193 /* 194 Returns the max of the first entry owned by this processor and the 195 sum of the second entry. 196 197 The reason sizes[2*i] contains lengths sizes[2*i+1] contains flag of 1 if length is nonzero 198 is so that the MPIU_MAXSUM_OP() can set TWO values, if we passed in only sizes[i] with lengths 199 there would be no place to store the both needed results. 200 */ 201 PetscErrorCode PetscMaxSum(MPI_Comm comm,const PetscInt sizes[],PetscInt *max,PetscInt *sum) 202 { 203 PetscErrorCode ierr; 204 205 PetscFunctionBegin; 206 #if defined(PETSC_HAVE_MPI_REDUCE_SCATTER_BLOCK) 207 { 208 struct {PetscInt max,sum;} work; 209 ierr = MPI_Reduce_scatter_block((void*)sizes,&work,1,MPIU_2INT,MPIU_MAXSUM_OP,comm);CHKERRMPI(ierr); 210 *max = work.max; 211 *sum = work.sum; 212 } 213 #else 214 { 215 PetscMPIInt size,rank; 216 struct {PetscInt max,sum;} *work; 217 ierr = MPI_Comm_size(comm,&size);CHKERRMPI(ierr); 218 ierr = MPI_Comm_rank(comm,&rank);CHKERRMPI(ierr); 219 ierr = PetscMalloc1(size,&work);CHKERRQ(ierr); 220 ierr = MPIU_Allreduce((void*)sizes,work,size,MPIU_2INT,MPIU_MAXSUM_OP,comm);CHKERRMPI(ierr); 221 *max = work[rank].max; 222 *sum = work[rank].sum; 223 ierr = PetscFree(work);CHKERRQ(ierr); 224 } 225 #endif 226 PetscFunctionReturn(0); 227 } 228 229 /* ----------------------------------------------------------------------------*/ 230 231 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16) 232 MPI_Op MPIU_SUM = 0; 233 234 PETSC_EXTERN void MPIAPI PetscSum_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 235 { 236 PetscInt i,count = *cnt; 237 238 PetscFunctionBegin; 239 if (*datatype == MPIU_REAL) { 240 PetscReal *xin = (PetscReal*)in,*xout = (PetscReal*)out; 241 for (i=0; i<count; i++) xout[i] += xin[i]; 242 } 243 #if defined(PETSC_HAVE_COMPLEX) 244 else if (*datatype == MPIU_COMPLEX) { 245 PetscComplex *xin = (PetscComplex*)in,*xout = (PetscComplex*)out; 246 for (i=0; i<count; i++) xout[i] += xin[i]; 247 } 248 #endif 249 else { 250 (*PetscErrorPrintf)("Can only handle MPIU_REAL or MPIU_COMPLEX data types"); 251 PETSCABORT(MPI_COMM_SELF,PETSC_ERR_ARG_WRONG); 252 } 253 PetscFunctionReturnVoid(); 254 } 255 #endif 256 257 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16) 258 MPI_Op MPIU_MAX = 0; 259 MPI_Op MPIU_MIN = 0; 260 261 PETSC_EXTERN void MPIAPI PetscMax_Local(void *in,void *out,PetscMPIInt *cnt,MPI_Datatype *datatype) 262 { 263 PetscInt i,count = *cnt; 264 265 PetscFunctionBegin; 266 if (*datatype == MPIU_REAL) { 267 PetscReal *xin = (PetscReal*)in,*xout = (PetscReal*)out; 268 for (i=0; i<count; i++) xout[i] = PetscMax(xout[i],xin[i]); 269 } 270 #if defined(PETSC_HAVE_COMPLEX) 271 else if (*datatype == MPIU_COMPLEX) { 272 PetscComplex *xin = (PetscComplex*)in,*xout = (PetscComplex*)out; 273 for (i=0; i<count; i++) { 274 xout[i] = PetscRealPartComplex(xout[i])<PetscRealPartComplex(xin[i]) ? xin[i] : xout[i]; 275 } 276 } 277 #endif 278 else { 279 (*PetscErrorPrintf)("Can only handle MPIU_REAL or MPIU_COMPLEX data types"); 280 PETSCABORT(MPI_COMM_SELF,PETSC_ERR_ARG_WRONG); 281 } 282 PetscFunctionReturnVoid(); 283 } 284 285 PETSC_EXTERN void MPIAPI PetscMin_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] = PetscMin(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++) { 298 xout[i] = PetscRealPartComplex(xout[i])>PetscRealPartComplex(xin[i]) ? xin[i] : xout[i]; 299 } 300 } 301 #endif 302 else { 303 (*PetscErrorPrintf)("Can only handle MPIU_REAL or MPIU_SCALAR data (i.e. double or complex) types"); 304 PETSCABORT(MPI_COMM_SELF,PETSC_ERR_ARG_WRONG); 305 } 306 PetscFunctionReturnVoid(); 307 } 308 #endif 309 310 /* 311 Private routine to delete internal tag/name counter storage when a communicator is freed. 312 313 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. 314 315 Note: this is declared extern "C" because it is passed to MPI_Comm_create_keyval() 316 317 */ 318 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_Counter_Attr_Delete_Fn(MPI_Comm comm,PetscMPIInt keyval,void *count_val,void *extra_state) 319 { 320 PetscErrorCode ierr; 321 PetscCommCounter *counter=(PetscCommCounter*)count_val; 322 323 PetscFunctionBegin; 324 ierr = PetscInfo1(NULL,"Deleting counter data in an MPI_Comm %ld\n",(long)comm);CHKERRMPI(ierr); 325 ierr = PetscFree(counter->iflags);CHKERRMPI(ierr); 326 ierr = PetscFree(counter);CHKERRMPI(ierr); 327 PetscFunctionReturn(MPI_SUCCESS); 328 } 329 330 /* 331 This is invoked on the outer comm as a result of either PetscCommDestroy() (via MPI_Comm_delete_attr) or when the user 332 calls MPI_Comm_free(). 333 334 This is the only entry point for breaking the links between inner and outer comms. 335 336 This is called by MPI, not by users. This is called when MPI_Comm_free() is called on the communicator. 337 338 Note: this is declared extern "C" because it is passed to MPI_Comm_create_keyval() 339 340 */ 341 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_InnerComm_Attr_Delete_Fn(MPI_Comm comm,PetscMPIInt keyval,void *attr_val,void *extra_state) 342 { 343 PetscErrorCode ierr; 344 union {MPI_Comm comm; void *ptr;} icomm; 345 346 PetscFunctionBegin; 347 if (keyval != Petsc_InnerComm_keyval) SETERRMPI(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Unexpected keyval"); 348 icomm.ptr = attr_val; 349 if (PetscDefined(USE_DEBUG)) { 350 /* Error out if the inner/outer comms are not correctly linked through their Outer/InnterComm attributes */ 351 PetscMPIInt flg; 352 union {MPI_Comm comm; void *ptr;} ocomm; 353 ierr = MPI_Comm_get_attr(icomm.comm,Petsc_OuterComm_keyval,&ocomm,&flg);CHKERRMPI(ierr); 354 if (!flg) SETERRMPI(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner comm does not have OuterComm attribute"); 355 if (ocomm.comm != comm) SETERRMPI(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner comm's OuterComm attribute does not point to outer PETSc comm"); 356 } 357 ierr = MPI_Comm_delete_attr(icomm.comm,Petsc_OuterComm_keyval);CHKERRMPI(ierr); 358 ierr = PetscInfo2(NULL,"User MPI_Comm %ld is being unlinked from inner PETSc comm %ld\n",(long)comm,(long)icomm.comm);CHKERRMPI(ierr); 359 PetscFunctionReturn(MPI_SUCCESS); 360 } 361 362 /* 363 * This is invoked on the inner comm when Petsc_InnerComm_Attr_Delete_Fn calls MPI_Comm_delete_attr(). It should not be reached any other way. 364 */ 365 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_OuterComm_Attr_Delete_Fn(MPI_Comm comm,PetscMPIInt keyval,void *attr_val,void *extra_state) 366 { 367 PetscErrorCode ierr; 368 369 PetscFunctionBegin; 370 ierr = PetscInfo1(NULL,"Removing reference to PETSc communicator embedded in a user MPI_Comm %ld\n",(long)comm);CHKERRMPI(ierr); 371 PetscFunctionReturn(MPI_SUCCESS); 372 } 373 374 PETSC_EXTERN PetscMPIInt MPIAPI Petsc_ShmComm_Attr_Delete_Fn(MPI_Comm,PetscMPIInt,void *,void *); 375 376 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32) 377 PETSC_EXTERN PetscMPIInt PetscDataRep_extent_fn(MPI_Datatype,MPI_Aint*,void*); 378 PETSC_EXTERN PetscMPIInt PetscDataRep_read_conv_fn(void*, MPI_Datatype,PetscMPIInt,void*,MPI_Offset,void*); 379 PETSC_EXTERN PetscMPIInt PetscDataRep_write_conv_fn(void*, MPI_Datatype,PetscMPIInt,void*,MPI_Offset,void*); 380 #endif 381 382 PetscMPIInt PETSC_MPI_ERROR_CLASS=MPI_ERR_LASTCODE,PETSC_MPI_ERROR_CODE; 383 384 PETSC_INTERN int PetscGlobalArgc; 385 PETSC_INTERN char **PetscGlobalArgs; 386 int PetscGlobalArgc = 0; 387 char **PetscGlobalArgs = NULL; 388 PetscSegBuffer PetscCitationsList; 389 390 PetscErrorCode PetscCitationsInitialize(void) 391 { 392 PetscErrorCode ierr; 393 394 PetscFunctionBegin; 395 ierr = PetscSegBufferCreate(1,10000,&PetscCitationsList);CHKERRQ(ierr); 396 ierr = PetscCitationsRegister("@TechReport{petsc-user-ref,\n Author = {Satish Balay and Shrirang Abhyankar and Mark F. Adams and Jed Brown \n and Peter Brune and Kris Buschelman and Lisandro Dalcin and\n Victor Eijkhout and William D. Gropp and Dmitry Karpeyev and\n Dinesh Kaushik and Matthew G. Knepley and Dave A. May and Lois Curfman McInnes\n and Richard Tran Mills and Todd Munson and Karl Rupp and Patrick Sanan\n and Barry F. Smith and Stefano Zampini and Hong Zhang and Hong Zhang},\n Title = {{PETS}c Users Manual},\n Number = {ANL-95/11 - Revision 3.11},\n Institution = {Argonne National Laboratory},\n Year = {2019}\n}\n",NULL);CHKERRQ(ierr); 397 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); 398 PetscFunctionReturn(0); 399 } 400 401 static char programname[PETSC_MAX_PATH_LEN] = ""; /* HP includes entire path in name */ 402 403 PetscErrorCode PetscSetProgramName(const char name[]) 404 { 405 PetscErrorCode ierr; 406 407 PetscFunctionBegin; 408 ierr = PetscStrncpy(programname,name,sizeof(programname));CHKERRQ(ierr); 409 PetscFunctionReturn(0); 410 } 411 412 /*@C 413 PetscGetProgramName - Gets the name of the running program. 414 415 Not Collective 416 417 Input Parameter: 418 . len - length of the string name 419 420 Output Parameter: 421 . name - the name of the running program 422 423 Level: advanced 424 425 Notes: 426 The name of the program is copied into the user-provided character 427 array of length len. On some machines the program name includes 428 its entire path, so one should generally set len >= PETSC_MAX_PATH_LEN. 429 @*/ 430 PetscErrorCode PetscGetProgramName(char name[],size_t len) 431 { 432 PetscErrorCode ierr; 433 434 PetscFunctionBegin; 435 ierr = PetscStrncpy(name,programname,len);CHKERRQ(ierr); 436 PetscFunctionReturn(0); 437 } 438 439 /*@C 440 PetscGetArgs - Allows you to access the raw command line arguments anywhere 441 after PetscInitialize() is called but before PetscFinalize(). 442 443 Not Collective 444 445 Output Parameters: 446 + argc - count of number of command line arguments 447 - args - the command line arguments 448 449 Level: intermediate 450 451 Notes: 452 This is usually used to pass the command line arguments into other libraries 453 that are called internally deep in PETSc or the application. 454 455 The first argument contains the program name as is normal for C arguments. 456 457 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArguments() 458 459 @*/ 460 PetscErrorCode PetscGetArgs(int *argc,char ***args) 461 { 462 PetscFunctionBegin; 463 if (!PetscInitializeCalled && PetscFinalizeCalled) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ORDER,"You must call after PetscInitialize() but before PetscFinalize()"); 464 *argc = PetscGlobalArgc; 465 *args = PetscGlobalArgs; 466 PetscFunctionReturn(0); 467 } 468 469 /*@C 470 PetscGetArguments - Allows you to access the command line arguments anywhere 471 after PetscInitialize() is called but before PetscFinalize(). 472 473 Not Collective 474 475 Output Parameters: 476 . args - the command line arguments 477 478 Level: intermediate 479 480 Notes: 481 This does NOT start with the program name and IS null terminated (final arg is void) 482 483 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscFreeArguments() 484 485 @*/ 486 PetscErrorCode PetscGetArguments(char ***args) 487 { 488 PetscInt i,argc = PetscGlobalArgc; 489 PetscErrorCode ierr; 490 491 PetscFunctionBegin; 492 if (!PetscInitializeCalled && PetscFinalizeCalled) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ORDER,"You must call after PetscInitialize() but before PetscFinalize()"); 493 if (!argc) {*args = NULL; PetscFunctionReturn(0);} 494 ierr = PetscMalloc1(argc,args);CHKERRQ(ierr); 495 for (i=0; i<argc-1; i++) { 496 ierr = PetscStrallocpy(PetscGlobalArgs[i+1],&(*args)[i]);CHKERRQ(ierr); 497 } 498 (*args)[argc-1] = NULL; 499 PetscFunctionReturn(0); 500 } 501 502 /*@C 503 PetscFreeArguments - Frees the memory obtained with PetscGetArguments() 504 505 Not Collective 506 507 Output Parameters: 508 . args - the command line arguments 509 510 Level: intermediate 511 512 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscGetArguments() 513 514 @*/ 515 PetscErrorCode PetscFreeArguments(char **args) 516 { 517 PetscInt i = 0; 518 PetscErrorCode ierr; 519 520 PetscFunctionBegin; 521 if (!args) PetscFunctionReturn(0); 522 while (args[i]) { 523 ierr = PetscFree(args[i]);CHKERRQ(ierr); 524 i++; 525 } 526 ierr = PetscFree(args);CHKERRQ(ierr); 527 PetscFunctionReturn(0); 528 } 529 530 #if defined(PETSC_HAVE_SAWS) 531 #include <petscconfiginfo.h> 532 533 PETSC_INTERN PetscErrorCode PetscInitializeSAWs(const char help[]) 534 { 535 if (!PetscGlobalRank) { 536 char cert[PETSC_MAX_PATH_LEN],root[PETSC_MAX_PATH_LEN],*intro,programname[64],*appline,*options,version[64]; 537 int port; 538 PetscBool flg,rootlocal = PETSC_FALSE,flg2,selectport = PETSC_FALSE; 539 size_t applinelen,introlen; 540 PetscErrorCode ierr; 541 char sawsurl[256]; 542 543 ierr = PetscOptionsHasName(NULL,NULL,"-saws_log",&flg);CHKERRQ(ierr); 544 if (flg) { 545 char sawslog[PETSC_MAX_PATH_LEN]; 546 547 ierr = PetscOptionsGetString(NULL,NULL,"-saws_log",sawslog,sizeof(sawslog),NULL);CHKERRQ(ierr); 548 if (sawslog[0]) { 549 PetscStackCallSAWs(SAWs_Set_Use_Logfile,(sawslog)); 550 } else { 551 PetscStackCallSAWs(SAWs_Set_Use_Logfile,(NULL)); 552 } 553 } 554 ierr = PetscOptionsGetString(NULL,NULL,"-saws_https",cert,sizeof(cert),&flg);CHKERRQ(ierr); 555 if (flg) { 556 PetscStackCallSAWs(SAWs_Set_Use_HTTPS,(cert)); 557 } 558 ierr = PetscOptionsGetBool(NULL,NULL,"-saws_port_auto_select",&selectport,NULL);CHKERRQ(ierr); 559 if (selectport) { 560 PetscStackCallSAWs(SAWs_Get_Available_Port,(&port)); 561 PetscStackCallSAWs(SAWs_Set_Port,(port)); 562 } else { 563 ierr = PetscOptionsGetInt(NULL,NULL,"-saws_port",&port,&flg);CHKERRQ(ierr); 564 if (flg) { 565 PetscStackCallSAWs(SAWs_Set_Port,(port)); 566 } 567 } 568 ierr = PetscOptionsGetString(NULL,NULL,"-saws_root",root,sizeof(root),&flg);CHKERRQ(ierr); 569 if (flg) { 570 PetscStackCallSAWs(SAWs_Set_Document_Root,(root));CHKERRQ(ierr); 571 ierr = PetscStrcmp(root,".",&rootlocal);CHKERRQ(ierr); 572 } else { 573 ierr = PetscOptionsHasName(NULL,NULL,"-saws_options",&flg);CHKERRQ(ierr); 574 if (flg) { 575 ierr = PetscStrreplace(PETSC_COMM_WORLD,"${PETSC_DIR}/share/petsc/saws",root,sizeof(root));CHKERRQ(ierr); 576 PetscStackCallSAWs(SAWs_Set_Document_Root,(root));CHKERRQ(ierr); 577 } 578 } 579 ierr = PetscOptionsHasName(NULL,NULL,"-saws_local",&flg2);CHKERRQ(ierr); 580 if (flg2) { 581 char jsdir[PETSC_MAX_PATH_LEN]; 582 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"-saws_local option requires -saws_root option"); 583 ierr = PetscSNPrintf(jsdir,sizeof(jsdir),"%s/js",root);CHKERRQ(ierr); 584 ierr = PetscTestDirectory(jsdir,'r',&flg);CHKERRQ(ierr); 585 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_FILE_READ,"-saws_local option requires js directory in root directory"); 586 PetscStackCallSAWs(SAWs_Push_Local_Header,());CHKERRQ(ierr); 587 } 588 ierr = PetscGetProgramName(programname,sizeof(programname));CHKERRQ(ierr); 589 ierr = PetscStrlen(help,&applinelen);CHKERRQ(ierr); 590 introlen = 4096 + applinelen; 591 applinelen += 1024; 592 ierr = PetscMalloc(applinelen,&appline);CHKERRQ(ierr); 593 ierr = PetscMalloc(introlen,&intro);CHKERRQ(ierr); 594 595 if (rootlocal) { 596 ierr = PetscSNPrintf(appline,applinelen,"%s.c.html",programname);CHKERRQ(ierr); 597 ierr = PetscTestFile(appline,'r',&rootlocal);CHKERRQ(ierr); 598 } 599 ierr = PetscOptionsGetAll(NULL,&options);CHKERRQ(ierr); 600 if (rootlocal && help) { 601 ierr = PetscSNPrintf(appline,applinelen,"<center> Running <a href=\"%s.c.html\">%s</a> %s</center><br><center><pre>%s</pre></center><br>\n",programname,programname,options,help);CHKERRQ(ierr); 602 } else if (help) { 603 ierr = PetscSNPrintf(appline,applinelen,"<center>Running %s %s</center><br><center><pre>%s</pre></center><br>",programname,options,help);CHKERRQ(ierr); 604 } else { 605 ierr = PetscSNPrintf(appline,applinelen,"<center> Running %s %s</center><br>\n",programname,options);CHKERRQ(ierr); 606 } 607 ierr = PetscFree(options);CHKERRQ(ierr); 608 ierr = PetscGetVersion(version,sizeof(version));CHKERRQ(ierr); 609 ierr = PetscSNPrintf(intro,introlen,"<body>\n" 610 "<center><h2> <a href=\"https://www.mcs.anl.gov/petsc\">PETSc</a> Application Web server powered by <a href=\"https://bitbucket.org/saws/saws\">SAWs</a> </h2></center>\n" 611 "<center>This is the default PETSc application dashboard, from it you can access any published PETSc objects or logging data</center><br><center>%s configured with %s</center><br>\n" 612 "%s",version,petscconfigureoptions,appline);CHKERRQ(ierr); 613 PetscStackCallSAWs(SAWs_Push_Body,("index.html",0,intro)); 614 ierr = PetscFree(intro);CHKERRQ(ierr); 615 ierr = PetscFree(appline);CHKERRQ(ierr); 616 if (selectport) { 617 PetscBool silent; 618 619 ierr = SAWs_Initialize(); 620 /* another process may have grabbed the port so keep trying */ 621 while (ierr) { 622 PetscStackCallSAWs(SAWs_Get_Available_Port,(&port)); 623 PetscStackCallSAWs(SAWs_Set_Port,(port)); 624 ierr = SAWs_Initialize(); 625 } 626 627 ierr = PetscOptionsGetBool(NULL,NULL,"-saws_port_auto_select_silent",&silent,NULL);CHKERRQ(ierr); 628 if (!silent) { 629 PetscStackCallSAWs(SAWs_Get_FullURL,(sizeof(sawsurl),sawsurl)); 630 ierr = PetscPrintf(PETSC_COMM_WORLD,"Point your browser to %s for SAWs\n",sawsurl);CHKERRQ(ierr); 631 } 632 } else { 633 PetscStackCallSAWs(SAWs_Initialize,()); 634 } 635 ierr = PetscCitationsRegister("@TechReport{ saws,\n" 636 " Author = {Matt Otten and Jed Brown and Barry Smith},\n" 637 " Title = {Scientific Application Web Server (SAWs) Users Manual},\n" 638 " Institution = {Argonne National Laboratory},\n" 639 " Year = 2013\n}\n",NULL);CHKERRQ(ierr); 640 } 641 PetscFunctionReturn(0); 642 } 643 #endif 644 645 /* Things must be done before MPI_Init() when MPI is not yet initialized, and can be shared between C init and Fortran init */ 646 PETSC_INTERN PetscErrorCode PetscPreMPIInit_Private(void) 647 { 648 PetscFunctionBegin; 649 #if defined(PETSC_HAVE_HWLOC_SOLARIS_BUG) 650 /* see MPI.py for details on this bug */ 651 (void) setenv("HWLOC_COMPONENTS","-x86",1); 652 #endif 653 PetscFunctionReturn(0); 654 } 655 656 #if defined(PETSC_HAVE_ADIOS) 657 #include <adios.h> 658 #include <adios_read.h> 659 int64_t Petsc_adios_group; 660 #endif 661 #if defined(PETSC_HAVE_OPENMP) 662 #include <omp.h> 663 PetscInt PetscNumOMPThreads; 664 #endif 665 666 #if defined(PETSC_HAVE_DLFCN_H) 667 #include <dlfcn.h> 668 #endif 669 670 /*@C 671 PetscInitialize - Initializes the PETSc database and MPI. 672 PetscInitialize() calls MPI_Init() if that has yet to be called, 673 so this routine should always be called near the beginning of 674 your program -- usually the very first line! 675 676 Collective on MPI_COMM_WORLD or PETSC_COMM_WORLD if it has been set 677 678 Input Parameters: 679 + argc - count of number of command line arguments 680 . args - the command line arguments 681 . file - [optional] PETSc database file, append ":yaml" to filename to specify YAML options format. 682 Use NULL or empty string to not check for code specific file. 683 Also checks ~/.petscrc, .petscrc and petscrc. 684 Use -skip_petscrc in the code specific file (or command line) to skip ~/.petscrc, .petscrc and petscrc files. 685 - help - [optional] Help message to print, use NULL for no message 686 687 If you wish PETSc code to run ONLY on a subcommunicator of MPI_COMM_WORLD, create that 688 communicator first and assign it to PETSC_COMM_WORLD BEFORE calling PetscInitialize(). Thus if you are running a 689 four process job and two processes will run PETSc and have PetscInitialize() and PetscFinalize() and two process will not, 690 then do this. If ALL processes in the job are using PetscInitialize() and PetscFinalize() then you don't need to do this, even 691 if different subcommunicators of the job are doing different things with PETSc. 692 693 Options Database Keys: 694 + -help [intro] - prints help method for each option; if intro is given the program stops after printing the introductory help message 695 . -start_in_debugger [noxterm,dbx,xdb,gdb,...] - Starts program in debugger 696 . -on_error_attach_debugger [noxterm,dbx,xdb,gdb,...] - Starts debugger when error detected 697 . -on_error_emacs <machinename> - causes emacsclient to jump to error file 698 . -on_error_abort - calls abort() when error detected (no traceback) 699 . -on_error_mpiabort - calls MPI_abort() when error detected 700 . -error_output_stderr - prints error messages to stderr instead of the default stdout 701 . -error_output_none - does not print the error messages (but handles errors in the same way as if this was not called) 702 . -debugger_ranks [rank1,rank2,...] - Indicates ranks to start in debugger 703 . -debugger_pause [sleeptime] (in seconds) - Pauses debugger 704 . -stop_for_debugger - Print message on how to attach debugger manually to 705 process and wait (-debugger_pause) seconds for attachment 706 . -malloc - Indicates use of PETSc error-checking malloc (on by default for debug version of libraries) (deprecated, use -malloc_debug) 707 . -malloc no - Indicates not to use error-checking malloc (deprecated, use -malloc_debug no) 708 . -malloc_debug - check for memory corruption at EVERY malloc or free, see PetscMallocSetDebug() 709 . -malloc_dump - prints a list of all unfreed memory at the end of the run 710 . -malloc_test - like -malloc_dump -malloc_debug, but only active for debugging builds, ignored in optimized build. May want to set in PETSC_OPTIONS environmental variable 711 . -malloc_view - show a list of all allocated memory during PetscFinalize() 712 . -malloc_view_threshold <t> - only list memory allocations of size greater than t with -malloc_view 713 . -malloc_requested_size - malloc logging will record the requested size rather than size after alignment 714 . -fp_trap - Stops on floating point exceptions 715 . -no_signal_handler - Indicates not to trap error signals 716 . -shared_tmp - indicates /tmp directory is shared by all processors 717 . -not_shared_tmp - each processor has own /tmp 718 . -tmp - alternative name of /tmp directory 719 . -get_total_flops - returns total flops done by all processors 720 - -memory_view - Print memory usage at end of run 721 722 Options Database Keys for Option Database: 723 + -skip_petscrc - skip the default option files ~/.petscrc, .petscrc, petscrc 724 . -options_monitor - monitor all set options to standard output for the whole program run 725 - -options_monitor_cancel - cancel options monitoring hard-wired using PetscOptionsMonitorSet() 726 727 Options -options_monitor_{all,cancel} are 728 position-independent and apply to all options set since the PETSc start. 729 They can be used also in option files. 730 731 See PetscOptionsMonitorSet() to do monitoring programmatically. 732 733 Options Database Keys for Profiling: 734 See Users-Manual: ch_profiling for details. 735 + -info [filename][:[~]<list,of,classnames>[:[~]self]] - Prints verbose information. See PetscInfo(). 736 . -log_sync - Enable barrier synchronization for all events. This option is useful to debug imbalance within each event, 737 however it slows things down and gives a distorted view of the overall runtime. 738 . -log_trace [filename] - Print traces of all PETSc calls to the screen (useful to determine where a program 739 hangs without running in the debugger). See PetscLogTraceBegin(). 740 . -log_view [:filename:format] - Prints summary of flop and timing information to screen or file, see PetscLogView(). 741 . -log_view_memory - Includes in the summary from -log_view the memory used in each method, see PetscLogView(). 742 . -log_summary [filename] - (Deprecated, use -log_view) Prints summary of flop and timing information to screen. If the filename is specified the 743 summary is written to the file. See PetscLogView(). 744 . -log_exclude: <vec,mat,pc,ksp,snes> - excludes subset of object classes from logging 745 . -log_all [filename] - Logs extensive profiling information See PetscLogDump(). 746 . -log [filename] - Logs basic profiline information See PetscLogDump(). 747 . -log_mpe [filename] - Creates a logfile viewable by the utility Jumpshot (in MPICH distribution) 748 . -viewfromoptions on,off - Enable or disable XXXSetFromOptions() calls, for applications with many small solves turn this off 749 - -check_pointer_intensity 0,1,2 - if pointers are checked for validity (debug version only), using 0 will result in faster code 750 751 Only one of -log_trace, -log_view, -log_view, -log_all, -log, or -log_mpe may be used at a time 752 753 Options Database Keys for SAWs: 754 + -saws_port <portnumber> - port number to publish SAWs data, default is 8080 755 . -saws_port_auto_select - have SAWs select a new unique port number where it publishes the data, the URL is printed to the screen 756 this is useful when you are running many jobs that utilize SAWs at the same time 757 . -saws_log <filename> - save a log of all SAWs communication 758 . -saws_https <certificate file> - have SAWs use HTTPS instead of HTTP 759 - -saws_root <directory> - allow SAWs to have access to the given directory to search for requested resources and files 760 761 Environmental Variables: 762 + PETSC_TMP - alternative tmp directory 763 . PETSC_SHARED_TMP - tmp is shared by all processes 764 . PETSC_NOT_SHARED_TMP - each process has its own private tmp 765 . PETSC_OPTIONS - a string containing additional options for petsc in the form of command line "-key value" pairs 766 . PETSC_OPTIONS_YAML - (requires configuring PETSc to use libyaml) a string containing additional options for petsc in the form of a YAML document 767 . PETSC_VIEWER_SOCKET_PORT - socket number to use for socket viewer 768 - PETSC_VIEWER_SOCKET_MACHINE - machine to use for socket viewer to connect to 769 770 Level: beginner 771 772 Notes: 773 If for some reason you must call MPI_Init() separately, call 774 it before PetscInitialize(). 775 776 Fortran Version: 777 In Fortran this routine has the format 778 $ call PetscInitialize(file,ierr) 779 780 + ierr - error return code 781 - file - [optional] PETSc database file, also checks ~/.petscrc, .petscrc and petscrc. 782 Use PETSC_NULL_CHARACTER to not check for code specific file. 783 Use -skip_petscrc in the code specific file (or command line) to skip ~/.petscrc, .petscrc and petscrc files. 784 785 Important Fortran Note: 786 In Fortran, you MUST use PETSC_NULL_CHARACTER to indicate a 787 null character string; you CANNOT just use NULL as 788 in the C version. See Users-Manual: ch_fortran for details. 789 790 If your main program is C but you call Fortran code that also uses PETSc you need to call PetscInitializeFortran() soon after 791 calling PetscInitialize(). 792 793 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscInitializeNoArguments() 794 795 @*/ 796 PetscErrorCode PetscInitialize(int *argc,char ***args,const char file[],const char help[]) 797 { 798 PetscErrorCode ierr; 799 PetscMPIInt flag, size; 800 PetscBool flg = PETSC_TRUE; 801 char hostname[256]; 802 803 PetscFunctionBegin; 804 if (PetscInitializeCalled) PetscFunctionReturn(0); 805 /* 806 The checking over compatible runtime libraries is complicated by the MPI ABI initiative 807 https://wiki.mpich.org/mpich/index.php/ABI_Compatibility_Initiative which started with 808 MPICH v3.1 (Released Feburary 2014) 809 IBM MPI v2.1 (December 2014) 810 Intel MPI Library v5.0 (2014) 811 Cray MPT v7.0.0 (June 2014) 812 As of July 31, 2017 the ABI number still appears to be 12, that is all of the versions 813 listed above and since that time are compatible. 814 815 Unfortunately the MPI ABI initiative has not defined a way to determine the ABI number 816 at compile time or runtime. Thus we will need to systematically track the allowed versions 817 and how they are represented in the mpi.h and MPI_Get_library_version() output in order 818 to perform the checking. 819 820 Currently we only check for pre MPI ABI versions (and packages that do not follow the MPI ABI). 821 822 Questions: 823 824 Should the checks for ABI incompatibility be only on the major version number below? 825 Presumably the output to stderr will be removed before a release. 826 */ 827 828 #if defined(PETSC_HAVE_MPI_GET_LIBRARY_VERSION) 829 { 830 char mpilibraryversion[MPI_MAX_LIBRARY_VERSION_STRING]; 831 PetscMPIInt mpilibraryversionlength; 832 ierr = MPI_Get_library_version(mpilibraryversion,&mpilibraryversionlength);if (ierr) return ierr; 833 /* check for MPICH versions before MPI ABI initiative */ 834 #if defined(MPICH_VERSION) 835 #if MPICH_NUMVERSION < 30100000 836 { 837 char *ver,*lf; 838 flg = PETSC_FALSE; 839 ierr = PetscStrstr(mpilibraryversion,"MPICH Version:",&ver);if (ierr) return ierr; 840 if (ver) { 841 ierr = PetscStrchr(ver,'\n',&lf);if (ierr) return ierr; 842 if (lf) { 843 *lf = 0; 844 ierr = PetscStrendswith(ver,MPICH_VERSION,&flg);if (ierr) return ierr; 845 } 846 } 847 if (!flg) { 848 PetscInfo1(NULL,"PETSc warning --- MPICH library version \n%s does not match what PETSc was compiled with %.\n",mpilibraryversion,MPICH_VESION); 849 flg = PETSC_TRUE; 850 } 851 } 852 #endif 853 /* check for OpenMPI version, it is not part of the MPI ABI initiative (is it part of another initiative that needs to be handled?) */ 854 #elif defined(OMPI_MAJOR_VERSION) 855 { 856 char *ver,bs[MPI_MAX_LIBRARY_VERSION_STRING],*bsf; 857 flg = PETSC_FALSE; 858 #define PSTRSZ 2 859 char ompistr1[PSTRSZ][MPI_MAX_LIBRARY_VERSION_STRING] = {"Open MPI","FUJITSU MPI"}; 860 char ompistr2[PSTRSZ][MPI_MAX_LIBRARY_VERSION_STRING] = {"v","Library "}; 861 int i; 862 for (i=0; i<PSTRSZ; i++) { 863 ierr = PetscStrstr(mpilibraryversion,ompistr1[i],&ver);if (ierr) return ierr; 864 if (ver) { 865 PetscSNPrintf(bs,MPI_MAX_LIBRARY_VERSION_STRING,"%s%d.%d",ompistr2[i],OMPI_MAJOR_VERSION,OMPI_MINOR_VERSION); 866 ierr = PetscStrstr(ver,bs,&bsf);if (ierr) return ierr; 867 if (bsf) flg = PETSC_TRUE; 868 break; 869 } 870 } 871 if (!flg) { 872 PetscInfo3(NULL,"PETSc warning --- Open MPI library version \n%s does not match what PETSc was compiled with %d.%d.\n",mpilibraryversion,OMPI_MAJOR_VERSION,OMPI_MINOR_VERSION); 873 flg = PETSC_TRUE; 874 } 875 } 876 #endif 877 } 878 #endif 879 880 #if defined(PETSC_HAVE_DLSYM) 881 { 882 PetscInt cnt = 0; 883 /* These symbols are currently in the OpenMPI and MPICH libraries; they may not always be, in that case the test will simply not detect the problem */ 884 if (dlsym(RTLD_DEFAULT,"ompi_mpi_init")) cnt++; 885 if (dlsym(RTLD_DEFAULT,"MPL_exit")) cnt++; 886 if (cnt > 1) { 887 fprintf(stderr,"PETSc Error --- Application was linked against both OpenMPI and MPICH based MPI libraries and will not run correctly\n"); 888 return PETSC_ERR_MPI_LIB_INCOMP; 889 } 890 } 891 #endif 892 893 /* these must be initialized in a routine, not as a constant declaration*/ 894 PETSC_STDOUT = stdout; 895 PETSC_STDERR = stderr; 896 897 /*CHKERRQ can be used from now */ 898 PetscErrorHandlingInitialized = PETSC_TRUE; 899 900 /* on Windows - set printf to default to printing 2 digit exponents */ 901 #if defined(PETSC_HAVE__SET_OUTPUT_FORMAT) 902 _set_output_format(_TWO_DIGIT_EXPONENT); 903 #endif 904 905 ierr = PetscOptionsCreateDefault();CHKERRQ(ierr); 906 907 /* 908 We initialize the program name here (before MPI_Init()) because MPICH has a bug in 909 it that it sets args[0] on all processors to be args[0] on the first processor. 910 */ 911 if (argc && *argc) { 912 ierr = PetscSetProgramName(**args);CHKERRQ(ierr); 913 } else { 914 ierr = PetscSetProgramName("Unknown Name");CHKERRQ(ierr); 915 } 916 917 ierr = MPI_Initialized(&flag);CHKERRMPI(ierr); 918 if (!flag) { 919 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"); 920 ierr = PetscPreMPIInit_Private();CHKERRQ(ierr); 921 #if defined(PETSC_HAVE_MPI_INIT_THREAD) 922 { 923 PetscMPIInt provided; 924 ierr = MPI_Init_thread(argc,args,PETSC_MPI_THREAD_REQUIRED,&provided);CHKERRMPI(ierr); 925 } 926 #else 927 ierr = MPI_Init(argc,args);CHKERRMPI(ierr); 928 #endif 929 PetscBeganMPI = PETSC_TRUE; 930 } 931 932 if (argc && args) { 933 PetscGlobalArgc = *argc; 934 PetscGlobalArgs = *args; 935 } 936 PetscFinalizeCalled = PETSC_FALSE; 937 ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockOpen);CHKERRQ(ierr); 938 ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockStdout);CHKERRQ(ierr); 939 ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockStderr);CHKERRQ(ierr); 940 ierr = PetscSpinlockCreate(&PetscCommSpinLock);CHKERRQ(ierr); 941 942 if (PETSC_COMM_WORLD == MPI_COMM_NULL) PETSC_COMM_WORLD = MPI_COMM_WORLD; 943 ierr = MPI_Comm_set_errhandler(PETSC_COMM_WORLD,MPI_ERRORS_RETURN);CHKERRMPI(ierr); 944 945 if (PETSC_MPI_ERROR_CLASS == MPI_ERR_LASTCODE) { 946 ierr = MPI_Add_error_class(&PETSC_MPI_ERROR_CLASS);CHKERRMPI(ierr); 947 ierr = MPI_Add_error_code(PETSC_MPI_ERROR_CLASS,&PETSC_MPI_ERROR_CODE);CHKERRMPI(ierr); 948 } 949 950 /* Done after init due to a bug in MPICH-GM? */ 951 ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr); 952 953 ierr = MPI_Comm_rank(MPI_COMM_WORLD,&PetscGlobalRank);CHKERRMPI(ierr); 954 ierr = MPI_Comm_size(MPI_COMM_WORLD,&PetscGlobalSize);CHKERRMPI(ierr); 955 956 MPIU_BOOL = MPI_INT; 957 MPIU_ENUM = MPI_INT; 958 MPIU_FORTRANADDR = (sizeof(void*) == sizeof(int)) ? MPI_INT : MPIU_INT64; 959 if (sizeof(size_t) == sizeof(unsigned)) MPIU_SIZE_T = MPI_UNSIGNED; 960 else if (sizeof(size_t) == sizeof(unsigned long)) MPIU_SIZE_T = MPI_UNSIGNED_LONG; 961 #if defined(PETSC_SIZEOF_LONG_LONG) 962 else if (sizeof(size_t) == sizeof(unsigned long long)) MPIU_SIZE_T = MPI_UNSIGNED_LONG_LONG; 963 #endif 964 else {(*PetscErrorPrintf)("PetscInitialize: Could not find MPI type for size_t\n"); return PETSC_ERR_SUP_SYS;} 965 966 /* 967 Initialized the global complex variable; this is because with 968 shared libraries the constructors for global variables 969 are not called; at least on IRIX. 970 */ 971 #if defined(PETSC_HAVE_COMPLEX) 972 { 973 #if defined(PETSC_CLANGUAGE_CXX) 974 PetscComplex ic(0.0,1.0); 975 PETSC_i = ic; 976 #else 977 PETSC_i = _Complex_I; 978 #endif 979 } 980 #endif /* PETSC_HAVE_COMPLEX */ 981 982 /* 983 Create the PETSc MPI reduction operator that sums of the first 984 half of the entries and maxes the second half. 985 */ 986 ierr = MPI_Op_create(MPIU_MaxSum_Local,1,&MPIU_MAXSUM_OP);CHKERRMPI(ierr); 987 988 #if defined(PETSC_USE_REAL___FLOAT128) 989 ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU___FLOAT128);CHKERRMPI(ierr); 990 ierr = MPI_Type_commit(&MPIU___FLOAT128);CHKERRMPI(ierr); 991 #if defined(PETSC_HAVE_COMPLEX) 992 ierr = MPI_Type_contiguous(4,MPI_DOUBLE,&MPIU___COMPLEX128);CHKERRMPI(ierr); 993 ierr = MPI_Type_commit(&MPIU___COMPLEX128);CHKERRMPI(ierr); 994 #endif 995 ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRMPI(ierr); 996 ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRMPI(ierr); 997 #elif defined(PETSC_USE_REAL___FP16) 998 ierr = MPI_Type_contiguous(2,MPI_CHAR,&MPIU___FP16);CHKERRMPI(ierr); 999 ierr = MPI_Type_commit(&MPIU___FP16);CHKERRMPI(ierr); 1000 ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRMPI(ierr); 1001 ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRMPI(ierr); 1002 #endif 1003 1004 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16) 1005 ierr = MPI_Op_create(PetscSum_Local,1,&MPIU_SUM);CHKERRMPI(ierr); 1006 #endif 1007 1008 ierr = MPI_Type_contiguous(2,MPIU_SCALAR,&MPIU_2SCALAR);CHKERRMPI(ierr); 1009 ierr = MPI_Type_commit(&MPIU_2SCALAR);CHKERRMPI(ierr); 1010 1011 /* create datatypes used by MPIU_MAXLOC, MPIU_MINLOC and PetscSplitReduction_Op */ 1012 #if !defined(PETSC_HAVE_MPIUNI) 1013 { 1014 struct PetscRealInt { PetscReal v; PetscInt i; }; 1015 PetscMPIInt blockSizes[2] = {1,1}; 1016 MPI_Aint blockOffsets[2] = {offsetof(struct PetscRealInt,v),offsetof(struct PetscRealInt,i)}; 1017 MPI_Datatype blockTypes[2] = {MPIU_REAL,MPIU_INT}, tmpStruct; 1018 1019 ierr = MPI_Type_create_struct(2,blockSizes,blockOffsets,blockTypes,&tmpStruct);CHKERRMPI(ierr); 1020 ierr = MPI_Type_create_resized(tmpStruct,0,sizeof(struct PetscRealInt),&MPIU_REAL_INT);CHKERRMPI(ierr); 1021 ierr = MPI_Type_free(&tmpStruct);CHKERRMPI(ierr); 1022 ierr = MPI_Type_commit(&MPIU_REAL_INT);CHKERRMPI(ierr); 1023 } 1024 { 1025 struct PetscScalarInt { PetscScalar v; PetscInt i; }; 1026 PetscMPIInt blockSizes[2] = {1,1}; 1027 MPI_Aint blockOffsets[2] = {offsetof(struct PetscScalarInt,v),offsetof(struct PetscScalarInt,i)}; 1028 MPI_Datatype blockTypes[2] = {MPIU_SCALAR,MPIU_INT}, tmpStruct; 1029 1030 ierr = MPI_Type_create_struct(2,blockSizes,blockOffsets,blockTypes,&tmpStruct);CHKERRMPI(ierr); 1031 ierr = MPI_Type_create_resized(tmpStruct,0,sizeof(struct PetscScalarInt),&MPIU_SCALAR_INT);CHKERRMPI(ierr); 1032 ierr = MPI_Type_free(&tmpStruct);CHKERRMPI(ierr); 1033 ierr = MPI_Type_commit(&MPIU_SCALAR_INT);CHKERRMPI(ierr); 1034 } 1035 #endif 1036 1037 #if defined(PETSC_USE_64BIT_INDICES) 1038 ierr = MPI_Type_contiguous(2,MPIU_INT,&MPIU_2INT);CHKERRMPI(ierr); 1039 ierr = MPI_Type_commit(&MPIU_2INT);CHKERRMPI(ierr); 1040 #endif 1041 1042 /* 1043 Attributes to be set on PETSc communicators 1044 */ 1045 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_Counter_Attr_Delete_Fn,&Petsc_Counter_keyval,(void*)0);CHKERRMPI(ierr); 1046 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_InnerComm_Attr_Delete_Fn,&Petsc_InnerComm_keyval,(void*)0);CHKERRMPI(ierr); 1047 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_OuterComm_Attr_Delete_Fn,&Petsc_OuterComm_keyval,(void*)0);CHKERRMPI(ierr); 1048 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_ShmComm_Attr_Delete_Fn,&Petsc_ShmComm_keyval,(void*)0);CHKERRMPI(ierr); 1049 1050 /* 1051 Build the options database 1052 */ 1053 ierr = PetscOptionsInsert(NULL,argc,args,file);CHKERRQ(ierr); 1054 1055 /* call a second time so it can look in the options database */ 1056 ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr); 1057 1058 /* 1059 Check system options and print help 1060 */ 1061 ierr = PetscOptionsCheckInitial_Private(help);CHKERRQ(ierr); 1062 1063 ierr = PetscCitationsInitialize();CHKERRQ(ierr); 1064 1065 #if defined(PETSC_HAVE_SAWS) 1066 ierr = PetscInitializeSAWs(help);CHKERRQ(ierr); 1067 #endif 1068 1069 /* 1070 Load the dynamic libraries (on machines that support them), this registers all 1071 the solvers etc. (On non-dynamic machines this initializes the PetscDraw and PetscViewer classes) 1072 */ 1073 ierr = PetscInitialize_DynamicLibraries();CHKERRQ(ierr); 1074 1075 ierr = MPI_Comm_size(PETSC_COMM_WORLD,&size);CHKERRMPI(ierr); 1076 ierr = PetscInfo1(NULL,"PETSc successfully started: number of processors = %d\n",size);CHKERRQ(ierr); 1077 ierr = PetscGetHostName(hostname,256);CHKERRQ(ierr); 1078 ierr = PetscInfo1(NULL,"Running on machine: %s\n",hostname);CHKERRQ(ierr); 1079 #if defined(PETSC_HAVE_OPENMP) 1080 { 1081 PetscBool omp_view_flag; 1082 char *threads = getenv("OMP_NUM_THREADS"); 1083 1084 if (threads) { 1085 ierr = PetscInfo1(NULL,"Number of OpenMP threads %s (given by OMP_NUM_THREADS)\n",threads);CHKERRQ(ierr); 1086 (void) sscanf(threads, "%" PetscInt_FMT,&PetscNumOMPThreads); 1087 } else { 1088 #define NMAX 10000 1089 int i; 1090 PetscScalar *x; 1091 ierr = PetscMalloc1(NMAX,&x);CHKERRQ(ierr); 1092 #pragma omp parallel for 1093 for (i=0; i<NMAX; i++) { 1094 x[i] = 0.0; 1095 PetscNumOMPThreads = (PetscInt) omp_get_num_threads(); 1096 } 1097 ierr = PetscFree(x);CHKERRQ(ierr); 1098 ierr = PetscInfo1(NULL,"Number of OpenMP threads %D (number not set with OMP_NUM_THREADS, chosen by system)\n",PetscNumOMPThreads);CHKERRQ(ierr); 1099 } 1100 ierr = PetscOptionsBegin(PETSC_COMM_WORLD,NULL,"OpenMP options","Sys");CHKERRQ(ierr); 1101 ierr = PetscOptionsInt("-omp_num_threads","Number of OpenMP threads to use (can also use environmental variable OMP_NUM_THREADS","None",PetscNumOMPThreads,&PetscNumOMPThreads,&flg);CHKERRQ(ierr); 1102 ierr = PetscOptionsName("-omp_view","Display OpenMP number of threads",NULL,&omp_view_flag);CHKERRQ(ierr); 1103 ierr = PetscOptionsEnd();CHKERRQ(ierr); 1104 if (flg) { 1105 ierr = PetscInfo1(NULL,"Number of OpenMP theads %D (given by -omp_num_threads)\n",PetscNumOMPThreads);CHKERRQ(ierr); 1106 omp_set_num_threads((int)PetscNumOMPThreads); 1107 } 1108 if (omp_view_flag) { 1109 ierr = PetscPrintf(PETSC_COMM_WORLD,"OpenMP: number of threads %D\n",PetscNumOMPThreads);CHKERRQ(ierr); 1110 } 1111 } 1112 #endif 1113 1114 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32) 1115 /* 1116 Tell MPI about our own data representation converter, this would/should be used if extern32 is not supported by the MPI 1117 1118 Currently not used because it is not supported by MPICH. 1119 */ 1120 if (!PetscBinaryBigEndian()) { 1121 ierr = MPI_Register_datarep((char*)"petsc",PetscDataRep_read_conv_fn,PetscDataRep_write_conv_fn,PetscDataRep_extent_fn,NULL);CHKERRMPI(ierr); 1122 } 1123 #endif 1124 1125 /* 1126 Setup building of stack frames for all function calls 1127 */ 1128 #if defined(PETSC_USE_DEBUG) && !defined(PETSC_HAVE_THREADSAFETY) 1129 ierr = PetscStackCreate();CHKERRQ(ierr); 1130 #endif 1131 1132 #if defined(PETSC_SERIALIZE_FUNCTIONS) 1133 ierr = PetscFPTCreate(10000);CHKERRQ(ierr); 1134 #endif 1135 1136 #if defined(PETSC_HAVE_HWLOC) 1137 { 1138 PetscViewer viewer; 1139 ierr = PetscOptionsGetViewer(PETSC_COMM_WORLD,NULL,NULL,"-process_view",&viewer,NULL,&flg);CHKERRQ(ierr); 1140 if (flg) { 1141 ierr = PetscProcessPlacementView(viewer);CHKERRQ(ierr); 1142 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1143 } 1144 } 1145 #endif 1146 1147 flg = PETSC_TRUE; 1148 ierr = PetscOptionsGetBool(NULL,NULL,"-viewfromoptions",&flg,NULL);CHKERRQ(ierr); 1149 if (!flg) {ierr = PetscOptionsPushGetViewerOff(PETSC_TRUE);CHKERRQ(ierr);} 1150 1151 #if defined(PETSC_HAVE_ADIOS) 1152 ierr = adios_init_noxml(PETSC_COMM_WORLD);CHKERRQ(ierr); 1153 ierr = adios_declare_group(&Petsc_adios_group,"PETSc","",adios_stat_default);CHKERRQ(ierr); 1154 ierr = adios_select_method(Petsc_adios_group,"MPI","","");CHKERRQ(ierr); 1155 ierr = adios_read_init_method(ADIOS_READ_METHOD_BP,PETSC_COMM_WORLD,"");CHKERRQ(ierr); 1156 #endif 1157 1158 /* 1159 Set flag that we are completely initialized 1160 */ 1161 PetscInitializeCalled = PETSC_TRUE; 1162 1163 ierr = PetscOptionsHasName(NULL,NULL,"-python",&flg);CHKERRQ(ierr); 1164 if (flg) {ierr = PetscPythonInitialize(NULL,NULL);CHKERRQ(ierr);} 1165 PetscFunctionReturn(0); 1166 } 1167 1168 #if defined(PETSC_USE_LOG) 1169 PETSC_INTERN PetscObject *PetscObjects; 1170 PETSC_INTERN PetscInt PetscObjectsCounts; 1171 PETSC_INTERN PetscInt PetscObjectsMaxCounts; 1172 PETSC_INTERN PetscBool PetscObjectsLog; 1173 #endif 1174 1175 /* 1176 Frees all the MPI types and operations that PETSc may have created 1177 */ 1178 PetscErrorCode PetscFreeMPIResources(void) 1179 { 1180 PetscErrorCode ierr; 1181 1182 PetscFunctionBegin; 1183 #if defined(PETSC_USE_REAL___FLOAT128) 1184 ierr = MPI_Type_free(&MPIU___FLOAT128);CHKERRMPI(ierr); 1185 #if defined(PETSC_HAVE_COMPLEX) 1186 ierr = MPI_Type_free(&MPIU___COMPLEX128);CHKERRMPI(ierr); 1187 #endif 1188 ierr = MPI_Op_free(&MPIU_MAX);CHKERRMPI(ierr); 1189 ierr = MPI_Op_free(&MPIU_MIN);CHKERRMPI(ierr); 1190 #elif defined(PETSC_USE_REAL___FP16) 1191 ierr = MPI_Type_free(&MPIU___FP16);CHKERRMPI(ierr); 1192 ierr = MPI_Op_free(&MPIU_MAX);CHKERRMPI(ierr); 1193 ierr = MPI_Op_free(&MPIU_MIN);CHKERRMPI(ierr); 1194 #endif 1195 1196 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16) 1197 ierr = MPI_Op_free(&MPIU_SUM);CHKERRMPI(ierr); 1198 #endif 1199 1200 ierr = MPI_Type_free(&MPIU_2SCALAR);CHKERRMPI(ierr); 1201 ierr = MPI_Type_free(&MPIU_REAL_INT);CHKERRMPI(ierr); 1202 ierr = MPI_Type_free(&MPIU_SCALAR_INT);CHKERRMPI(ierr); 1203 #if defined(PETSC_USE_64BIT_INDICES) 1204 ierr = MPI_Type_free(&MPIU_2INT);CHKERRMPI(ierr); 1205 #endif 1206 ierr = MPI_Op_free(&MPIU_MAXSUM_OP);CHKERRMPI(ierr); 1207 PetscFunctionReturn(0); 1208 } 1209 1210 /*@C 1211 PetscFinalize - Checks for options to be called at the conclusion 1212 of the program. MPI_Finalize() is called only if the user had not 1213 called MPI_Init() before calling PetscInitialize(). 1214 1215 Collective on PETSC_COMM_WORLD 1216 1217 Options Database Keys: 1218 + -options_view - Calls PetscOptionsView() 1219 . -options_left - Prints unused options that remain in the database 1220 . -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 1221 . -mpidump - Calls PetscMPIDump() 1222 . -malloc_dump <optional filename> - Calls PetscMallocDump(), displays all memory allocated that has not been freed 1223 . -malloc_info - Prints total memory usage 1224 - -malloc_view <optional filename> - Prints list of all memory allocated and where 1225 1226 Level: beginner 1227 1228 Note: 1229 See PetscInitialize() for more general runtime options. 1230 1231 .seealso: PetscInitialize(), PetscOptionsView(), PetscMallocDump(), PetscMPIDump(), PetscEnd() 1232 @*/ 1233 PetscErrorCode PetscFinalize(void) 1234 { 1235 PetscErrorCode ierr; 1236 PetscMPIInt rank; 1237 PetscInt nopt; 1238 PetscBool flg1 = PETSC_FALSE,flg2 = PETSC_FALSE,flg3 = PETSC_FALSE; 1239 PetscBool flg; 1240 #if defined(PETSC_USE_LOG) 1241 char mname[PETSC_MAX_PATH_LEN]; 1242 #endif 1243 1244 if (!PetscInitializeCalled) { 1245 printf("PetscInitialize() must be called before PetscFinalize()\n"); 1246 return(PETSC_ERR_ARG_WRONGSTATE); 1247 } 1248 PetscFunctionBegin; 1249 ierr = PetscInfo(NULL,"PetscFinalize() called\n");CHKERRQ(ierr); 1250 1251 ierr = MPI_Comm_rank(PETSC_COMM_WORLD,&rank);CHKERRMPI(ierr); 1252 #if defined(PETSC_HAVE_ADIOS) 1253 ierr = adios_read_finalize_method(ADIOS_READ_METHOD_BP_AGGREGATE);CHKERRQ(ierr); 1254 ierr = adios_finalize(rank);CHKERRQ(ierr); 1255 #endif 1256 ierr = PetscOptionsHasName(NULL,NULL,"-citations",&flg);CHKERRQ(ierr); 1257 if (flg) { 1258 char *cits, filename[PETSC_MAX_PATH_LEN]; 1259 FILE *fd = PETSC_STDOUT; 1260 1261 ierr = PetscOptionsGetString(NULL,NULL,"-citations",filename,sizeof(filename),NULL);CHKERRQ(ierr); 1262 if (filename[0]) { 1263 ierr = PetscFOpen(PETSC_COMM_WORLD,filename,"w",&fd);CHKERRQ(ierr); 1264 } 1265 ierr = PetscSegBufferGet(PetscCitationsList,1,&cits);CHKERRQ(ierr); 1266 cits[0] = 0; 1267 ierr = PetscSegBufferExtractAlloc(PetscCitationsList,&cits);CHKERRQ(ierr); 1268 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"If you publish results based on this computation please cite the following:\n");CHKERRQ(ierr); 1269 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr); 1270 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"%s",cits);CHKERRQ(ierr); 1271 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr); 1272 ierr = PetscFClose(PETSC_COMM_WORLD,fd);CHKERRQ(ierr); 1273 ierr = PetscFree(cits);CHKERRQ(ierr); 1274 } 1275 ierr = PetscSegBufferDestroy(&PetscCitationsList);CHKERRQ(ierr); 1276 1277 #if defined(PETSC_HAVE_SSL) && defined(PETSC_USE_SOCKET_VIEWER) 1278 /* TextBelt is run for testing purposes only, please do not use this feature often */ 1279 { 1280 PetscInt nmax = 2; 1281 char **buffs; 1282 ierr = PetscMalloc1(2,&buffs);CHKERRQ(ierr); 1283 ierr = PetscOptionsGetStringArray(NULL,NULL,"-textbelt",buffs,&nmax,&flg1);CHKERRQ(ierr); 1284 if (flg1) { 1285 if (!nmax) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_USER,"-textbelt requires either the phone number or number,\"message\""); 1286 if (nmax == 1) { 1287 ierr = PetscMalloc1(128,&buffs[1]);CHKERRQ(ierr); 1288 ierr = PetscGetProgramName(buffs[1],32);CHKERRQ(ierr); 1289 ierr = PetscStrcat(buffs[1]," has completed");CHKERRQ(ierr); 1290 } 1291 ierr = PetscTextBelt(PETSC_COMM_WORLD,buffs[0],buffs[1],NULL);CHKERRQ(ierr); 1292 ierr = PetscFree(buffs[0]);CHKERRQ(ierr); 1293 ierr = PetscFree(buffs[1]);CHKERRQ(ierr); 1294 } 1295 ierr = PetscFree(buffs);CHKERRQ(ierr); 1296 } 1297 { 1298 PetscInt nmax = 2; 1299 char **buffs; 1300 ierr = PetscMalloc1(2,&buffs);CHKERRQ(ierr); 1301 ierr = PetscOptionsGetStringArray(NULL,NULL,"-tellmycell",buffs,&nmax,&flg1);CHKERRQ(ierr); 1302 if (flg1) { 1303 if (!nmax) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_USER,"-tellmycell requires either the phone number or number,\"message\""); 1304 if (nmax == 1) { 1305 ierr = PetscMalloc1(128,&buffs[1]);CHKERRQ(ierr); 1306 ierr = PetscGetProgramName(buffs[1],32);CHKERRQ(ierr); 1307 ierr = PetscStrcat(buffs[1]," has completed");CHKERRQ(ierr); 1308 } 1309 ierr = PetscTellMyCell(PETSC_COMM_WORLD,buffs[0],buffs[1],NULL);CHKERRQ(ierr); 1310 ierr = PetscFree(buffs[0]);CHKERRQ(ierr); 1311 ierr = PetscFree(buffs[1]);CHKERRQ(ierr); 1312 } 1313 ierr = PetscFree(buffs);CHKERRQ(ierr); 1314 } 1315 #endif 1316 1317 #if defined(PETSC_SERIALIZE_FUNCTIONS) 1318 ierr = PetscFPTDestroy();CHKERRQ(ierr); 1319 #endif 1320 1321 #if defined(PETSC_HAVE_SAWS) 1322 flg = PETSC_FALSE; 1323 ierr = PetscOptionsGetBool(NULL,NULL,"-saw_options",&flg,NULL);CHKERRQ(ierr); 1324 if (flg) { 1325 ierr = PetscOptionsSAWsDestroy();CHKERRQ(ierr); 1326 } 1327 #endif 1328 1329 #if defined(PETSC_HAVE_X) 1330 flg1 = PETSC_FALSE; 1331 ierr = PetscOptionsGetBool(NULL,NULL,"-x_virtual",&flg1,NULL);CHKERRQ(ierr); 1332 if (flg1) { 1333 /* this is a crude hack, but better than nothing */ 1334 ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 Xvfb","r",NULL);CHKERRQ(ierr); 1335 } 1336 #endif 1337 1338 #if !defined(PETSC_HAVE_THREADSAFETY) 1339 ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_info",&flg2,NULL);CHKERRQ(ierr); 1340 if (!flg2) { 1341 flg2 = PETSC_FALSE; 1342 ierr = PetscOptionsGetBool(NULL,NULL,"-memory_view",&flg2,NULL);CHKERRQ(ierr); 1343 } 1344 if (flg2) { 1345 ierr = PetscMemoryView(PETSC_VIEWER_STDOUT_WORLD,"Summary of Memory Usage in PETSc\n");CHKERRQ(ierr); 1346 } 1347 #endif 1348 1349 #if defined(PETSC_USE_LOG) 1350 flg1 = PETSC_FALSE; 1351 ierr = PetscOptionsGetBool(NULL,NULL,"-get_total_flops",&flg1,NULL);CHKERRQ(ierr); 1352 if (flg1) { 1353 PetscLogDouble flops = 0; 1354 ierr = MPI_Reduce(&petsc_TotalFlops,&flops,1,MPI_DOUBLE,MPI_SUM,0,PETSC_COMM_WORLD);CHKERRMPI(ierr); 1355 ierr = PetscPrintf(PETSC_COMM_WORLD,"Total flops over all processors %g\n",flops);CHKERRQ(ierr); 1356 } 1357 #endif 1358 1359 #if defined(PETSC_USE_LOG) 1360 #if defined(PETSC_HAVE_MPE) 1361 mname[0] = 0; 1362 ierr = PetscOptionsGetString(NULL,NULL,"-log_mpe",mname,sizeof(mname),&flg1);CHKERRQ(ierr); 1363 if (flg1) { 1364 if (mname[0]) {ierr = PetscLogMPEDump(mname);CHKERRQ(ierr);} 1365 else {ierr = PetscLogMPEDump(0);CHKERRQ(ierr);} 1366 } 1367 #endif 1368 #endif 1369 1370 /* 1371 Free all objects registered with PetscObjectRegisterDestroy() such as PETSC_VIEWER_XXX_(). 1372 */ 1373 ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr); 1374 1375 #if defined(PETSC_USE_LOG) 1376 ierr = PetscOptionsPushGetViewerOff(PETSC_FALSE);CHKERRQ(ierr); 1377 ierr = PetscLogViewFromOptions();CHKERRQ(ierr); 1378 ierr = PetscOptionsPopGetViewerOff();CHKERRQ(ierr); 1379 1380 mname[0] = 0; 1381 ierr = PetscOptionsGetString(NULL,NULL,"-log_summary",mname,sizeof(mname),&flg1);CHKERRQ(ierr); 1382 if (flg1) { 1383 PetscViewer viewer; 1384 ierr = (*PetscHelpPrintf)(PETSC_COMM_WORLD,"\n\n WARNING: -log_summary is being deprecated; switch to -log_view\n\n\n");CHKERRQ(ierr); 1385 if (mname[0]) { 1386 ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr); 1387 ierr = PetscLogView(viewer);CHKERRQ(ierr); 1388 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1389 } else { 1390 viewer = PETSC_VIEWER_STDOUT_WORLD; 1391 ierr = PetscViewerPushFormat(viewer,PETSC_VIEWER_DEFAULT);CHKERRQ(ierr); 1392 ierr = PetscLogView(viewer);CHKERRQ(ierr); 1393 ierr = PetscViewerPopFormat(viewer);CHKERRQ(ierr); 1394 } 1395 } 1396 1397 /* 1398 Free any objects created by the last block of code. 1399 */ 1400 ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr); 1401 1402 mname[0] = 0; 1403 ierr = PetscOptionsGetString(NULL,NULL,"-log_all",mname,sizeof(mname),&flg1);CHKERRQ(ierr); 1404 ierr = PetscOptionsGetString(NULL,NULL,"-log",mname,sizeof(mname),&flg2);CHKERRQ(ierr); 1405 if (flg1 || flg2) {ierr = PetscLogDump(mname);CHKERRQ(ierr);} 1406 #endif 1407 1408 ierr = PetscStackDestroy();CHKERRQ(ierr); 1409 1410 flg1 = PETSC_FALSE; 1411 ierr = PetscOptionsGetBool(NULL,NULL,"-no_signal_handler",&flg1,NULL);CHKERRQ(ierr); 1412 if (!flg1) { ierr = PetscPopSignalHandler();CHKERRQ(ierr);} 1413 flg1 = PETSC_FALSE; 1414 ierr = PetscOptionsGetBool(NULL,NULL,"-mpidump",&flg1,NULL);CHKERRQ(ierr); 1415 if (flg1) { 1416 ierr = PetscMPIDump(stdout);CHKERRQ(ierr); 1417 } 1418 flg1 = PETSC_FALSE; 1419 flg2 = PETSC_FALSE; 1420 /* preemptive call to avoid listing this option in options table as unused */ 1421 ierr = PetscOptionsHasName(NULL,NULL,"-malloc_dump",&flg1);CHKERRQ(ierr); 1422 ierr = PetscOptionsHasName(NULL,NULL,"-objects_dump",&flg1);CHKERRQ(ierr); 1423 ierr = PetscOptionsGetBool(NULL,NULL,"-options_view",&flg2,NULL);CHKERRQ(ierr); 1424 1425 if (flg2) { 1426 PetscViewer viewer; 1427 ierr = PetscViewerCreate(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr); 1428 ierr = PetscViewerSetType(viewer,PETSCVIEWERASCII);CHKERRQ(ierr); 1429 ierr = PetscOptionsView(NULL,viewer);CHKERRQ(ierr); 1430 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1431 } 1432 1433 /* to prevent PETSc -options_left from warning */ 1434 ierr = PetscOptionsHasName(NULL,NULL,"-nox",&flg1);CHKERRQ(ierr); 1435 ierr = PetscOptionsHasName(NULL,NULL,"-nox_warning",&flg1);CHKERRQ(ierr); 1436 1437 flg3 = PETSC_FALSE; /* default value is required */ 1438 ierr = PetscOptionsGetBool(NULL,NULL,"-options_left",&flg3,&flg1);CHKERRQ(ierr); 1439 if (PetscUnlikelyDebug(!flg1)) flg3 = PETSC_TRUE; 1440 if (flg3) { 1441 if (!flg2 && flg1) { /* have not yet printed the options */ 1442 PetscViewer viewer; 1443 ierr = PetscViewerCreate(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr); 1444 ierr = PetscViewerSetType(viewer,PETSCVIEWERASCII);CHKERRQ(ierr); 1445 ierr = PetscOptionsView(NULL,viewer);CHKERRQ(ierr); 1446 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1447 } 1448 ierr = PetscOptionsAllUsed(NULL,&nopt);CHKERRQ(ierr); 1449 if (nopt) { 1450 ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! There are options you set that were not used!\n");CHKERRQ(ierr); 1451 ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! could be spelling mistake, etc!\n");CHKERRQ(ierr); 1452 if (nopt == 1) { 1453 ierr = PetscPrintf(PETSC_COMM_WORLD,"There is one unused database option. It is:\n");CHKERRQ(ierr); 1454 } else { 1455 ierr = PetscPrintf(PETSC_COMM_WORLD,"There are %D unused database options. They are:\n",nopt);CHKERRQ(ierr); 1456 } 1457 } else if (flg3 && flg1) { 1458 ierr = PetscPrintf(PETSC_COMM_WORLD,"There are no unused options.\n");CHKERRQ(ierr); 1459 } 1460 ierr = PetscOptionsLeft(NULL);CHKERRQ(ierr); 1461 } 1462 1463 #if defined(PETSC_HAVE_SAWS) 1464 if (!PetscGlobalRank) { 1465 ierr = PetscStackSAWsViewOff();CHKERRQ(ierr); 1466 PetscStackCallSAWs(SAWs_Finalize,()); 1467 } 1468 #endif 1469 1470 #if defined(PETSC_USE_LOG) 1471 /* 1472 List all objects the user may have forgot to free 1473 */ 1474 if (PetscObjectsLog) { 1475 ierr = PetscOptionsHasName(NULL,NULL,"-objects_dump",&flg1);CHKERRQ(ierr); 1476 if (flg1) { 1477 MPI_Comm local_comm; 1478 char string[64]; 1479 1480 ierr = PetscOptionsGetString(NULL,NULL,"-objects_dump",string,sizeof(string),NULL);CHKERRQ(ierr); 1481 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRMPI(ierr); 1482 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1483 ierr = PetscObjectsDump(stdout,(string[0] == 'a') ? PETSC_TRUE : PETSC_FALSE);CHKERRQ(ierr); 1484 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1485 ierr = MPI_Comm_free(&local_comm);CHKERRMPI(ierr); 1486 } 1487 } 1488 #endif 1489 1490 #if defined(PETSC_USE_LOG) 1491 PetscObjectsCounts = 0; 1492 PetscObjectsMaxCounts = 0; 1493 ierr = PetscFree(PetscObjects);CHKERRQ(ierr); 1494 #endif 1495 1496 /* 1497 Destroy any packages that registered a finalize 1498 */ 1499 ierr = PetscRegisterFinalizeAll();CHKERRQ(ierr); 1500 1501 #if defined(PETSC_USE_LOG) 1502 ierr = PetscLogFinalize();CHKERRQ(ierr); 1503 #endif 1504 1505 /* 1506 Print PetscFunctionLists that have not been properly freed 1507 1508 ierr = PetscFunctionListPrintAll();CHKERRQ(ierr); 1509 */ 1510 1511 if (petsc_history) { 1512 ierr = PetscCloseHistoryFile(&petsc_history);CHKERRQ(ierr); 1513 petsc_history = NULL; 1514 } 1515 ierr = PetscOptionsHelpPrintedDestroy(&PetscOptionsHelpPrintedSingleton);CHKERRQ(ierr); 1516 ierr = PetscInfoDestroy();CHKERRQ(ierr); 1517 1518 #if !defined(PETSC_HAVE_THREADSAFETY) 1519 if (!(PETSC_RUNNING_ON_VALGRIND)) { 1520 char fname[PETSC_MAX_PATH_LEN]; 1521 char sname[PETSC_MAX_PATH_LEN]; 1522 FILE *fd; 1523 int err; 1524 1525 flg2 = PETSC_FALSE; 1526 flg3 = PETSC_FALSE; 1527 if (PetscDefined(USE_DEBUG)) {ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_test",&flg2,NULL);CHKERRQ(ierr);} 1528 ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_debug",&flg3,NULL);CHKERRQ(ierr); 1529 fname[0] = 0; 1530 ierr = PetscOptionsGetString(NULL,NULL,"-malloc_dump",fname,sizeof(fname),&flg1);CHKERRQ(ierr); 1531 if (flg1 && fname[0]) { 1532 1533 PetscSNPrintf(sname,sizeof(sname),"%s_%d",fname,rank); 1534 fd = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname); 1535 ierr = PetscMallocDump(fd);CHKERRQ(ierr); 1536 err = fclose(fd); 1537 if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file"); 1538 } else if (flg1 || flg2 || flg3) { 1539 MPI_Comm local_comm; 1540 1541 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRMPI(ierr); 1542 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1543 ierr = PetscMallocDump(stdout);CHKERRQ(ierr); 1544 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1545 ierr = MPI_Comm_free(&local_comm);CHKERRMPI(ierr); 1546 } 1547 fname[0] = 0; 1548 ierr = PetscOptionsGetString(NULL,NULL,"-malloc_view",fname,sizeof(fname),&flg1);CHKERRQ(ierr); 1549 if (flg1 && fname[0]) { 1550 1551 PetscSNPrintf(sname,sizeof(sname),"%s_%d",fname,rank); 1552 fd = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname); 1553 ierr = PetscMallocView(fd);CHKERRQ(ierr); 1554 err = fclose(fd); 1555 if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file"); 1556 } else if (flg1) { 1557 MPI_Comm local_comm; 1558 1559 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRMPI(ierr); 1560 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1561 ierr = PetscMallocView(stdout);CHKERRQ(ierr); 1562 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1563 ierr = MPI_Comm_free(&local_comm);CHKERRMPI(ierr); 1564 } 1565 } 1566 #endif 1567 1568 /* 1569 Close any open dynamic libraries 1570 */ 1571 ierr = PetscFinalize_DynamicLibraries();CHKERRQ(ierr); 1572 1573 /* Can be destroyed only after all the options are used */ 1574 ierr = PetscOptionsDestroyDefault();CHKERRQ(ierr); 1575 1576 PetscGlobalArgc = 0; 1577 PetscGlobalArgs = NULL; 1578 1579 #if defined(PETSC_HAVE_KOKKOS) 1580 if (PetscBeganKokkos) { 1581 ierr = PetscKokkosFinalize_Private();CHKERRQ(ierr); 1582 PetscBeganKokkos = PETSC_FALSE; 1583 PetscKokkosInitialized = PETSC_FALSE; 1584 } 1585 #endif 1586 1587 #if defined(PETSC_HAVE_NVSHMEM) 1588 if (PetscBeganNvshmem) { 1589 ierr = PetscNvshmemFinalize();CHKERRQ(ierr); 1590 PetscBeganNvshmem = PETSC_FALSE; 1591 } 1592 #endif 1593 1594 #if defined(PETSC_HAVE_CUDA) 1595 if (PetscDefaultCudaStream) {cudaError_t cerr = cudaStreamDestroy(PetscDefaultCudaStream);CHKERRCUDA(cerr);} 1596 if (petsc_gputimer_begin) { 1597 cudaError_t cerr = cudaEventDestroy(petsc_gputimer_begin);CHKERRCUDA(cerr); 1598 } 1599 if (petsc_gputimer_end) { 1600 cudaError_t cerr = cudaEventDestroy(petsc_gputimer_end);CHKERRCUDA(cerr); 1601 } 1602 #endif 1603 1604 #if defined(PETSC_HAVE_HIP) 1605 if (PetscDefaultHipStream) {hipError_t cerr = hipStreamDestroy(PetscDefaultHipStream);CHKERRHIP(cerr);} 1606 if (petsc_gputimer_begin) { 1607 hipError_t cerr = hipEventDestroy(petsc_gputimer_begin);CHKERRHIP(cerr); 1608 } 1609 if (petsc_gputimer_end) { 1610 hipError_t cerr = hipEventDestroy(petsc_gputimer_end);CHKERRHIP(cerr); 1611 } 1612 #endif 1613 1614 ierr = PetscFreeMPIResources();CHKERRQ(ierr); 1615 1616 /* 1617 Destroy any known inner MPI_Comm's and attributes pointing to them 1618 Note this will not destroy any new communicators the user has created. 1619 1620 If all PETSc objects were not destroyed those left over objects will have hanging references to 1621 the MPI_Comms that were freed; but that is ok because those PETSc objects will never be used again 1622 */ 1623 { 1624 PetscCommCounter *counter; 1625 PetscMPIInt flg; 1626 MPI_Comm icomm; 1627 union {MPI_Comm comm; void *ptr;} ucomm; 1628 ierr = MPI_Comm_get_attr(PETSC_COMM_SELF,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRMPI(ierr); 1629 if (flg) { 1630 icomm = ucomm.comm; 1631 ierr = MPI_Comm_get_attr(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRMPI(ierr); 1632 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory"); 1633 1634 ierr = MPI_Comm_delete_attr(PETSC_COMM_SELF,Petsc_InnerComm_keyval);CHKERRMPI(ierr); 1635 ierr = MPI_Comm_delete_attr(icomm,Petsc_Counter_keyval);CHKERRMPI(ierr); 1636 ierr = MPI_Comm_free(&icomm);CHKERRMPI(ierr); 1637 } 1638 ierr = MPI_Comm_get_attr(PETSC_COMM_WORLD,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRMPI(ierr); 1639 if (flg) { 1640 icomm = ucomm.comm; 1641 ierr = MPI_Comm_get_attr(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRMPI(ierr); 1642 if (!flg) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory"); 1643 1644 ierr = MPI_Comm_delete_attr(PETSC_COMM_WORLD,Petsc_InnerComm_keyval);CHKERRMPI(ierr); 1645 ierr = MPI_Comm_delete_attr(icomm,Petsc_Counter_keyval);CHKERRMPI(ierr); 1646 ierr = MPI_Comm_free(&icomm);CHKERRMPI(ierr); 1647 } 1648 } 1649 1650 ierr = MPI_Comm_free_keyval(&Petsc_Counter_keyval);CHKERRMPI(ierr); 1651 ierr = MPI_Comm_free_keyval(&Petsc_InnerComm_keyval);CHKERRMPI(ierr); 1652 ierr = MPI_Comm_free_keyval(&Petsc_OuterComm_keyval);CHKERRMPI(ierr); 1653 ierr = MPI_Comm_free_keyval(&Petsc_ShmComm_keyval);CHKERRMPI(ierr); 1654 1655 ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockOpen);CHKERRQ(ierr); 1656 ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockStdout);CHKERRQ(ierr); 1657 ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockStderr);CHKERRQ(ierr); 1658 ierr = PetscSpinlockDestroy(&PetscCommSpinLock);CHKERRQ(ierr); 1659 1660 if (PetscBeganMPI) { 1661 #if defined(PETSC_HAVE_MPI_FINALIZED) 1662 PetscMPIInt flag; 1663 ierr = MPI_Finalized(&flag);CHKERRMPI(ierr); 1664 if (flag) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_LIB,"MPI_Finalize() has already been called, even though MPI_Init() was called by PetscInitialize()"); 1665 #endif 1666 ierr = MPI_Finalize();CHKERRMPI(ierr); 1667 } 1668 /* 1669 1670 Note: In certain cases PETSC_COMM_WORLD is never MPI_Comm_free()ed because 1671 the communicator has some outstanding requests on it. Specifically if the 1672 flag PETSC_HAVE_BROKEN_REQUEST_FREE is set (for IBM MPI implementation). See 1673 src/vec/utils/vpscat.c. Due to this the memory allocated in PetscCommDuplicate() 1674 is never freed as it should be. Thus one may obtain messages of the form 1675 [ 1] 8 bytes PetscCommDuplicate() line 645 in src/sys/mpiu.c indicating the 1676 memory was not freed. 1677 1678 */ 1679 ierr = PetscMallocClear();CHKERRQ(ierr); 1680 1681 PetscErrorHandlingInitialized = PETSC_FALSE; 1682 PetscInitializeCalled = PETSC_FALSE; 1683 PetscFinalizeCalled = PETSC_TRUE; 1684 #if defined(PETSC_USE_GCOV) 1685 /* 1686 flush gcov, otherwise during CI the flushing continues into the next pipeline resulting in git not being able to delete directories since the 1687 gcov files are still being added to the directories as git tries to remove the directories. 1688 */ 1689 __gcov_flush(); 1690 #endif 1691 PetscFunctionReturn(0); 1692 } 1693 1694 #if defined(PETSC_MISSING_LAPACK_lsame_) 1695 PETSC_EXTERN int lsame_(char *a,char *b) 1696 { 1697 if (*a == *b) return 1; 1698 if (*a + 32 == *b) return 1; 1699 if (*a - 32 == *b) return 1; 1700 return 0; 1701 } 1702 #endif 1703 1704 #if defined(PETSC_MISSING_LAPACK_lsame) 1705 PETSC_EXTERN int lsame(char *a,char *b) 1706 { 1707 if (*a == *b) return 1; 1708 if (*a + 32 == *b) return 1; 1709 if (*a - 32 == *b) return 1; 1710 return 0; 1711 } 1712 #endif 1713