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 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 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 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 771 Level: beginner 772 773 Notes: 774 If for some reason you must call MPI_Init() separately, call 775 it before PetscInitialize(). 776 777 Fortran Version: 778 In Fortran this routine has the format 779 $ call PetscInitialize(file,ierr) 780 781 + ierr - error return code 782 - file - [optional] PETSc database file, also checks ~/.petscrc, .petscrc and petscrc. 783 Use PETSC_NULL_CHARACTER to not check for code specific file. 784 Use -skip_petscrc in the code specific file (or command line) to skip ~/.petscrc, .petscrc and petscrc files. 785 786 Important Fortran Note: 787 In Fortran, you MUST use PETSC_NULL_CHARACTER to indicate a 788 null character string; you CANNOT just use NULL as 789 in the C version. See Users-Manual: ch_fortran for details. 790 791 If your main program is C but you call Fortran code that also uses PETSc you need to call PetscInitializeFortran() soon after 792 calling PetscInitialize(). 793 794 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscInitializeNoArguments() 795 796 @*/ 797 PetscErrorCode PetscInitialize(int *argc,char ***args,const char file[],const char help[]) 798 { 799 PetscErrorCode ierr; 800 PetscMPIInt flag, size; 801 PetscBool flg = PETSC_TRUE; 802 char hostname[256]; 803 804 PetscFunctionBegin; 805 if (PetscInitializeCalled) PetscFunctionReturn(0); 806 /* 807 The checking over compatible runtime libraries is complicated by the MPI ABI initiative 808 https://wiki.mpich.org/mpich/index.php/ABI_Compatibility_Initiative which started with 809 MPICH v3.1 (Released Feburary 2014) 810 IBM MPI v2.1 (December 2014) 811 Intel MPI Library v5.0 (2014) 812 Cray MPT v7.0.0 (June 2014) 813 As of July 31, 2017 the ABI number still appears to be 12, that is all of the versions 814 listed above and since that time are compatible. 815 816 Unfortunately the MPI ABI initiative has not defined a way to determine the ABI number 817 at compile time or runtime. Thus we will need to systematically track the allowed versions 818 and how they are represented in the mpi.h and MPI_Get_library_version() output in order 819 to perform the checking. 820 821 Currently we only check for pre MPI ABI versions (and packages that do not follow the MPI ABI). 822 823 Questions: 824 825 Should the checks for ABI incompatibility be only on the major version number below? 826 Presumably the output to stderr will be removed before a release. 827 */ 828 829 #if defined(PETSC_HAVE_MPI_GET_LIBRARY_VERSION) 830 { 831 char mpilibraryversion[MPI_MAX_LIBRARY_VERSION_STRING]; 832 PetscMPIInt mpilibraryversionlength; 833 ierr = MPI_Get_library_version(mpilibraryversion,&mpilibraryversionlength);if (ierr) return ierr; 834 /* check for MPICH versions before MPI ABI initiative */ 835 #if defined(MPICH_VERSION) 836 #if MPICH_NUMVERSION < 30100000 837 { 838 char *ver,*lf; 839 flg = PETSC_FALSE; 840 ierr = PetscStrstr(mpilibraryversion,"MPICH Version:",&ver);if (ierr) return ierr; 841 if (ver) { 842 ierr = PetscStrchr(ver,'\n',&lf);if (ierr) return ierr; 843 if (lf) { 844 *lf = 0; 845 ierr = PetscStrendswith(ver,MPICH_VERSION,&flg);if (ierr) return ierr; 846 } 847 } 848 if (!flg) { 849 fprintf(stderr,"PETSc Error --- MPICH library version \n%s does not match what PETSc was compiled with %s, aborting\n",mpilibraryversion,MPICH_VERSION); 850 return PETSC_ERR_MPI_LIB_INCOMP; 851 } 852 } 853 #endif 854 /* check for OpenMPI version, it is not part of the MPI ABI initiative (is it part of another initiative that needs to be handled?) */ 855 #elif defined(OMPI_MAJOR_VERSION) 856 { 857 char *ver,bs[MPI_MAX_LIBRARY_VERSION_STRING],*bsf; 858 flg = PETSC_FALSE; 859 #define PSTRSZ 2 860 char ompistr1[PSTRSZ][MPI_MAX_LIBRARY_VERSION_STRING] = {"Open MPI","FUJITSU MPI"}; 861 char ompistr2[PSTRSZ][MPI_MAX_LIBRARY_VERSION_STRING] = {"v","Library "}; 862 int i; 863 for (i=0; i<PSTRSZ; i++) { 864 ierr = PetscStrstr(mpilibraryversion,ompistr1[i],&ver);if (ierr) return ierr; 865 if (ver) { 866 PetscSNPrintf(bs,MPI_MAX_LIBRARY_VERSION_STRING,"%s%d.%d",ompistr2[i],OMPI_MAJOR_VERSION,OMPI_MINOR_VERSION); 867 ierr = PetscStrstr(ver,bs,&bsf);if (ierr) return ierr; 868 if (bsf) flg = PETSC_TRUE; 869 break; 870 } 871 } 872 if (!flg) { 873 fprintf(stderr,"PETSc Error --- Open MPI library version \n%s does not match what PETSc was compiled with %d.%d, aborting\n",mpilibraryversion,OMPI_MAJOR_VERSION,OMPI_MINOR_VERSION); 874 return PETSC_ERR_MPI_LIB_INCOMP; 875 } 876 } 877 #endif 878 } 879 #endif 880 881 #if defined(PETSC_HAVE_DLSYM) 882 { 883 PetscInt cnt = 0; 884 /* 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 */ 885 if (dlsym(RTLD_DEFAULT,"ompi_mpi_init")) cnt++; 886 if (dlsym(RTLD_DEFAULT,"MPL_exit")) cnt++; 887 if (cnt > 1) { 888 fprintf(stderr,"PETSc Error --- Application was linked against both OpenMPI and MPICH based MPI libraries and will not run correctly\n"); 889 return PETSC_ERR_MPI_LIB_INCOMP; 890 } 891 } 892 #endif 893 894 /* these must be initialized in a routine, not as a constant declaration*/ 895 PETSC_STDOUT = stdout; 896 PETSC_STDERR = stderr; 897 898 /*CHKERRQ can be used from now */ 899 PetscErrorHandlingInitialized = PETSC_TRUE; 900 901 /* on Windows - set printf to default to printing 2 digit exponents */ 902 #if defined(PETSC_HAVE__SET_OUTPUT_FORMAT) 903 _set_output_format(_TWO_DIGIT_EXPONENT); 904 #endif 905 906 ierr = PetscOptionsCreateDefault();CHKERRQ(ierr); 907 908 /* 909 We initialize the program name here (before MPI_Init()) because MPICH has a bug in 910 it that it sets args[0] on all processors to be args[0] on the first processor. 911 */ 912 if (argc && *argc) { 913 ierr = PetscSetProgramName(**args);CHKERRQ(ierr); 914 } else { 915 ierr = PetscSetProgramName("Unknown Name");CHKERRQ(ierr); 916 } 917 918 ierr = MPI_Initialized(&flag);CHKERRMPI(ierr); 919 if (!flag) { 920 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"); 921 ierr = PetscPreMPIInit_Private();CHKERRQ(ierr); 922 #if defined(PETSC_HAVE_MPI_INIT_THREAD) 923 { 924 PetscMPIInt provided; 925 ierr = MPI_Init_thread(argc,args,PETSC_MPI_THREAD_REQUIRED,&provided);CHKERRMPI(ierr); 926 } 927 #else 928 ierr = MPI_Init(argc,args);CHKERRMPI(ierr); 929 #endif 930 PetscBeganMPI = PETSC_TRUE; 931 } 932 933 if (argc && args) { 934 PetscGlobalArgc = *argc; 935 PetscGlobalArgs = *args; 936 } 937 PetscFinalizeCalled = PETSC_FALSE; 938 ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockOpen);CHKERRQ(ierr); 939 ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockStdout);CHKERRQ(ierr); 940 ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockStderr);CHKERRQ(ierr); 941 ierr = PetscSpinlockCreate(&PetscCommSpinLock);CHKERRQ(ierr); 942 943 if (PETSC_COMM_WORLD == MPI_COMM_NULL) PETSC_COMM_WORLD = MPI_COMM_WORLD; 944 ierr = MPI_Comm_set_errhandler(PETSC_COMM_WORLD,MPI_ERRORS_RETURN);CHKERRMPI(ierr); 945 946 if (PETSC_MPI_ERROR_CLASS == MPI_ERR_LASTCODE) { 947 ierr = MPI_Add_error_class(&PETSC_MPI_ERROR_CLASS);CHKERRMPI(ierr); 948 ierr = MPI_Add_error_code(PETSC_MPI_ERROR_CLASS,&PETSC_MPI_ERROR_CODE);CHKERRMPI(ierr); 949 } 950 951 /* Done after init due to a bug in MPICH-GM? */ 952 ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr); 953 954 ierr = MPI_Comm_rank(MPI_COMM_WORLD,&PetscGlobalRank);CHKERRMPI(ierr); 955 ierr = MPI_Comm_size(MPI_COMM_WORLD,&PetscGlobalSize);CHKERRMPI(ierr); 956 957 MPIU_BOOL = MPI_INT; 958 MPIU_ENUM = MPI_INT; 959 MPIU_FORTRANADDR = (sizeof(void*) == sizeof(int)) ? MPI_INT : MPIU_INT64; 960 if (sizeof(size_t) == sizeof(unsigned)) MPIU_SIZE_T = MPI_UNSIGNED; 961 else if (sizeof(size_t) == sizeof(unsigned long)) MPIU_SIZE_T = MPI_UNSIGNED_LONG; 962 #if defined(PETSC_SIZEOF_LONG_LONG) 963 else if (sizeof(size_t) == sizeof(unsigned long long)) MPIU_SIZE_T = MPI_UNSIGNED_LONG_LONG; 964 #endif 965 else {(*PetscErrorPrintf)("PetscInitialize: Could not find MPI type for size_t\n"); return PETSC_ERR_SUP_SYS;} 966 967 /* 968 Initialized the global complex variable; this is because with 969 shared libraries the constructors for global variables 970 are not called; at least on IRIX. 971 */ 972 #if defined(PETSC_HAVE_COMPLEX) 973 { 974 #if defined(PETSC_CLANGUAGE_CXX) 975 PetscComplex ic(0.0,1.0); 976 PETSC_i = ic; 977 #else 978 PETSC_i = _Complex_I; 979 #endif 980 } 981 #endif /* PETSC_HAVE_COMPLEX */ 982 983 /* 984 Create the PETSc MPI reduction operator that sums of the first 985 half of the entries and maxes the second half. 986 */ 987 ierr = MPI_Op_create(MPIU_MaxSum_Local,1,&MPIU_MAXSUM_OP);CHKERRMPI(ierr); 988 989 #if defined(PETSC_USE_REAL___FLOAT128) 990 ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU___FLOAT128);CHKERRMPI(ierr); 991 ierr = MPI_Type_commit(&MPIU___FLOAT128);CHKERRMPI(ierr); 992 #if defined(PETSC_HAVE_COMPLEX) 993 ierr = MPI_Type_contiguous(4,MPI_DOUBLE,&MPIU___COMPLEX128);CHKERRMPI(ierr); 994 ierr = MPI_Type_commit(&MPIU___COMPLEX128);CHKERRMPI(ierr); 995 #endif 996 ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRMPI(ierr); 997 ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRMPI(ierr); 998 #elif defined(PETSC_USE_REAL___FP16) 999 ierr = MPI_Type_contiguous(2,MPI_CHAR,&MPIU___FP16);CHKERRMPI(ierr); 1000 ierr = MPI_Type_commit(&MPIU___FP16);CHKERRMPI(ierr); 1001 ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRMPI(ierr); 1002 ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRMPI(ierr); 1003 #endif 1004 1005 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16) 1006 ierr = MPI_Op_create(PetscSum_Local,1,&MPIU_SUM);CHKERRMPI(ierr); 1007 #endif 1008 1009 ierr = MPI_Type_contiguous(2,MPIU_SCALAR,&MPIU_2SCALAR);CHKERRMPI(ierr); 1010 ierr = MPI_Type_commit(&MPIU_2SCALAR);CHKERRMPI(ierr); 1011 1012 #if defined(PETSC_USE_64BIT_INDICES) 1013 ierr = MPI_Type_contiguous(2,MPIU_INT,&MPIU_2INT);CHKERRMPI(ierr); 1014 ierr = MPI_Type_commit(&MPIU_2INT);CHKERRMPI(ierr); 1015 #endif 1016 1017 /* 1018 Attributes to be set on PETSc communicators 1019 */ 1020 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_Counter_Attr_Delete_Fn,&Petsc_Counter_keyval,(void*)0);CHKERRMPI(ierr); 1021 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_InnerComm_Attr_Delete_Fn,&Petsc_InnerComm_keyval,(void*)0);CHKERRMPI(ierr); 1022 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_OuterComm_Attr_Delete_Fn,&Petsc_OuterComm_keyval,(void*)0);CHKERRMPI(ierr); 1023 ierr = MPI_Comm_create_keyval(MPI_COMM_NULL_COPY_FN,Petsc_ShmComm_Attr_Delete_Fn,&Petsc_ShmComm_keyval,(void*)0);CHKERRMPI(ierr); 1024 1025 /* 1026 Build the options database 1027 */ 1028 ierr = PetscOptionsInsert(NULL,argc,args,file);CHKERRQ(ierr); 1029 1030 /* call a second time so it can look in the options database */ 1031 ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr); 1032 1033 /* 1034 Check system options and print help 1035 */ 1036 ierr = PetscOptionsCheckInitial_Private(help);CHKERRQ(ierr); 1037 1038 ierr = PetscCitationsInitialize();CHKERRQ(ierr); 1039 1040 #if defined(PETSC_HAVE_SAWS) 1041 ierr = PetscInitializeSAWs(help);CHKERRQ(ierr); 1042 #endif 1043 1044 /* 1045 Load the dynamic libraries (on machines that support them), this registers all 1046 the solvers etc. (On non-dynamic machines this initializes the PetscDraw and PetscViewer classes) 1047 */ 1048 ierr = PetscInitialize_DynamicLibraries();CHKERRQ(ierr); 1049 1050 ierr = MPI_Comm_size(PETSC_COMM_WORLD,&size);CHKERRMPI(ierr); 1051 ierr = PetscInfo1(NULL,"PETSc successfully started: number of processors = %d\n",size);CHKERRQ(ierr); 1052 ierr = PetscGetHostName(hostname,256);CHKERRQ(ierr); 1053 ierr = PetscInfo1(NULL,"Running on machine: %s\n",hostname);CHKERRQ(ierr); 1054 #if defined(PETSC_HAVE_OPENMP) 1055 { 1056 PetscBool omp_view_flag; 1057 char *threads = getenv("OMP_NUM_THREADS"); 1058 1059 if (threads) { 1060 ierr = PetscInfo1(NULL,"Number of OpenMP threads %s (given by OMP_NUM_THREADS)\n",threads);CHKERRQ(ierr); 1061 (void) sscanf(threads, "%" PetscInt_FMT,&PetscNumOMPThreads); 1062 } else { 1063 #define NMAX 10000 1064 int i; 1065 PetscScalar *x; 1066 ierr = PetscMalloc1(NMAX,&x);CHKERRQ(ierr); 1067 #pragma omp parallel for 1068 for (i=0; i<NMAX; i++) { 1069 x[i] = 0.0; 1070 PetscNumOMPThreads = (PetscInt) omp_get_num_threads(); 1071 } 1072 ierr = PetscFree(x);CHKERRQ(ierr); 1073 ierr = PetscInfo1(NULL,"Number of OpenMP threads %D (number not set with OMP_NUM_THREADS, chosen by system)\n",PetscNumOMPThreads);CHKERRQ(ierr); 1074 } 1075 ierr = PetscOptionsBegin(PETSC_COMM_WORLD,NULL,"OpenMP options","Sys");CHKERRQ(ierr); 1076 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); 1077 ierr = PetscOptionsName("-omp_view","Display OpenMP number of threads",NULL,&omp_view_flag);CHKERRQ(ierr); 1078 ierr = PetscOptionsEnd();CHKERRQ(ierr); 1079 if (flg) { 1080 ierr = PetscInfo1(NULL,"Number of OpenMP theads %D (given by -omp_num_threads)\n",PetscNumOMPThreads);CHKERRQ(ierr); 1081 omp_set_num_threads((int)PetscNumOMPThreads); 1082 } 1083 if (omp_view_flag) { 1084 ierr = PetscPrintf(PETSC_COMM_WORLD,"OpenMP: number of threads %D\n",PetscNumOMPThreads);CHKERRQ(ierr); 1085 } 1086 } 1087 #endif 1088 1089 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32) 1090 /* 1091 Tell MPI about our own data representation converter, this would/should be used if extern32 is not supported by the MPI 1092 1093 Currently not used because it is not supported by MPICH. 1094 */ 1095 if (!PetscBinaryBigEndian()) { 1096 ierr = MPI_Register_datarep((char*)"petsc",PetscDataRep_read_conv_fn,PetscDataRep_write_conv_fn,PetscDataRep_extent_fn,NULL);CHKERRMPI(ierr); 1097 } 1098 #endif 1099 1100 /* 1101 Setup building of stack frames for all function calls 1102 */ 1103 #if defined(PETSC_USE_DEBUG) && !defined(PETSC_HAVE_THREADSAFETY) 1104 ierr = PetscStackCreate();CHKERRQ(ierr); 1105 #endif 1106 1107 #if defined(PETSC_SERIALIZE_FUNCTIONS) 1108 ierr = PetscFPTCreate(10000);CHKERRQ(ierr); 1109 #endif 1110 1111 #if defined(PETSC_HAVE_HWLOC) 1112 { 1113 PetscViewer viewer; 1114 ierr = PetscOptionsGetViewer(PETSC_COMM_WORLD,NULL,NULL,"-process_view",&viewer,NULL,&flg);CHKERRQ(ierr); 1115 if (flg) { 1116 ierr = PetscProcessPlacementView(viewer);CHKERRQ(ierr); 1117 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1118 } 1119 } 1120 #endif 1121 1122 flg = PETSC_TRUE; 1123 ierr = PetscOptionsGetBool(NULL,NULL,"-viewfromoptions",&flg,NULL);CHKERRQ(ierr); 1124 if (!flg) {ierr = PetscOptionsPushGetViewerOff(PETSC_TRUE);CHKERRQ(ierr);} 1125 1126 #if defined(PETSC_HAVE_ADIOS) 1127 ierr = adios_init_noxml(PETSC_COMM_WORLD);CHKERRQ(ierr); 1128 ierr = adios_declare_group(&Petsc_adios_group,"PETSc","",adios_stat_default);CHKERRQ(ierr); 1129 ierr = adios_select_method(Petsc_adios_group,"MPI","","");CHKERRQ(ierr); 1130 ierr = adios_read_init_method(ADIOS_READ_METHOD_BP,PETSC_COMM_WORLD,"");CHKERRQ(ierr); 1131 #endif 1132 1133 /* 1134 Set flag that we are completely initialized 1135 */ 1136 PetscInitializeCalled = PETSC_TRUE; 1137 1138 ierr = PetscOptionsHasName(NULL,NULL,"-python",&flg);CHKERRQ(ierr); 1139 if (flg) {ierr = PetscPythonInitialize(NULL,NULL);CHKERRQ(ierr);} 1140 PetscFunctionReturn(0); 1141 } 1142 1143 #if defined(PETSC_USE_LOG) 1144 PETSC_INTERN PetscObject *PetscObjects; 1145 PETSC_INTERN PetscInt PetscObjectsCounts; 1146 PETSC_INTERN PetscInt PetscObjectsMaxCounts; 1147 PETSC_INTERN PetscBool PetscObjectsLog; 1148 #endif 1149 1150 /* 1151 Frees all the MPI types and operations that PETSc may have created 1152 */ 1153 PetscErrorCode PetscFreeMPIResources(void) 1154 { 1155 PetscErrorCode ierr; 1156 1157 PetscFunctionBegin; 1158 #if defined(PETSC_USE_REAL___FLOAT128) 1159 ierr = MPI_Type_free(&MPIU___FLOAT128);CHKERRMPI(ierr); 1160 #if defined(PETSC_HAVE_COMPLEX) 1161 ierr = MPI_Type_free(&MPIU___COMPLEX128);CHKERRMPI(ierr); 1162 #endif 1163 ierr = MPI_Op_free(&MPIU_MAX);CHKERRMPI(ierr); 1164 ierr = MPI_Op_free(&MPIU_MIN);CHKERRMPI(ierr); 1165 #elif defined(PETSC_USE_REAL___FP16) 1166 ierr = MPI_Type_free(&MPIU___FP16);CHKERRMPI(ierr); 1167 ierr = MPI_Op_free(&MPIU_MAX);CHKERRMPI(ierr); 1168 ierr = MPI_Op_free(&MPIU_MIN);CHKERRMPI(ierr); 1169 #endif 1170 1171 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16) 1172 ierr = MPI_Op_free(&MPIU_SUM);CHKERRMPI(ierr); 1173 #endif 1174 1175 ierr = MPI_Type_free(&MPIU_2SCALAR);CHKERRMPI(ierr); 1176 #if defined(PETSC_USE_64BIT_INDICES) 1177 ierr = MPI_Type_free(&MPIU_2INT);CHKERRMPI(ierr); 1178 #endif 1179 ierr = MPI_Op_free(&MPIU_MAXSUM_OP);CHKERRMPI(ierr); 1180 PetscFunctionReturn(0); 1181 } 1182 1183 /*@C 1184 PetscFinalize - Checks for options to be called at the conclusion 1185 of the program. MPI_Finalize() is called only if the user had not 1186 called MPI_Init() before calling PetscInitialize(). 1187 1188 Collective on PETSC_COMM_WORLD 1189 1190 Options Database Keys: 1191 + -options_view - Calls PetscOptionsView() 1192 . -options_left - Prints unused options that remain in the database 1193 . -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 1194 . -mpidump - Calls PetscMPIDump() 1195 . -malloc_dump <optional filename> - Calls PetscMallocDump(), displays all memory allocated that has not been freed 1196 . -malloc_info - Prints total memory usage 1197 - -malloc_view <optional filename> - Prints list of all memory allocated and where 1198 1199 Level: beginner 1200 1201 Note: 1202 See PetscInitialize() for more general runtime options. 1203 1204 .seealso: PetscInitialize(), PetscOptionsView(), PetscMallocDump(), PetscMPIDump(), PetscEnd() 1205 @*/ 1206 PetscErrorCode PetscFinalize(void) 1207 { 1208 PetscErrorCode ierr; 1209 PetscMPIInt rank; 1210 PetscInt nopt; 1211 PetscBool flg1 = PETSC_FALSE,flg2 = PETSC_FALSE,flg3 = PETSC_FALSE; 1212 PetscBool flg; 1213 #if defined(PETSC_USE_LOG) 1214 char mname[PETSC_MAX_PATH_LEN]; 1215 #endif 1216 1217 if (!PetscInitializeCalled) { 1218 printf("PetscInitialize() must be called before PetscFinalize()\n"); 1219 return(PETSC_ERR_ARG_WRONGSTATE); 1220 } 1221 PetscFunctionBegin; 1222 ierr = PetscInfo(NULL,"PetscFinalize() called\n");CHKERRQ(ierr); 1223 1224 ierr = MPI_Comm_rank(PETSC_COMM_WORLD,&rank);CHKERRMPI(ierr); 1225 #if defined(PETSC_HAVE_ADIOS) 1226 ierr = adios_read_finalize_method(ADIOS_READ_METHOD_BP_AGGREGATE);CHKERRQ(ierr); 1227 ierr = adios_finalize(rank);CHKERRQ(ierr); 1228 #endif 1229 ierr = PetscOptionsHasName(NULL,NULL,"-citations",&flg);CHKERRQ(ierr); 1230 if (flg) { 1231 char *cits, filename[PETSC_MAX_PATH_LEN]; 1232 FILE *fd = PETSC_STDOUT; 1233 1234 ierr = PetscOptionsGetString(NULL,NULL,"-citations",filename,sizeof(filename),NULL);CHKERRQ(ierr); 1235 if (filename[0]) { 1236 ierr = PetscFOpen(PETSC_COMM_WORLD,filename,"w",&fd);CHKERRQ(ierr); 1237 } 1238 ierr = PetscSegBufferGet(PetscCitationsList,1,&cits);CHKERRQ(ierr); 1239 cits[0] = 0; 1240 ierr = PetscSegBufferExtractAlloc(PetscCitationsList,&cits);CHKERRQ(ierr); 1241 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"If you publish results based on this computation please cite the following:\n");CHKERRQ(ierr); 1242 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr); 1243 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"%s",cits);CHKERRQ(ierr); 1244 ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr); 1245 ierr = PetscFClose(PETSC_COMM_WORLD,fd);CHKERRQ(ierr); 1246 ierr = PetscFree(cits);CHKERRQ(ierr); 1247 } 1248 ierr = PetscSegBufferDestroy(&PetscCitationsList);CHKERRQ(ierr); 1249 1250 #if defined(PETSC_HAVE_SSL) && defined(PETSC_USE_SOCKET_VIEWER) 1251 /* TextBelt is run for testing purposes only, please do not use this feature often */ 1252 { 1253 PetscInt nmax = 2; 1254 char **buffs; 1255 ierr = PetscMalloc1(2,&buffs);CHKERRQ(ierr); 1256 ierr = PetscOptionsGetStringArray(NULL,NULL,"-textbelt",buffs,&nmax,&flg1);CHKERRQ(ierr); 1257 if (flg1) { 1258 if (!nmax) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_USER,"-textbelt requires either the phone number or number,\"message\""); 1259 if (nmax == 1) { 1260 ierr = PetscMalloc1(128,&buffs[1]);CHKERRQ(ierr); 1261 ierr = PetscGetProgramName(buffs[1],32);CHKERRQ(ierr); 1262 ierr = PetscStrcat(buffs[1]," has completed");CHKERRQ(ierr); 1263 } 1264 ierr = PetscTextBelt(PETSC_COMM_WORLD,buffs[0],buffs[1],NULL);CHKERRQ(ierr); 1265 ierr = PetscFree(buffs[0]);CHKERRQ(ierr); 1266 ierr = PetscFree(buffs[1]);CHKERRQ(ierr); 1267 } 1268 ierr = PetscFree(buffs);CHKERRQ(ierr); 1269 } 1270 { 1271 PetscInt nmax = 2; 1272 char **buffs; 1273 ierr = PetscMalloc1(2,&buffs);CHKERRQ(ierr); 1274 ierr = PetscOptionsGetStringArray(NULL,NULL,"-tellmycell",buffs,&nmax,&flg1);CHKERRQ(ierr); 1275 if (flg1) { 1276 if (!nmax) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_USER,"-tellmycell requires either the phone number or number,\"message\""); 1277 if (nmax == 1) { 1278 ierr = PetscMalloc1(128,&buffs[1]);CHKERRQ(ierr); 1279 ierr = PetscGetProgramName(buffs[1],32);CHKERRQ(ierr); 1280 ierr = PetscStrcat(buffs[1]," has completed");CHKERRQ(ierr); 1281 } 1282 ierr = PetscTellMyCell(PETSC_COMM_WORLD,buffs[0],buffs[1],NULL);CHKERRQ(ierr); 1283 ierr = PetscFree(buffs[0]);CHKERRQ(ierr); 1284 ierr = PetscFree(buffs[1]);CHKERRQ(ierr); 1285 } 1286 ierr = PetscFree(buffs);CHKERRQ(ierr); 1287 } 1288 #endif 1289 1290 #if defined(PETSC_SERIALIZE_FUNCTIONS) 1291 ierr = PetscFPTDestroy();CHKERRQ(ierr); 1292 #endif 1293 1294 #if defined(PETSC_HAVE_SAWS) 1295 flg = PETSC_FALSE; 1296 ierr = PetscOptionsGetBool(NULL,NULL,"-saw_options",&flg,NULL);CHKERRQ(ierr); 1297 if (flg) { 1298 ierr = PetscOptionsSAWsDestroy();CHKERRQ(ierr); 1299 } 1300 #endif 1301 1302 #if defined(PETSC_HAVE_X) 1303 flg1 = PETSC_FALSE; 1304 ierr = PetscOptionsGetBool(NULL,NULL,"-x_virtual",&flg1,NULL);CHKERRQ(ierr); 1305 if (flg1) { 1306 /* this is a crude hack, but better than nothing */ 1307 ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 Xvfb","r",NULL);CHKERRQ(ierr); 1308 } 1309 #endif 1310 1311 #if !defined(PETSC_HAVE_THREADSAFETY) 1312 ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_info",&flg2,NULL);CHKERRQ(ierr); 1313 if (!flg2) { 1314 flg2 = PETSC_FALSE; 1315 ierr = PetscOptionsGetBool(NULL,NULL,"-memory_view",&flg2,NULL);CHKERRQ(ierr); 1316 } 1317 if (flg2) { 1318 ierr = PetscMemoryView(PETSC_VIEWER_STDOUT_WORLD,"Summary of Memory Usage in PETSc\n");CHKERRQ(ierr); 1319 } 1320 #endif 1321 1322 #if defined(PETSC_USE_LOG) 1323 flg1 = PETSC_FALSE; 1324 ierr = PetscOptionsGetBool(NULL,NULL,"-get_total_flops",&flg1,NULL);CHKERRQ(ierr); 1325 if (flg1) { 1326 PetscLogDouble flops = 0; 1327 ierr = MPI_Reduce(&petsc_TotalFlops,&flops,1,MPI_DOUBLE,MPI_SUM,0,PETSC_COMM_WORLD);CHKERRMPI(ierr); 1328 ierr = PetscPrintf(PETSC_COMM_WORLD,"Total flops over all processors %g\n",flops);CHKERRQ(ierr); 1329 } 1330 #endif 1331 1332 1333 #if defined(PETSC_USE_LOG) 1334 #if defined(PETSC_HAVE_MPE) 1335 mname[0] = 0; 1336 ierr = PetscOptionsGetString(NULL,NULL,"-log_mpe",mname,sizeof(mname),&flg1);CHKERRQ(ierr); 1337 if (flg1) { 1338 if (mname[0]) {ierr = PetscLogMPEDump(mname);CHKERRQ(ierr);} 1339 else {ierr = PetscLogMPEDump(0);CHKERRQ(ierr);} 1340 } 1341 #endif 1342 #endif 1343 1344 /* 1345 Free all objects registered with PetscObjectRegisterDestroy() such as PETSC_VIEWER_XXX_(). 1346 */ 1347 ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr); 1348 1349 #if defined(PETSC_USE_LOG) 1350 ierr = PetscOptionsPushGetViewerOff(PETSC_FALSE);CHKERRQ(ierr); 1351 ierr = PetscLogViewFromOptions();CHKERRQ(ierr); 1352 ierr = PetscOptionsPopGetViewerOff();CHKERRQ(ierr); 1353 1354 mname[0] = 0; 1355 ierr = PetscOptionsGetString(NULL,NULL,"-log_summary",mname,sizeof(mname),&flg1);CHKERRQ(ierr); 1356 if (flg1) { 1357 PetscViewer viewer; 1358 ierr = (*PetscHelpPrintf)(PETSC_COMM_WORLD,"\n\n WARNING: -log_summary is being deprecated; switch to -log_view\n\n\n");CHKERRQ(ierr); 1359 if (mname[0]) { 1360 ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr); 1361 ierr = PetscLogView(viewer);CHKERRQ(ierr); 1362 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1363 } else { 1364 viewer = PETSC_VIEWER_STDOUT_WORLD; 1365 ierr = PetscViewerPushFormat(viewer,PETSC_VIEWER_DEFAULT);CHKERRQ(ierr); 1366 ierr = PetscLogView(viewer);CHKERRQ(ierr); 1367 ierr = PetscViewerPopFormat(viewer);CHKERRQ(ierr); 1368 } 1369 } 1370 1371 /* 1372 Free any objects created by the last block of code. 1373 */ 1374 ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr); 1375 1376 mname[0] = 0; 1377 ierr = PetscOptionsGetString(NULL,NULL,"-log_all",mname,sizeof(mname),&flg1);CHKERRQ(ierr); 1378 ierr = PetscOptionsGetString(NULL,NULL,"-log",mname,sizeof(mname),&flg2);CHKERRQ(ierr); 1379 if (flg1 || flg2) {ierr = PetscLogDump(mname);CHKERRQ(ierr);} 1380 #endif 1381 1382 ierr = PetscStackDestroy();CHKERRQ(ierr); 1383 1384 flg1 = PETSC_FALSE; 1385 ierr = PetscOptionsGetBool(NULL,NULL,"-no_signal_handler",&flg1,NULL);CHKERRQ(ierr); 1386 if (!flg1) { ierr = PetscPopSignalHandler();CHKERRQ(ierr);} 1387 flg1 = PETSC_FALSE; 1388 ierr = PetscOptionsGetBool(NULL,NULL,"-mpidump",&flg1,NULL);CHKERRQ(ierr); 1389 if (flg1) { 1390 ierr = PetscMPIDump(stdout);CHKERRQ(ierr); 1391 } 1392 flg1 = PETSC_FALSE; 1393 flg2 = PETSC_FALSE; 1394 /* preemptive call to avoid listing this option in options table as unused */ 1395 ierr = PetscOptionsHasName(NULL,NULL,"-malloc_dump",&flg1);CHKERRQ(ierr); 1396 ierr = PetscOptionsHasName(NULL,NULL,"-objects_dump",&flg1);CHKERRQ(ierr); 1397 ierr = PetscOptionsGetBool(NULL,NULL,"-options_view",&flg2,NULL);CHKERRQ(ierr); 1398 1399 if (flg2) { 1400 PetscViewer viewer; 1401 ierr = PetscViewerCreate(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr); 1402 ierr = PetscViewerSetType(viewer,PETSCVIEWERASCII);CHKERRQ(ierr); 1403 ierr = PetscOptionsView(NULL,viewer);CHKERRQ(ierr); 1404 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1405 } 1406 1407 /* to prevent PETSc -options_left from warning */ 1408 ierr = PetscOptionsHasName(NULL,NULL,"-nox",&flg1);CHKERRQ(ierr); 1409 ierr = PetscOptionsHasName(NULL,NULL,"-nox_warning",&flg1);CHKERRQ(ierr); 1410 1411 flg3 = PETSC_FALSE; /* default value is required */ 1412 ierr = PetscOptionsGetBool(NULL,NULL,"-options_left",&flg3,&flg1);CHKERRQ(ierr); 1413 if (PetscUnlikelyDebug(!flg1)) flg3 = PETSC_TRUE; 1414 if (flg3) { 1415 if (!flg2 && flg1) { /* have not yet printed the options */ 1416 PetscViewer viewer; 1417 ierr = PetscViewerCreate(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr); 1418 ierr = PetscViewerSetType(viewer,PETSCVIEWERASCII);CHKERRQ(ierr); 1419 ierr = PetscOptionsView(NULL,viewer);CHKERRQ(ierr); 1420 ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr); 1421 } 1422 ierr = PetscOptionsAllUsed(NULL,&nopt);CHKERRQ(ierr); 1423 if (nopt) { 1424 ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! There are options you set that were not used!\n");CHKERRQ(ierr); 1425 ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! could be spelling mistake, etc!\n");CHKERRQ(ierr); 1426 if (nopt == 1) { 1427 ierr = PetscPrintf(PETSC_COMM_WORLD,"There is one unused database option. It is:\n");CHKERRQ(ierr); 1428 } else { 1429 ierr = PetscPrintf(PETSC_COMM_WORLD,"There are %D unused database options. They are:\n",nopt);CHKERRQ(ierr); 1430 } 1431 } else if (flg3 && flg1) { 1432 ierr = PetscPrintf(PETSC_COMM_WORLD,"There are no unused options.\n");CHKERRQ(ierr); 1433 } 1434 ierr = PetscOptionsLeft(NULL);CHKERRQ(ierr); 1435 } 1436 1437 #if defined(PETSC_HAVE_SAWS) 1438 if (!PetscGlobalRank) { 1439 ierr = PetscStackSAWsViewOff();CHKERRQ(ierr); 1440 PetscStackCallSAWs(SAWs_Finalize,()); 1441 } 1442 #endif 1443 1444 #if defined(PETSC_USE_LOG) 1445 /* 1446 List all objects the user may have forgot to free 1447 */ 1448 if (PetscObjectsLog) { 1449 ierr = PetscOptionsHasName(NULL,NULL,"-objects_dump",&flg1);CHKERRQ(ierr); 1450 if (flg1) { 1451 MPI_Comm local_comm; 1452 char string[64]; 1453 1454 ierr = PetscOptionsGetString(NULL,NULL,"-objects_dump",string,sizeof(string),NULL);CHKERRQ(ierr); 1455 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRMPI(ierr); 1456 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1457 ierr = PetscObjectsDump(stdout,(string[0] == 'a') ? PETSC_TRUE : PETSC_FALSE);CHKERRQ(ierr); 1458 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1459 ierr = MPI_Comm_free(&local_comm);CHKERRMPI(ierr); 1460 } 1461 } 1462 #endif 1463 1464 #if defined(PETSC_USE_LOG) 1465 PetscObjectsCounts = 0; 1466 PetscObjectsMaxCounts = 0; 1467 ierr = PetscFree(PetscObjects);CHKERRQ(ierr); 1468 #endif 1469 1470 /* 1471 Destroy any packages that registered a finalize 1472 */ 1473 ierr = PetscRegisterFinalizeAll();CHKERRQ(ierr); 1474 1475 #if defined(PETSC_USE_LOG) 1476 ierr = PetscLogFinalize();CHKERRQ(ierr); 1477 #endif 1478 1479 /* 1480 Print PetscFunctionLists that have not been properly freed 1481 1482 ierr = PetscFunctionListPrintAll();CHKERRQ(ierr); 1483 */ 1484 1485 if (petsc_history) { 1486 ierr = PetscCloseHistoryFile(&petsc_history);CHKERRQ(ierr); 1487 petsc_history = NULL; 1488 } 1489 ierr = PetscOptionsHelpPrintedDestroy(&PetscOptionsHelpPrintedSingleton);CHKERRQ(ierr); 1490 ierr = PetscInfoDestroy();CHKERRQ(ierr); 1491 1492 #if !defined(PETSC_HAVE_THREADSAFETY) 1493 if (!(PETSC_RUNNING_ON_VALGRIND)) { 1494 char fname[PETSC_MAX_PATH_LEN]; 1495 char sname[PETSC_MAX_PATH_LEN]; 1496 FILE *fd; 1497 int err; 1498 1499 flg2 = PETSC_FALSE; 1500 flg3 = PETSC_FALSE; 1501 if (PetscDefined(USE_DEBUG)) {ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_test",&flg2,NULL);CHKERRQ(ierr);} 1502 ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_debug",&flg3,NULL);CHKERRQ(ierr); 1503 fname[0] = 0; 1504 ierr = PetscOptionsGetString(NULL,NULL,"-malloc_dump",fname,sizeof(fname),&flg1);CHKERRQ(ierr); 1505 if (flg1 && fname[0]) { 1506 1507 PetscSNPrintf(sname,sizeof(sname),"%s_%d",fname,rank); 1508 fd = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname); 1509 ierr = PetscMallocDump(fd);CHKERRQ(ierr); 1510 err = fclose(fd); 1511 if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file"); 1512 } else if (flg1 || flg2 || flg3) { 1513 MPI_Comm local_comm; 1514 1515 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRMPI(ierr); 1516 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1517 ierr = PetscMallocDump(stdout);CHKERRQ(ierr); 1518 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1519 ierr = MPI_Comm_free(&local_comm);CHKERRMPI(ierr); 1520 } 1521 fname[0] = 0; 1522 ierr = PetscOptionsGetString(NULL,NULL,"-malloc_view",fname,sizeof(fname),&flg1);CHKERRQ(ierr); 1523 if (flg1 && fname[0]) { 1524 1525 PetscSNPrintf(sname,sizeof(sname),"%s_%d",fname,rank); 1526 fd = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname); 1527 ierr = PetscMallocView(fd);CHKERRQ(ierr); 1528 err = fclose(fd); 1529 if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file"); 1530 } else if (flg1) { 1531 MPI_Comm local_comm; 1532 1533 ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRMPI(ierr); 1534 ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr); 1535 ierr = PetscMallocView(stdout);CHKERRQ(ierr); 1536 ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr); 1537 ierr = MPI_Comm_free(&local_comm);CHKERRMPI(ierr); 1538 } 1539 } 1540 #endif 1541 1542 /* 1543 Close any open dynamic libraries 1544 */ 1545 ierr = PetscFinalize_DynamicLibraries();CHKERRQ(ierr); 1546 1547 /* Can be destroyed only after all the options are used */ 1548 ierr = PetscOptionsDestroyDefault();CHKERRQ(ierr); 1549 1550 PetscGlobalArgc = 0; 1551 PetscGlobalArgs = NULL; 1552 1553 #if defined(PETSC_HAVE_KOKKOS) 1554 if (PetscBeganKokkos) { 1555 ierr = PetscKokkosFinalize_Private();CHKERRQ(ierr); 1556 PetscBeganKokkos = PETSC_FALSE; 1557 PetscKokkosInitialized = PETSC_FALSE; 1558 } 1559 #endif 1560 1561 #if defined(PETSC_HAVE_NVSHMEM) 1562 if (PetscBeganNvshmem) { 1563 ierr = PetscNvshmemFinalize();CHKERRQ(ierr); 1564 PetscBeganNvshmem = PETSC_FALSE; 1565 } 1566 #endif 1567 1568 #if defined(PETSC_HAVE_CUDA) 1569 if (PetscDefaultCudaStream) {cudaError_t cerr = cudaStreamDestroy(PetscDefaultCudaStream);CHKERRCUDA(cerr);} 1570 if (petsc_gputimer_begin) { 1571 cudaError_t cerr = cudaEventDestroy(petsc_gputimer_begin);CHKERRCUDA(cerr); 1572 } 1573 if (petsc_gputimer_end) { 1574 cudaError_t cerr = cudaEventDestroy(petsc_gputimer_end);CHKERRCUDA(cerr); 1575 } 1576 #endif 1577 1578 #if defined(PETSC_HAVE_HIP) 1579 if (PetscDefaultHipStream) {hipError_t cerr = hipStreamDestroy(PetscDefaultHipStream);CHKERRHIP(cerr);} 1580 if (petsc_gputimer_begin) { 1581 hipError_t cerr = hipEventDestroy(petsc_gputimer_begin);CHKERRHIP(cerr); 1582 } 1583 if (petsc_gputimer_end) { 1584 hipError_t cerr = hipEventDestroy(petsc_gputimer_end);CHKERRHIP(cerr); 1585 } 1586 #endif 1587 1588 ierr = PetscFreeMPIResources();CHKERRQ(ierr); 1589 1590 /* 1591 Destroy any known inner MPI_Comm's and attributes pointing to them 1592 Note this will not destroy any new communicators the user has created. 1593 1594 If all PETSc objects were not destroyed those left over objects will have hanging references to 1595 the MPI_Comms that were freed; but that is ok because those PETSc objects will never be used again 1596 */ 1597 { 1598 PetscCommCounter *counter; 1599 PetscMPIInt flg; 1600 MPI_Comm icomm; 1601 union {MPI_Comm comm; void *ptr;} ucomm; 1602 ierr = MPI_Comm_get_attr(PETSC_COMM_SELF,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRMPI(ierr); 1603 if (flg) { 1604 icomm = ucomm.comm; 1605 ierr = MPI_Comm_get_attr(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRMPI(ierr); 1606 if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory"); 1607 1608 ierr = MPI_Comm_delete_attr(PETSC_COMM_SELF,Petsc_InnerComm_keyval);CHKERRMPI(ierr); 1609 ierr = MPI_Comm_delete_attr(icomm,Petsc_Counter_keyval);CHKERRMPI(ierr); 1610 ierr = MPI_Comm_free(&icomm);CHKERRMPI(ierr); 1611 } 1612 ierr = MPI_Comm_get_attr(PETSC_COMM_WORLD,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRMPI(ierr); 1613 if (flg) { 1614 icomm = ucomm.comm; 1615 ierr = MPI_Comm_get_attr(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRMPI(ierr); 1616 if (!flg) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory"); 1617 1618 ierr = MPI_Comm_delete_attr(PETSC_COMM_WORLD,Petsc_InnerComm_keyval);CHKERRMPI(ierr); 1619 ierr = MPI_Comm_delete_attr(icomm,Petsc_Counter_keyval);CHKERRMPI(ierr); 1620 ierr = MPI_Comm_free(&icomm);CHKERRMPI(ierr); 1621 } 1622 } 1623 1624 ierr = MPI_Comm_free_keyval(&Petsc_Counter_keyval);CHKERRMPI(ierr); 1625 ierr = MPI_Comm_free_keyval(&Petsc_InnerComm_keyval);CHKERRMPI(ierr); 1626 ierr = MPI_Comm_free_keyval(&Petsc_OuterComm_keyval);CHKERRMPI(ierr); 1627 ierr = MPI_Comm_free_keyval(&Petsc_ShmComm_keyval);CHKERRMPI(ierr); 1628 1629 ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockOpen);CHKERRQ(ierr); 1630 ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockStdout);CHKERRQ(ierr); 1631 ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockStderr);CHKERRQ(ierr); 1632 ierr = PetscSpinlockDestroy(&PetscCommSpinLock);CHKERRQ(ierr); 1633 1634 if (PetscBeganMPI) { 1635 #if defined(PETSC_HAVE_MPI_FINALIZED) 1636 PetscMPIInt flag; 1637 ierr = MPI_Finalized(&flag);CHKERRMPI(ierr); 1638 if (flag) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_LIB,"MPI_Finalize() has already been called, even though MPI_Init() was called by PetscInitialize()"); 1639 #endif 1640 ierr = MPI_Finalize();CHKERRMPI(ierr); 1641 } 1642 /* 1643 1644 Note: In certain cases PETSC_COMM_WORLD is never MPI_Comm_free()ed because 1645 the communicator has some outstanding requests on it. Specifically if the 1646 flag PETSC_HAVE_BROKEN_REQUEST_FREE is set (for IBM MPI implementation). See 1647 src/vec/utils/vpscat.c. Due to this the memory allocated in PetscCommDuplicate() 1648 is never freed as it should be. Thus one may obtain messages of the form 1649 [ 1] 8 bytes PetscCommDuplicate() line 645 in src/sys/mpiu.c indicating the 1650 memory was not freed. 1651 1652 */ 1653 ierr = PetscMallocClear();CHKERRQ(ierr); 1654 1655 PetscErrorHandlingInitialized = PETSC_FALSE; 1656 PetscInitializeCalled = PETSC_FALSE; 1657 PetscFinalizeCalled = PETSC_TRUE; 1658 #if defined(PETSC_USE_GCOV) 1659 /* 1660 flush gcov, otherwise during CI the flushing continues into the next pipeline resulting in git not being able to delete directories since the 1661 gcov files are still being added to the directories as git tries to remove the directories. 1662 */ 1663 __gcov_flush(); 1664 #endif 1665 PetscFunctionReturn(0); 1666 } 1667 1668 #if defined(PETSC_MISSING_LAPACK_lsame_) 1669 PETSC_EXTERN int lsame_(char *a,char *b) 1670 { 1671 if (*a == *b) return 1; 1672 if (*a + 32 == *b) return 1; 1673 if (*a - 32 == *b) return 1; 1674 return 0; 1675 } 1676 #endif 1677 1678 #if defined(PETSC_MISSING_LAPACK_lsame) 1679 PETSC_EXTERN int lsame(char *a,char *b) 1680 { 1681 if (*a == *b) return 1; 1682 if (*a + 32 == *b) return 1; 1683 if (*a - 32 == *b) return 1; 1684 return 0; 1685 } 1686 #endif 1687