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