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