xref: /petsc/src/sys/objects/pinit.c (revision 1c287f868b87547f7872a682a7b0051d361920ef)
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.7},\n  Institution = {Argonne National Laboratory},\n  Year = {2016}\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 +  -start_in_debugger [noxterm,dbx,xdb,gdb,...] - Starts program in debugger
629 .  -on_error_attach_debugger [noxterm,dbx,xdb,gdb,...] - Starts debugger when error detected
630 .  -on_error_emacs <machinename> causes emacsclient to jump to error file
631 .  -on_error_abort calls abort() when error detected (no traceback)
632 .  -on_error_mpiabort calls MPI_abort() when error detected
633 .  -error_output_stderr prints error messages to stderr instead of the default stdout
634 .  -error_output_none does not print the error messages (but handles errors in the same way as if this was not called)
635 .  -debugger_nodes [node1,node2,...] - Indicates nodes to start in debugger
636 .  -debugger_pause [sleeptime] (in seconds) - Pauses debugger
637 .  -stop_for_debugger - Print message on how to attach debugger manually to
638                         process and wait (-debugger_pause) seconds for attachment
639 .  -malloc - Indicates use of PETSc error-checking malloc (on by default for debug version of libraries)
640 .  -malloc no - Indicates not to use error-checking malloc
641 .  -malloc_debug - check for memory corruption at EVERY malloc or free
642 .  -malloc_dump - prints a list of all unfreed memory at the end of the run
643 .  -malloc_test - like -malloc_dump -malloc_debug, but only active for debugging builds
644 .  -fp_trap - Stops on floating point exceptions (Note that on the
645               IBM RS6000 this slows code by at least a factor of 10.)
646 .  -no_signal_handler - Indicates not to trap error signals
647 .  -shared_tmp - indicates /tmp directory is shared by all processors
648 .  -not_shared_tmp - each processor has own /tmp
649 .  -tmp - alternative name of /tmp directory
650 .  -get_total_flops - returns total flops done by all processors
651 -  -memory_view - Print memory usage at end of run
652 
653    Options Database Keys for Profiling:
654    See Users-Manual: ch_profiling for details.
655 +  -info <optional filename> - Prints verbose information to the screen
656 .  -info_exclude <null,vec,mat,pc,ksp,snes,ts> - Excludes some of the verbose messages
657 .  -log_sync - Log the synchronization in scatters, inner products and norms
658 .  -log_trace [filename] - Print traces of all PETSc calls to the screen (useful to determine where a program
659         hangs without running in the debugger).  See PetscLogTraceBegin().
660 .  -log_view [:filename:format] - Prints summary of flop and timing information to screen or file, see PetscLogView().
661 .  -log_summary [filename] - (Deprecated, use -log_view) Prints summary of flop and timing information to screen. If the filename is specified the
662         summary is written to the file.  See PetscLogView().
663 .  -log_exclude: <vec,mat,pc.ksp,snes> - excludes subset of object classes from logging
664 .  -log_all [filename] - Logs extensive profiling information  See PetscLogDump().
665 .  -log [filename] - Logs basic profiline information  See PetscLogDump().
666 -  -log_mpe [filename] - Creates a logfile viewable by the utility Jumpshot (in MPICH distribution)
667 
668     Only one of -log_trace, -log_view, -log_view, -log_all, -log, or -log_mpe may be used at a time
669 
670    Options Database Keys for SAWs:
671 +  -saws_port <portnumber> - port number to publish SAWs data, default is 8080
672 .  -saws_port_auto_select - have SAWs select a new unique port number where it publishes the data, the URL is printed to the screen
673                             this is useful when you are running many jobs that utilize SAWs at the same time
674 .  -saws_log <filename> - save a log of all SAWs communication
675 .  -saws_https <certificate file> - have SAWs use HTTPS instead of HTTP
676 -  -saws_root <directory> - allow SAWs to have access to the given directory to search for requested resources and files
677 
678    Environmental Variables:
679 +   PETSC_TMP - alternative tmp directory
680 .   PETSC_SHARED_TMP - tmp is shared by all processes
681 .   PETSC_NOT_SHARED_TMP - each process has its own private tmp
682 .   PETSC_VIEWER_SOCKET_PORT - socket number to use for socket viewer
683 -   PETSC_VIEWER_SOCKET_MACHINE - machine to use for socket viewer to connect to
684 
685 
686    Level: beginner
687 
688    Notes:
689    If for some reason you must call MPI_Init() separately, call
690    it before PetscInitialize().
691 
692    Fortran Version:
693    In Fortran this routine has the format
694 $       call PetscInitialize(file,ierr)
695 
696 +   ierr - error return code
697 -  file - [optional] PETSc database file, also checks ~username/.petscrc and .petscrc use PETSC_NULL_CHARACTER to not check for
698           code specific file. Use -skip_petscrc in the code specific file to skip the .petscrc files
699 
700    Important Fortran Note:
701    In Fortran, you MUST use PETSC_NULL_CHARACTER to indicate a
702    null character string; you CANNOT just use NULL as
703    in the C version. See Users-Manual: ch_fortran for details.
704 
705    If your main program is C but you call Fortran code that also uses PETSc you need to call PetscInitializeFortran() soon after
706    calling PetscInitialize().
707 
708    Concepts: initializing PETSc
709 
710 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscInitializeNoArguments()
711 
712 @*/
713 PetscErrorCode  PetscInitialize(int *argc,char ***args,const char file[],const char help[])
714 {
715   PetscErrorCode ierr;
716   PetscMPIInt    flag, size;
717   PetscBool      flg;
718   char           hostname[256];
719 #if defined(PETSC_HAVE_CUDA)
720   cublasStatus_t cberr;
721 #endif
722 
723   PetscFunctionBegin;
724   if (PetscInitializeCalled) PetscFunctionReturn(0);
725 
726   /* these must be initialized in a routine, not as a constant declaration*/
727   PETSC_STDOUT = stdout;
728   PETSC_STDERR = stderr;
729 
730   /* on Windows - set printf to default to printing 2 digit exponents */
731 #if defined(PETSC_HAVE__SET_OUTPUT_FORMAT)
732   _set_output_format(_TWO_DIGIT_EXPONENT);
733 #endif
734 
735   ierr = PetscOptionsCreateDefault();CHKERRQ(ierr);
736 
737   /*
738      We initialize the program name here (before MPI_Init()) because MPICH has a bug in
739      it that it sets args[0] on all processors to be args[0] on the first processor.
740   */
741   if (argc && *argc) {
742     ierr = PetscSetProgramName(**args);CHKERRQ(ierr);
743   } else {
744     ierr = PetscSetProgramName("Unknown Name");CHKERRQ(ierr);
745   }
746 
747   ierr = MPI_Initialized(&flag);CHKERRQ(ierr);
748   if (!flag) {
749     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");
750 #if defined(PETSC_HAVE_MPI_INIT_THREAD)
751     {
752       PetscMPIInt provided;
753       ierr = MPI_Init_thread(argc,args,MPI_THREAD_FUNNELED,&provided);CHKERRQ(ierr);
754     }
755 #else
756     ierr = MPI_Init(argc,args);CHKERRQ(ierr);
757 #endif
758     PetscBeganMPI = PETSC_TRUE;
759   }
760   if (argc && args) {
761     PetscGlobalArgc = *argc;
762     PetscGlobalArgs = *args;
763   }
764   PetscFinalizeCalled = PETSC_FALSE;
765   ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockOpen);CHKERRQ(ierr);
766   ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockStdout);CHKERRQ(ierr);
767   ierr = PetscSpinlockCreate(&PetscViewerASCIISpinLockStderr);CHKERRQ(ierr);
768   ierr = PetscSpinlockCreate(&PetscCommSpinLock);CHKERRQ(ierr);
769 
770   if (PETSC_COMM_WORLD == MPI_COMM_NULL) PETSC_COMM_WORLD = MPI_COMM_WORLD;
771   ierr = MPI_Comm_set_errhandler(PETSC_COMM_WORLD,MPI_ERRORS_RETURN);CHKERRQ(ierr);
772 
773   /* Done after init due to a bug in MPICH-GM? */
774   ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr);
775 
776   ierr = MPI_Comm_rank(MPI_COMM_WORLD,&PetscGlobalRank);CHKERRQ(ierr);
777   ierr = MPI_Comm_size(MPI_COMM_WORLD,&PetscGlobalSize);CHKERRQ(ierr);
778 
779   MPIU_BOOL = MPI_INT;
780   MPIU_ENUM = MPI_INT;
781 
782   /*
783      Initialized the global complex variable; this is because with
784      shared libraries the constructors for global variables
785      are not called; at least on IRIX.
786   */
787 #if defined(PETSC_HAVE_COMPLEX)
788   {
789 #if defined(PETSC_CLANGUAGE_CXX)
790     PetscComplex ic(0.0,1.0);
791     PETSC_i = ic;
792 #elif defined(PETSC_CLANGUAGE_C)
793     PETSC_i = _Complex_I;
794 #endif
795   }
796 
797 #if !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)
798   ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr);
799   ierr = MPI_Type_commit(&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr);
800   ierr = MPI_Type_contiguous(2,MPI_FLOAT,&MPIU_C_COMPLEX);CHKERRQ(ierr);
801   ierr = MPI_Type_commit(&MPIU_C_COMPLEX);CHKERRQ(ierr);
802 #endif
803 #endif /* PETSC_HAVE_COMPLEX */
804 
805   /*
806      Create the PETSc MPI reduction operator that sums of the first
807      half of the entries and maxes the second half.
808   */
809   ierr = MPI_Op_create(MPIU_MaxSum_Local,1,&MPIU_MAXSUM_OP);CHKERRQ(ierr);
810 
811 #if defined(PETSC_USE_REAL___FLOAT128)
812   ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU___FLOAT128);CHKERRQ(ierr);
813   ierr = MPI_Type_commit(&MPIU___FLOAT128);CHKERRQ(ierr);
814 #if defined(PETSC_HAVE_COMPLEX)
815   ierr = MPI_Type_contiguous(4,MPI_DOUBLE,&MPIU___COMPLEX128);CHKERRQ(ierr);
816   ierr = MPI_Type_commit(&MPIU___COMPLEX128);CHKERRQ(ierr);
817 #endif
818   ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRQ(ierr);
819   ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRQ(ierr);
820 #elif defined(PETSC_USE_REAL___FP16)
821   ierr = MPI_Type_contiguous(2,MPI_CHAR,&MPIU___FP16);CHKERRQ(ierr);
822   ierr = MPI_Type_commit(&MPIU___FP16);CHKERRQ(ierr);
823   ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRQ(ierr);
824   ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRQ(ierr);
825 #endif
826 
827 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16)
828   ierr = MPI_Op_create(PetscSum_Local,1,&MPIU_SUM);CHKERRQ(ierr);
829 #endif
830 
831   ierr = MPI_Type_contiguous(2,MPIU_SCALAR,&MPIU_2SCALAR);CHKERRQ(ierr);
832   ierr = MPI_Type_commit(&MPIU_2SCALAR);CHKERRQ(ierr);
833 
834 #if defined(PETSC_USE_64BIT_INDICES) || !defined(MPI_2INT)
835   ierr = MPI_Type_contiguous(2,MPIU_INT,&MPIU_2INT);CHKERRQ(ierr);
836   ierr = MPI_Type_commit(&MPIU_2INT);CHKERRQ(ierr);
837 #endif
838 
839 
840   /*
841      Attributes to be set on PETSc communicators
842   */
843   ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelCounter,&Petsc_Counter_keyval,(void*)0);CHKERRQ(ierr);
844   ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelComm_Outer,&Petsc_InnerComm_keyval,(void*)0);CHKERRQ(ierr);
845   ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelComm_Inner,&Petsc_OuterComm_keyval,(void*)0);CHKERRQ(ierr);
846 
847   /*
848      Build the options database
849   */
850   ierr = PetscOptionsInsert(NULL,argc,args,file);CHKERRQ(ierr);
851 
852 
853   /*
854      Print main application help message
855   */
856   ierr = PetscOptionsHasName(NULL,NULL,"-help",&flg);CHKERRQ(ierr);
857   if (help && flg) {
858     ierr = PetscPrintf(PETSC_COMM_WORLD,help);CHKERRQ(ierr);
859   }
860   ierr = PetscOptionsCheckInitial_Private();CHKERRQ(ierr);
861 
862   ierr = PetscCitationsInitialize();CHKERRQ(ierr);
863 
864 #if defined(PETSC_HAVE_SAWS)
865   ierr = PetscInitializeSAWs(help);CHKERRQ(ierr);
866 #endif
867 
868   /* Creates the logging data structures; this is enabled even if logging is not turned on */
869 #if defined(PETSC_USE_LOG)
870   ierr = PetscLogInitialize();CHKERRQ(ierr);
871 #endif
872 
873   /*
874      Load the dynamic libraries (on machines that support them), this registers all
875      the solvers etc. (On non-dynamic machines this initializes the PetscDraw and PetscViewer classes)
876   */
877   ierr = PetscInitialize_DynamicLibraries();CHKERRQ(ierr);
878 
879   ierr = MPI_Comm_size(PETSC_COMM_WORLD,&size);CHKERRQ(ierr);
880   ierr = PetscInfo1(0,"PETSc successfully started: number of processors = %d\n",size);CHKERRQ(ierr);
881   ierr = PetscGetHostName(hostname,256);CHKERRQ(ierr);
882   ierr = PetscInfo1(0,"Running on machine: %s\n",hostname);CHKERRQ(ierr);
883 
884   ierr = PetscOptionsCheckInitial_Components();CHKERRQ(ierr);
885   /* Check the options database for options related to the options database itself */
886   ierr = PetscOptionsSetFromOptions(NULL);CHKERRQ(ierr);
887 
888 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32)
889   /*
890       Tell MPI about our own data representation converter, this would/should be used if extern32 is not supported by the MPI
891 
892       Currently not used because it is not supported by MPICH.
893   */
894 #if !defined(PETSC_WORDS_BIGENDIAN)
895   ierr = MPI_Register_datarep((char*)"petsc",PetscDataRep_read_conv_fn,PetscDataRep_write_conv_fn,PetscDataRep_extent_fn,NULL);CHKERRQ(ierr);
896 #endif
897 #endif
898 
899 #if defined(PETSC_HAVE_CUDA)
900   flg  = PETSC_TRUE;
901   ierr = PetscOptionsGetBool(NULL,NULL,"-cublas",&flg,NULL);CHKERRQ(ierr);
902   if (flg) {
903     PetscMPIInt p;
904     for (p = 0; p < PetscGlobalSize; ++p) {
905       if (p == PetscGlobalRank) {
906         cberr = cublasCreate(&cublasv2handle);CHKERRCUBLAS(cberr);
907       }
908       ierr = MPI_Barrier(PETSC_COMM_WORLD);CHKERRQ(ierr);
909     }
910   }
911 #endif
912 
913   ierr = PetscOptionsHasName(NULL,NULL,"-python",&flg);CHKERRQ(ierr);
914   if (flg) {
915     PetscInitializeCalled = PETSC_TRUE;
916     ierr = PetscPythonInitialize(NULL,NULL);CHKERRQ(ierr);
917   }
918 
919   /*
920       Setup building of stack frames for all function calls
921   */
922 #if defined(PETSC_USE_DEBUG) && !defined(PETSC_HAVE_THREADSAFETY)
923   ierr = PetscStackCreate();CHKERRQ(ierr);
924 #endif
925 
926 #if defined(PETSC_SERIALIZE_FUNCTIONS)
927   ierr = PetscFPTCreate(10000);CHKERRQ(ierr);
928 #endif
929 
930 
931   /*
932       Once we are completedly initialized then we can set this variables
933   */
934   PetscInitializeCalled = PETSC_TRUE;
935   PetscFunctionReturn(0);
936 }
937 
938 #if defined(PETSC_USE_LOG)
939 extern PetscObject *PetscObjects;
940 extern PetscInt    PetscObjectsCounts, PetscObjectsMaxCounts;
941 extern PetscBool   PetscObjectsLog;
942 #endif
943 
944 /*@C
945    PetscFinalize - Checks for options to be called at the conclusion
946    of the program. MPI_Finalize() is called only if the user had not
947    called MPI_Init() before calling PetscInitialize().
948 
949    Collective on PETSC_COMM_WORLD
950 
951    Options Database Keys:
952 +  -options_table - Calls PetscOptionsView()
953 .  -options_left - Prints unused options that remain in the database
954 .  -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
955 .  -mpidump - Calls PetscMPIDump()
956 .  -malloc_dump - Calls PetscMallocDump()
957 .  -malloc_info - Prints total memory usage
958 -  -malloc_log - Prints summary of memory usage
959 
960    Level: beginner
961 
962    Note:
963    See PetscInitialize() for more general runtime options.
964 
965 .seealso: PetscInitialize(), PetscOptionsView(), PetscMallocDump(), PetscMPIDump(), PetscEnd()
966 @*/
967 PetscErrorCode  PetscFinalize(void)
968 {
969   PetscErrorCode ierr;
970   PetscMPIInt    rank;
971   PetscInt       nopt;
972   PetscBool      flg1 = PETSC_FALSE,flg2 = PETSC_FALSE,flg3 = PETSC_FALSE;
973   PetscBool      flg;
974 #if defined(PETSC_USE_LOG)
975   char           mname[PETSC_MAX_PATH_LEN];
976 #endif
977 #if defined(PETSC_HAVE_CUDA)
978   cublasStatus_t cberr;
979 #endif
980 
981   PetscFunctionBegin;
982   if (!PetscInitializeCalled) {
983     printf("PetscInitialize() must be called before PetscFinalize()\n");
984     PetscFunctionReturn(PETSC_ERR_ARG_WRONGSTATE);
985   }
986   ierr = PetscInfo(NULL,"PetscFinalize() called\n");CHKERRQ(ierr);
987 
988   ierr = MPI_Comm_rank(PETSC_COMM_WORLD,&rank);CHKERRQ(ierr);
989 
990   ierr = PetscOptionsHasName(NULL,NULL,"-citations",&flg);CHKERRQ(ierr);
991   if (flg) {
992     char  *cits, filename[PETSC_MAX_PATH_LEN];
993     FILE  *fd = PETSC_STDOUT;
994 
995     ierr = PetscOptionsGetString(NULL,NULL,"-citations",filename,PETSC_MAX_PATH_LEN,NULL);CHKERRQ(ierr);
996     if (filename[0]) {
997       ierr = PetscFOpen(PETSC_COMM_WORLD,filename,"w",&fd);CHKERRQ(ierr);
998     }
999     ierr = PetscSegBufferGet(PetscCitationsList,1,&cits);CHKERRQ(ierr);
1000     cits[0] = 0;
1001     ierr = PetscSegBufferExtractAlloc(PetscCitationsList,&cits);CHKERRQ(ierr);
1002     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"If you publish results based on this computation please cite the following:\n");CHKERRQ(ierr);
1003     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr);
1004     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"%s",cits);CHKERRQ(ierr);
1005     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr);
1006     ierr = PetscFClose(PETSC_COMM_WORLD,fd);CHKERRQ(ierr);
1007     ierr = PetscFree(cits);CHKERRQ(ierr);
1008   }
1009   ierr = PetscSegBufferDestroy(&PetscCitationsList);CHKERRQ(ierr);
1010 
1011 #if defined(PETSC_HAVE_SSL) && defined(PETSC_USE_SOCKET_VIEWER)
1012   /* TextBelt is run for testing purposes only, please do not use this feature often */
1013   {
1014     PetscInt nmax = 2;
1015     char     **buffs;
1016     ierr = PetscMalloc1(2,&buffs);CHKERRQ(ierr);
1017     ierr = PetscOptionsGetStringArray(NULL,NULL,"-textbelt",buffs,&nmax,&flg1);CHKERRQ(ierr);
1018     if (flg1) {
1019       if (!nmax) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_USER,"-textbelt requires either the phone number or number,\"message\"");
1020       if (nmax == 1) {
1021         ierr = PetscMalloc1(128,&buffs[1]);CHKERRQ(ierr);
1022         ierr = PetscGetProgramName(buffs[1],32);CHKERRQ(ierr);
1023         ierr = PetscStrcat(buffs[1]," has completed");CHKERRQ(ierr);
1024       }
1025       ierr = PetscTextBelt(PETSC_COMM_WORLD,buffs[0],buffs[1],NULL);CHKERRQ(ierr);
1026       ierr = PetscFree(buffs[0]);CHKERRQ(ierr);
1027       ierr = PetscFree(buffs[1]);CHKERRQ(ierr);
1028     }
1029     ierr = PetscFree(buffs);CHKERRQ(ierr);
1030   }
1031   {
1032     PetscInt nmax = 2;
1033     char     **buffs;
1034     ierr = PetscMalloc1(2,&buffs);CHKERRQ(ierr);
1035     ierr = PetscOptionsGetStringArray(NULL,NULL,"-tellmycell",buffs,&nmax,&flg1);CHKERRQ(ierr);
1036     if (flg1) {
1037       if (!nmax) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_USER,"-tellmycell requires either the phone number or number,\"message\"");
1038       if (nmax == 1) {
1039         ierr = PetscMalloc1(128,&buffs[1]);CHKERRQ(ierr);
1040         ierr = PetscGetProgramName(buffs[1],32);CHKERRQ(ierr);
1041         ierr = PetscStrcat(buffs[1]," has completed");CHKERRQ(ierr);
1042       }
1043       ierr = PetscTellMyCell(PETSC_COMM_WORLD,buffs[0],buffs[1],NULL);CHKERRQ(ierr);
1044       ierr = PetscFree(buffs[0]);CHKERRQ(ierr);
1045       ierr = PetscFree(buffs[1]);CHKERRQ(ierr);
1046     }
1047     ierr = PetscFree(buffs);CHKERRQ(ierr);
1048   }
1049 #endif
1050   /*
1051     It should be safe to cancel the options monitors, since we don't expect to be setting options
1052     here (at least that are worth monitoring).  Monitors ought to be released so that they release
1053     whatever memory was allocated there before -malloc_dump reports unfreed memory.
1054   */
1055   ierr = PetscOptionsMonitorCancel();CHKERRQ(ierr);
1056 
1057 #if defined(PETSC_SERIALIZE_FUNCTIONS)
1058   ierr = PetscFPTDestroy();CHKERRQ(ierr);
1059 #endif
1060 
1061 
1062 #if defined(PETSC_HAVE_SAWS)
1063   flg = PETSC_FALSE;
1064   ierr = PetscOptionsGetBool(NULL,NULL,"-saw_options",&flg,NULL);CHKERRQ(ierr);
1065   if (flg) {
1066     ierr = PetscOptionsSAWsDestroy();CHKERRQ(ierr);
1067   }
1068 #endif
1069 
1070 #if defined(PETSC_HAVE_X)
1071   flg1 = PETSC_FALSE;
1072   ierr = PetscOptionsGetBool(NULL,NULL,"-x_virtual",&flg1,NULL);CHKERRQ(ierr);
1073   if (flg1) {
1074     /*  this is a crude hack, but better than nothing */
1075     ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 Xvfb","r",NULL);CHKERRQ(ierr);
1076   }
1077 #endif
1078 
1079 #if !defined(PETSC_HAVE_THREADSAFETY)
1080   ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_info",&flg2,NULL);CHKERRQ(ierr);
1081   if (!flg2) {
1082     flg2 = PETSC_FALSE;
1083     ierr = PetscOptionsGetBool(NULL,NULL,"-memory_view",&flg2,NULL);CHKERRQ(ierr);
1084   }
1085   if (flg2) {
1086     ierr = PetscMemoryView(PETSC_VIEWER_STDOUT_WORLD,"Summary of Memory Usage in PETSc\n");CHKERRQ(ierr);
1087   }
1088 #endif
1089 
1090 #if defined(PETSC_USE_LOG)
1091   flg1 = PETSC_FALSE;
1092   ierr = PetscOptionsGetBool(NULL,NULL,"-get_total_flops",&flg1,NULL);CHKERRQ(ierr);
1093   if (flg1) {
1094     PetscLogDouble flops = 0;
1095     ierr = MPI_Reduce(&petsc_TotalFlops,&flops,1,MPI_DOUBLE,MPI_SUM,0,PETSC_COMM_WORLD);CHKERRQ(ierr);
1096     ierr = PetscPrintf(PETSC_COMM_WORLD,"Total flops over all processors %g\n",flops);CHKERRQ(ierr);
1097   }
1098 #endif
1099 
1100 
1101 #if defined(PETSC_USE_LOG)
1102 #if defined(PETSC_HAVE_MPE)
1103   mname[0] = 0;
1104 
1105   ierr = PetscOptionsGetString(NULL,NULL,"-log_mpe",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1106   if (flg1) {
1107     if (mname[0]) {ierr = PetscLogMPEDump(mname);CHKERRQ(ierr);}
1108     else          {ierr = PetscLogMPEDump(0);CHKERRQ(ierr);}
1109   }
1110 #endif
1111   mname[0] = 0;
1112 
1113   ierr = PetscLogViewFromOptions();CHKERRQ(ierr);
1114   ierr = PetscOptionsGetString(NULL,NULL,"-log_summary",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1115   if (flg1) {
1116     PetscViewer viewer;
1117     ierr = (*PetscHelpPrintf)(PETSC_COMM_WORLD,"\n\n WARNING:   -log_summary is being deprecated; switch to -log_view\n\n\n");CHKERRQ(ierr);
1118     if (mname[0]) {
1119       ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr);
1120       ierr = PetscLogView(viewer);CHKERRQ(ierr);
1121       ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1122     } else {
1123       viewer = PETSC_VIEWER_STDOUT_WORLD;
1124       ierr   = PetscViewerPushFormat(viewer,PETSC_VIEWER_DEFAULT);CHKERRQ(ierr);
1125       ierr   = PetscLogView(viewer);CHKERRQ(ierr);
1126       ierr   = PetscViewerPopFormat(viewer);CHKERRQ(ierr);
1127     }
1128   }
1129   mname[0] = 0;
1130 
1131   ierr = PetscOptionsGetString(NULL,NULL,"-log_all",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1132   ierr = PetscOptionsGetString(NULL,NULL,"-log",mname,PETSC_MAX_PATH_LEN,&flg2);CHKERRQ(ierr);
1133   if (flg1 || flg2) {
1134     if (mname[0]) PetscLogDump(mname);
1135     else          PetscLogDump(0);
1136   }
1137 #endif
1138 
1139   /*
1140      Free all objects registered with PetscObjectRegisterDestroy() such as PETSC_VIEWER_XXX_().
1141   */
1142   ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr);
1143 
1144   ierr = PetscStackDestroy();CHKERRQ(ierr);
1145 
1146   flg1 = PETSC_FALSE;
1147   ierr = PetscOptionsGetBool(NULL,NULL,"-no_signal_handler",&flg1,NULL);CHKERRQ(ierr);
1148   if (!flg1) { ierr = PetscPopSignalHandler();CHKERRQ(ierr);}
1149   flg1 = PETSC_FALSE;
1150   ierr = PetscOptionsGetBool(NULL,NULL,"-mpidump",&flg1,NULL);CHKERRQ(ierr);
1151   if (flg1) {
1152     ierr = PetscMPIDump(stdout);CHKERRQ(ierr);
1153   }
1154   flg1 = PETSC_FALSE;
1155   flg2 = PETSC_FALSE;
1156   /* preemptive call to avoid listing this option in options table as unused */
1157   ierr = PetscOptionsHasName(NULL,NULL,"-malloc_dump",&flg1);CHKERRQ(ierr);
1158   ierr = PetscOptionsHasName(NULL,NULL,"-objects_dump",&flg1);CHKERRQ(ierr);
1159   ierr = PetscOptionsGetBool(NULL,NULL,"-options_view",&flg2,NULL);CHKERRQ(ierr);
1160 
1161   if (flg2) {
1162     PetscViewer viewer;
1163     ierr = PetscViewerCreate(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr);
1164     ierr = PetscViewerSetType(viewer,PETSCVIEWERASCII);CHKERRQ(ierr);
1165     ierr = PetscOptionsView(NULL,viewer);CHKERRQ(ierr);
1166     ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1167   }
1168 
1169   /* to prevent PETSc -options_left from warning */
1170   ierr = PetscOptionsHasName(NULL,NULL,"-nox",&flg1);CHKERRQ(ierr);
1171   ierr = PetscOptionsHasName(NULL,NULL,"-nox_warning",&flg1);CHKERRQ(ierr);
1172 
1173   flg3 = PETSC_FALSE; /* default value is required */
1174   ierr = PetscOptionsGetBool(NULL,NULL,"-options_left",&flg3,&flg1);CHKERRQ(ierr);
1175   ierr = PetscOptionsAllUsed(NULL,&nopt);CHKERRQ(ierr);
1176   if (flg3) {
1177     if (!flg2) { /* have not yet printed the options */
1178       PetscViewer viewer;
1179       ierr = PetscViewerCreate(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr);
1180       ierr = PetscViewerSetType(viewer,PETSCVIEWERASCII);CHKERRQ(ierr);
1181       ierr = PetscOptionsView(NULL,viewer);CHKERRQ(ierr);
1182       ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1183     }
1184     if (!nopt) {
1185       ierr = PetscPrintf(PETSC_COMM_WORLD,"There are no unused options.\n");CHKERRQ(ierr);
1186     } else if (nopt == 1) {
1187       ierr = PetscPrintf(PETSC_COMM_WORLD,"There is one unused database option. It is:\n");CHKERRQ(ierr);
1188     } else {
1189       ierr = PetscPrintf(PETSC_COMM_WORLD,"There are %D unused database options. They are:\n",nopt);CHKERRQ(ierr);
1190     }
1191   }
1192 #if defined(PETSC_USE_DEBUG)
1193   if (nopt && !flg3 && !flg1) {
1194     ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! There are options you set that were not used!\n");CHKERRQ(ierr);
1195     ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! could be spelling mistake, etc!\n");CHKERRQ(ierr);
1196     ierr = PetscOptionsLeft(NULL);CHKERRQ(ierr);
1197   } else if (nopt && flg3) {
1198 #else
1199   if (nopt && flg3) {
1200 #endif
1201     ierr = PetscOptionsLeft(NULL);CHKERRQ(ierr);
1202   }
1203 
1204 #if defined(PETSC_HAVE_SAWS)
1205   if (!PetscGlobalRank) {
1206     ierr = PetscStackSAWsViewOff();CHKERRQ(ierr);
1207     PetscStackCallSAWs(SAWs_Finalize,());
1208   }
1209 #endif
1210 
1211 #if defined(PETSC_USE_LOG)
1212   /*
1213        List all objects the user may have forgot to free
1214   */
1215   if (PetscObjectsLog) {
1216     ierr = PetscOptionsHasName(NULL,NULL,"-objects_dump",&flg1);CHKERRQ(ierr);
1217     if (flg1) {
1218       MPI_Comm local_comm;
1219       char     string[64];
1220 
1221       ierr = PetscOptionsGetString(NULL,NULL,"-objects_dump",string,64,NULL);CHKERRQ(ierr);
1222       ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRQ(ierr);
1223       ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr);
1224       ierr = PetscObjectsDump(stdout,(string[0] == 'a') ? PETSC_TRUE : PETSC_FALSE);CHKERRQ(ierr);
1225       ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr);
1226       ierr = MPI_Comm_free(&local_comm);CHKERRQ(ierr);
1227     }
1228   }
1229 #endif
1230 
1231 #if defined(PETSC_USE_LOG)
1232   PetscObjectsCounts    = 0;
1233   PetscObjectsMaxCounts = 0;
1234   ierr = PetscFree(PetscObjects);CHKERRQ(ierr);
1235 #endif
1236 
1237   /*
1238      Destroy any packages that registered a finalize
1239   */
1240   ierr = PetscRegisterFinalizeAll();CHKERRQ(ierr);
1241 
1242 #if defined(PETSC_USE_LOG)
1243   ierr = PetscLogDestroy();CHKERRQ(ierr);
1244 #endif
1245 
1246   /*
1247      Print PetscFunctionLists that have not been properly freed
1248 
1249   ierr = PetscFunctionListPrintAll();CHKERRQ(ierr);
1250   */
1251 
1252   if (petsc_history) {
1253     ierr = PetscCloseHistoryFile(&petsc_history);CHKERRQ(ierr);
1254     petsc_history = 0;
1255   }
1256   ierr = PetscOptionsHelpPrintedDestroy(&PetscOptionsHelpPrintedSingleton);CHKERRQ(ierr);
1257 
1258   ierr = PetscInfoAllow(PETSC_FALSE,NULL);CHKERRQ(ierr);
1259 
1260 #if !defined(PETSC_HAVE_THREADSAFETY)
1261   {
1262     char fname[PETSC_MAX_PATH_LEN];
1263     FILE *fd;
1264     int  err;
1265 
1266     fname[0] = 0;
1267 
1268     ierr = PetscOptionsGetString(NULL,NULL,"-malloc_dump",fname,250,&flg1);CHKERRQ(ierr);
1269     flg2 = PETSC_FALSE;
1270     ierr = PetscOptionsGetBool(NULL,NULL,"-malloc_test",&flg2,NULL);CHKERRQ(ierr);
1271 #if defined(PETSC_USE_DEBUG)
1272     if (PETSC_RUNNING_ON_VALGRIND) flg2 = PETSC_FALSE;
1273 #else
1274     flg2 = PETSC_FALSE;         /* Skip reporting for optimized builds regardless of -malloc_test */
1275 #endif
1276     if (flg1 && fname[0]) {
1277       char sname[PETSC_MAX_PATH_LEN];
1278 
1279       sprintf(sname,"%s_%d",fname,rank);
1280       fd   = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname);
1281       ierr = PetscMallocDump(fd);CHKERRQ(ierr);
1282       err  = fclose(fd);
1283       if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file");
1284     } else if (flg1 || flg2) {
1285       MPI_Comm local_comm;
1286 
1287       ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRQ(ierr);
1288       ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr);
1289       ierr = PetscMallocDump(stdout);CHKERRQ(ierr);
1290       ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr);
1291       ierr = MPI_Comm_free(&local_comm);CHKERRQ(ierr);
1292     }
1293   }
1294 
1295   {
1296     char fname[PETSC_MAX_PATH_LEN];
1297     FILE *fd = NULL;
1298 
1299     fname[0] = 0;
1300 
1301     ierr = PetscOptionsGetString(NULL,NULL,"-malloc_log",fname,250,&flg1);CHKERRQ(ierr);
1302     ierr = PetscOptionsHasName(NULL,NULL,"-malloc_log_threshold",&flg2);CHKERRQ(ierr);
1303     if (flg1 && fname[0]) {
1304       int err;
1305 
1306       if (!rank) {
1307         fd = fopen(fname,"w");
1308         if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",fname);
1309       }
1310       ierr = PetscMallocDumpLog(fd);CHKERRQ(ierr);
1311       if (fd) {
1312         err = fclose(fd);
1313         if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file");
1314       }
1315     } else if (flg1 || flg2) {
1316       ierr = PetscMallocDumpLog(stdout);CHKERRQ(ierr);
1317     }
1318   }
1319 #endif
1320 
1321   /*
1322      Close any open dynamic libraries
1323   */
1324   ierr = PetscFinalize_DynamicLibraries();CHKERRQ(ierr);
1325 
1326 #if defined(PETSC_HAVE_CUDA)
1327   flg  = PETSC_TRUE;
1328   ierr = PetscOptionsGetBool(NULL,NULL,"-cublas",&flg,NULL);CHKERRQ(ierr);
1329   if (flg) {
1330     PetscInt p;
1331     for (p = 0; p < PetscGlobalSize; ++p) {
1332       if (p == PetscGlobalRank) {
1333         if (cublasv2handle) {
1334           cberr = cublasDestroy(cublasv2handle);CHKERRCUBLAS(cberr);
1335         }
1336       }
1337       ierr = MPI_Barrier(PETSC_COMM_WORLD);CHKERRQ(ierr);
1338     }
1339   }
1340 #endif
1341 
1342   /* Can be destroyed only after all the options are used */
1343   ierr = PetscOptionsDestroyDefault();CHKERRQ(ierr);
1344 
1345   PetscGlobalArgc = 0;
1346   PetscGlobalArgs = 0;
1347 
1348 #if defined(PETSC_USE_REAL___FLOAT128)
1349   ierr = MPI_Type_free(&MPIU___FLOAT128);CHKERRQ(ierr);
1350 #if defined(PETSC_HAVE_COMPLEX)
1351   ierr = MPI_Type_free(&MPIU___COMPLEX128);CHKERRQ(ierr);
1352 #endif
1353   ierr = MPI_Op_free(&MPIU_MAX);CHKERRQ(ierr);
1354   ierr = MPI_Op_free(&MPIU_MIN);CHKERRQ(ierr);
1355 #elif defined(PETSC_USE_REAL___FP16)
1356   ierr = MPI_Type_free(&MPIU___FP16);CHKERRQ(ierr);
1357   ierr = MPI_Op_free(&MPIU_MAX);CHKERRQ(ierr);
1358   ierr = MPI_Op_free(&MPIU_MIN);CHKERRQ(ierr);
1359 #endif
1360 
1361 #if defined(PETSC_HAVE_COMPLEX)
1362 #if !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)
1363   ierr = MPI_Type_free(&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr);
1364   ierr = MPI_Type_free(&MPIU_C_COMPLEX);CHKERRQ(ierr);
1365 #endif
1366 #endif
1367 
1368 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16)
1369   ierr = MPI_Op_free(&MPIU_SUM);CHKERRQ(ierr);
1370 #endif
1371 
1372   ierr = MPI_Type_free(&MPIU_2SCALAR);CHKERRQ(ierr);
1373 #if defined(PETSC_USE_64BIT_INDICES) || !defined(MPI_2INT)
1374   ierr = MPI_Type_free(&MPIU_2INT);CHKERRQ(ierr);
1375 #endif
1376   ierr = MPI_Op_free(&MPIU_MAXSUM_OP);CHKERRQ(ierr);
1377 
1378   /*
1379      Destroy any known inner MPI_Comm's and attributes pointing to them
1380      Note this will not destroy any new communicators the user has created.
1381 
1382      If all PETSc objects were not destroyed those left over objects will have hanging references to
1383      the MPI_Comms that were freed; but that is ok because those PETSc objects will never be used again
1384  */
1385   {
1386     PetscCommCounter *counter;
1387     PetscMPIInt      flg;
1388     MPI_Comm         icomm;
1389     union {MPI_Comm comm; void *ptr;} ucomm;
1390     ierr = MPI_Attr_get(PETSC_COMM_SELF,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRQ(ierr);
1391     if (flg) {
1392       icomm = ucomm.comm;
1393       ierr = MPI_Attr_get(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRQ(ierr);
1394       if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory");
1395 
1396       ierr = MPI_Attr_delete(PETSC_COMM_SELF,Petsc_InnerComm_keyval);CHKERRQ(ierr);
1397       ierr = MPI_Attr_delete(icomm,Petsc_Counter_keyval);CHKERRQ(ierr);
1398       ierr = MPI_Comm_free(&icomm);CHKERRQ(ierr);
1399     }
1400     ierr = MPI_Attr_get(PETSC_COMM_WORLD,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRQ(ierr);
1401     if (flg) {
1402       icomm = ucomm.comm;
1403       ierr = MPI_Attr_get(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRQ(ierr);
1404       if (!flg) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory");
1405 
1406       ierr = MPI_Attr_delete(PETSC_COMM_WORLD,Petsc_InnerComm_keyval);CHKERRQ(ierr);
1407       ierr = MPI_Attr_delete(icomm,Petsc_Counter_keyval);CHKERRQ(ierr);
1408       ierr = MPI_Comm_free(&icomm);CHKERRQ(ierr);
1409     }
1410   }
1411 
1412   ierr = MPI_Keyval_free(&Petsc_Counter_keyval);CHKERRQ(ierr);
1413   ierr = MPI_Keyval_free(&Petsc_InnerComm_keyval);CHKERRQ(ierr);
1414   ierr = MPI_Keyval_free(&Petsc_OuterComm_keyval);CHKERRQ(ierr);
1415 
1416   ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockOpen);CHKERRQ(ierr);
1417   ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockStdout);CHKERRQ(ierr);
1418   ierr = PetscSpinlockDestroy(&PetscViewerASCIISpinLockStderr);CHKERRQ(ierr);
1419   ierr = PetscSpinlockDestroy(&PetscCommSpinLock);CHKERRQ(ierr);
1420 
1421   if (PetscBeganMPI) {
1422 #if defined(PETSC_HAVE_MPI_FINALIZED)
1423     PetscMPIInt flag;
1424     ierr = MPI_Finalized(&flag);CHKERRQ(ierr);
1425     if (flag) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_LIB,"MPI_Finalize() has already been called, even though MPI_Init() was called by PetscInitialize()");
1426 #endif
1427     ierr = MPI_Finalize();CHKERRQ(ierr);
1428   }
1429 /*
1430 
1431      Note: In certain cases PETSC_COMM_WORLD is never MPI_Comm_free()ed because
1432    the communicator has some outstanding requests on it. Specifically if the
1433    flag PETSC_HAVE_BROKEN_REQUEST_FREE is set (for IBM MPI implementation). See
1434    src/vec/utils/vpscat.c. Due to this the memory allocated in PetscCommDuplicate()
1435    is never freed as it should be. Thus one may obtain messages of the form
1436    [ 1] 8 bytes PetscCommDuplicate() line 645 in src/sys/mpiu.c indicating the
1437    memory was not freed.
1438 
1439 */
1440   ierr = PetscMallocClear();CHKERRQ(ierr);
1441 
1442   PetscInitializeCalled = PETSC_FALSE;
1443   PetscFinalizeCalled   = PETSC_TRUE;
1444   PetscFunctionReturn(0);
1445 }
1446 
1447 #if defined(PETSC_MISSING_LAPACK_lsame_)
1448 PETSC_EXTERN int lsame_(char *a,char *b)
1449 {
1450   if (*a == *b) return 1;
1451   if (*a + 32 == *b) return 1;
1452   if (*a - 32 == *b) return 1;
1453   return 0;
1454 }
1455 #endif
1456 
1457 #if defined(PETSC_MISSING_LAPACK_lsame)
1458 PETSC_EXTERN int lsame(char *a,char *b)
1459 {
1460   if (*a == *b) return 1;
1461   if (*a + 32 == *b) return 1;
1462   if (*a - 32 == *b) return 1;
1463   return 0;
1464 }
1465 #endif
1466