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