xref: /petsc/src/sys/objects/pinit.c (revision 1cda70a7b7f993daa62b160574fd531aa3ebf25e)
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 <SAWs.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_test - like -malloc_dump -malloc_debug, but only active for debugging builds
602 .  -fp_trap - Stops on floating point exceptions (Note that on the
603               IBM RS6000 this slows code by at least a factor of 10.)
604 .  -no_signal_handler - Indicates not to trap error signals
605 .  -shared_tmp - indicates /tmp directory is shared by all processors
606 .  -not_shared_tmp - each processor has own /tmp
607 .  -tmp - alternative name of /tmp directory
608 .  -get_total_flops - returns total flops done by all processors
609 .  -memory_info - Print memory usage at end of run
610 -  -server <port> - start PETSc webserver (default port is 8080)
611 
612    Options Database Keys for Profiling:
613    See the <a href="../../docs/manual.pdf#nameddest=ch_profiling">profiling chapter of the users manual</a> for details.
614 +  -info <optional filename> - Prints verbose information to the screen
615 .  -info_exclude <null,vec,mat,pc,ksp,snes,ts> - Excludes some of the verbose messages
616 .  -log_sync - Log the synchronization in scatters, inner products and norms
617 .  -log_trace [filename] - Print traces of all PETSc calls to the screen (useful to determine where a program
618         hangs without running in the debugger).  See PetscLogTraceBegin().
619 .  -log_summary [filename] - Prints summary of flop and timing information to screen. If the filename is specified the
620         summary is written to the file.  See PetscLogView().
621 .  -log_summary_python [filename] - Prints data on of flop and timing usage to a file or screen. See PetscLogPrintSViewPython().
622 .  -log_all [filename] - Logs extensive profiling information  See PetscLogDump().
623 .  -log [filename] - Logs basic profiline information  See PetscLogDump().
624 -  -log_mpe [filename] - Creates a logfile viewable by the utility Jumpshot (in MPICH distribution)
625 
626     Only one of -log_trace, -log_summary, -log_all, -log, or -log_mpe may be used at a time
627 
628    Environmental Variables:
629 +   PETSC_TMP - alternative tmp directory
630 .   PETSC_SHARED_TMP - tmp is shared by all processes
631 .   PETSC_NOT_SHARED_TMP - each process has its own private tmp
632 .   PETSC_VIEWER_SOCKET_PORT - socket number to use for socket viewer
633 -   PETSC_VIEWER_SOCKET_MACHINE - machine to use for socket viewer to connect to
634 
635 
636    Level: beginner
637 
638    Notes:
639    If for some reason you must call MPI_Init() separately, call
640    it before PetscInitialize().
641 
642    Fortran Version:
643    In Fortran this routine has the format
644 $       call PetscInitialize(file,ierr)
645 
646 +   ierr - error return code
647 -  file - [optional] PETSc database file, also checks ~username/.petscrc and .petscrc use NULL_CHARACTER to not check for
648           code specific file. Use -skip_petscrc in the code specific file to skip the .petscrc files
649 
650    Important Fortran Note:
651    In Fortran, you MUST use NULL_CHARACTER to indicate a
652    null character string; you CANNOT just use NULL as
653    in the C version. See the <a href="../../docs/manual.pdf">users manual</a> for details.
654 
655    If your main program is C but you call Fortran code that also uses PETSc you need to call PetscInitializeFortran() soon after
656    calling PetscInitialize().
657 
658    Concepts: initializing PETSc
659 
660 .seealso: PetscFinalize(), PetscInitializeFortran(), PetscGetArgs(), PetscInitializeNoArguments()
661 
662 @*/
663 PetscErrorCode  PetscInitialize(int *argc,char ***args,const char file[],const char help[])
664 {
665   PetscErrorCode ierr;
666   PetscMPIInt    flag, size;
667   PetscInt       nodesize;
668   PetscBool      flg;
669   char           hostname[256];
670 
671   PetscFunctionBegin;
672   if (PetscInitializeCalled) PetscFunctionReturn(0);
673 
674   /* these must be initialized in a routine, not as a constant declaration*/
675   PETSC_STDOUT = stdout;
676   PETSC_STDERR = stderr;
677 
678   ierr = PetscOptionsCreate();CHKERRQ(ierr);
679 
680   /*
681      We initialize the program name here (before MPI_Init()) because MPICH has a bug in
682      it that it sets args[0] on all processors to be args[0] on the first processor.
683   */
684   if (argc && *argc) {
685     ierr = PetscSetProgramName(**args);CHKERRQ(ierr);
686   } else {
687     ierr = PetscSetProgramName("Unknown Name");CHKERRQ(ierr);
688   }
689 
690   ierr = MPI_Initialized(&flag);CHKERRQ(ierr);
691   if (!flag) {
692     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");
693 #if defined(PETSC_HAVE_MPI_INIT_THREAD)
694     {
695       PetscMPIInt provided;
696       ierr = MPI_Init_thread(argc,args,MPI_THREAD_FUNNELED,&provided);CHKERRQ(ierr);
697     }
698 #else
699     ierr = MPI_Init(argc,args);CHKERRQ(ierr);
700 #endif
701     PetscBeganMPI = PETSC_TRUE;
702   }
703   if (argc && args) {
704     PetscGlobalArgc = *argc;
705     PetscGlobalArgs = *args;
706   }
707   PetscFinalizeCalled = PETSC_FALSE;
708 
709   if (PETSC_COMM_WORLD == MPI_COMM_NULL) PETSC_COMM_WORLD = MPI_COMM_WORLD;
710   ierr = MPI_Comm_set_errhandler(PETSC_COMM_WORLD,MPI_ERRORS_RETURN);CHKERRQ(ierr);
711 
712   /* Done after init due to a bug in MPICH-GM? */
713   ierr = PetscErrorPrintfInitialize();CHKERRQ(ierr);
714 
715   ierr = MPI_Comm_rank(MPI_COMM_WORLD,&PetscGlobalRank);CHKERRQ(ierr);
716   ierr = MPI_Comm_size(MPI_COMM_WORLD,&PetscGlobalSize);CHKERRQ(ierr);
717 
718   MPIU_BOOL = MPI_INT;
719   MPIU_ENUM = MPI_INT;
720 
721   /*
722      Initialized the global complex variable; this is because with
723      shared libraries the constructors for global variables
724      are not called; at least on IRIX.
725   */
726 #if defined(PETSC_HAVE_COMPLEX)
727   {
728 #if defined(PETSC_CLANGUAGE_CXX)
729     PetscComplex ic(0.0,1.0);
730     PETSC_i = ic;
731 #elif defined(PETSC_CLANGUAGE_C)
732     PETSC_i = _Complex_I;
733 #endif
734   }
735 
736 #if !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)
737   ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr);
738   ierr = MPI_Type_commit(&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr);
739   ierr = MPI_Type_contiguous(2,MPI_FLOAT,&MPIU_C_COMPLEX);CHKERRQ(ierr);
740   ierr = MPI_Type_commit(&MPIU_C_COMPLEX);CHKERRQ(ierr);
741 #endif
742 #endif /* PETSC_HAVE_COMPLEX */
743 
744   /*
745      Create the PETSc MPI reduction operator that sums of the first
746      half of the entries and maxes the second half.
747   */
748   ierr = MPI_Op_create(PetscMaxSum_Local,1,&PetscMaxSum_Op);CHKERRQ(ierr);
749 
750 #if defined(PETSC_USE_REAL___FLOAT128)
751   ierr = MPI_Type_contiguous(2,MPI_DOUBLE,&MPIU___FLOAT128);CHKERRQ(ierr);
752   ierr = MPI_Type_commit(&MPIU___FLOAT128);CHKERRQ(ierr);
753 #if defined(PETSC_HAVE_COMPLEX)
754   ierr = MPI_Type_contiguous(4,MPI_DOUBLE,&MPIU___COMPLEX128);CHKERRQ(ierr);
755   ierr = MPI_Type_commit(&MPIU___COMPLEX128);CHKERRQ(ierr);
756 #endif
757   ierr = MPI_Op_create(PetscMax_Local,1,&MPIU_MAX);CHKERRQ(ierr);
758   ierr = MPI_Op_create(PetscMin_Local,1,&MPIU_MIN);CHKERRQ(ierr);
759 #endif
760 
761 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128)
762   ierr = MPI_Op_create(PetscSum_Local,1,&MPIU_SUM);CHKERRQ(ierr);
763 #endif
764 
765   ierr = MPI_Type_contiguous(2,MPIU_SCALAR,&MPIU_2SCALAR);CHKERRQ(ierr);
766   ierr = MPI_Type_commit(&MPIU_2SCALAR);CHKERRQ(ierr);
767   ierr = MPI_Op_create(PetscADMax_Local,1,&PetscADMax_Op);CHKERRQ(ierr);
768   ierr = MPI_Op_create(PetscADMin_Local,1,&PetscADMin_Op);CHKERRQ(ierr);
769 
770 #if defined(PETSC_USE_64BIT_INDICES) || !defined(MPI_2INT)
771   ierr = MPI_Type_contiguous(2,MPIU_INT,&MPIU_2INT);CHKERRQ(ierr);
772   ierr = MPI_Type_commit(&MPIU_2INT);CHKERRQ(ierr);
773 #endif
774 
775 
776   /*
777      Attributes to be set on PETSc communicators
778   */
779   ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelCounter,&Petsc_Counter_keyval,(void*)0);CHKERRQ(ierr);
780   ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelComm_Outer,&Petsc_InnerComm_keyval,(void*)0);CHKERRQ(ierr);
781   ierr = MPI_Keyval_create(MPI_NULL_COPY_FN,Petsc_DelComm_Inner,&Petsc_OuterComm_keyval,(void*)0);CHKERRQ(ierr);
782 
783   /*
784      Build the options database
785   */
786   ierr = PetscOptionsInsert(argc,args,file);CHKERRQ(ierr);
787 
788 
789   /*
790      Print main application help message
791   */
792   ierr = PetscOptionsHasName(NULL,"-help",&flg);CHKERRQ(ierr);
793   if (help && flg) {
794     ierr = PetscPrintf(PETSC_COMM_WORLD,help);CHKERRQ(ierr);
795   }
796   ierr = PetscOptionsCheckInitial_Private();CHKERRQ(ierr);
797 
798 #if defined(PETSC_HAVE_SAWS)
799   {
800     char      cert[PETSC_MAX_PATH_LEN],root[PETSC_MAX_PATH_LEN],intro[4024],programname[64],appline[256];
801     int       port;
802     PetscBool rootlocal = PETSC_FALSE;
803 
804     ierr = PetscOptionsHasName(NULL,"-saws_log",&flg);CHKERRQ(ierr);
805     if (flg) {
806       char  sawslog[PETSC_MAX_PATH_LEN];
807 
808       ierr = PetscOptionsGetString(NULL,"-saws_log",sawslog,PETSC_MAX_PATH_LEN,NULL);CHKERRQ(ierr);
809       if (sawslog[0]) {
810         ierr = SAWs_Set_Use_Logfile(sawslog);CHKERRQ(ierr);
811       } else {
812         ierr = SAWs_Set_Use_Logfile(NULL);CHKERRQ(ierr);
813       }
814     }
815     ierr = PetscOptionsGetString(NULL,"-saws_https",cert,PETSC_MAX_PATH_LEN,&flg);CHKERRQ(ierr);
816     if (flg) {
817       ierr = SAWs_Set_Use_HTTPS(cert);CHKERRQ(ierr);
818     }
819     ierr = PetscOptionsGetInt(NULL,"-saws_port",&port,&flg);CHKERRQ(ierr);
820     if (flg) {
821       ierr = SAWs_Set_Port(port);CHKERRQ(ierr);
822     }
823     ierr = PetscOptionsGetString(NULL,"-saws_root",root,PETSC_MAX_PATH_LEN,&flg);CHKERRQ(ierr);
824     if (flg) {
825       ierr = SAWs_Set_Document_Root(root);CHKERRQ(ierr);
826       ierr = PetscStrcmp(root,".",&rootlocal);CHKERRQ(ierr);
827     }
828     ierr = PetscGetProgramName(programname,64);CHKERRQ(ierr);
829     if (rootlocal) {
830       ierr = PetscSNPrintf(appline,256,"%s.c.html",programname);CHKERRQ(ierr);
831       ierr = PetscTestFile(appline,'r',&rootlocal);CHKERRQ(ierr);
832     }
833     if (rootlocal && help) {
834       ierr = PetscSNPrintf(appline,256,"<center> Running <a href=\"%s.c.html\">%s</a> which %s </center><br>\n",programname,programname,help);
835     } else if (help) {
836       ierr = PetscSNPrintf(appline,256,"<center> Running %s which %s </center><br>\n",programname,help);
837     } else {
838       ierr = PetscSNPrintf(appline,256,"<center> Running %s</center><br>\n",programname);
839     }
840 
841     ierr = PetscSNPrintf(intro,4024,"<body>\n"
842                                     "<center><h2> PETSc Application Web server powered by <a href=\"https://bitbucket.org/saws/saws\">SAWs</a> </h2></center>\n"
843                                     "%s"
844                                     "<center>This is the default PETSc application dashboard, from it you can access any published PETSc objects or logging data</center><br>\n",appline);
845     ierr = SAWs_Set_Default_Body(0,intro);
846     ierr = SAWs_Initialize();CHKERRQ(ierr);
847   }
848 
849 #endif
850 
851   /* SHOULD PUT IN GUARDS: Make sure logging is initialized, even if we do not print it out */
852 #if defined(PETSC_USE_LOG)
853   ierr = PetscLogBegin_Private();CHKERRQ(ierr);
854 #endif
855 
856   /*
857      Load the dynamic libraries (on machines that support them), this registers all
858      the solvers etc. (On non-dynamic machines this initializes the PetscDraw and PetscViewer classes)
859   */
860   ierr = PetscInitialize_DynamicLibraries();CHKERRQ(ierr);
861 
862   ierr = MPI_Comm_size(PETSC_COMM_WORLD,&size);CHKERRQ(ierr);
863   ierr = PetscInfo1(0,"PETSc successfully started: number of processors = %d\n",size);CHKERRQ(ierr);
864   ierr = PetscGetHostName(hostname,256);CHKERRQ(ierr);
865   ierr = PetscInfo1(0,"Running on machine: %s\n",hostname);CHKERRQ(ierr);
866 
867   ierr = PetscOptionsCheckInitial_Components();CHKERRQ(ierr);
868   /* Check the options database for options related to the options database itself */
869   ierr = PetscOptionsSetFromOptions();CHKERRQ(ierr);
870 
871 #if defined(PETSC_USE_PETSC_MPI_EXTERNAL32)
872   /*
873       Tell MPI about our own data representation converter, this would/should be used if extern32 is not supported by the MPI
874 
875       Currently not used because it is not supported by MPICH.
876   */
877 #if !defined(PETSC_WORDS_BIGENDIAN)
878   ierr = MPI_Register_datarep((char*)"petsc",PetscDataRep_read_conv_fn,PetscDataRep_write_conv_fn,PetscDataRep_extent_fn,NULL);CHKERRQ(ierr);
879 #endif
880 #endif
881 
882   ierr = PetscOptionsGetInt(NULL,"-hmpi_spawn_size",&nodesize,&flg);CHKERRQ(ierr);
883   if (flg) {
884 #if defined(PETSC_HAVE_MPI_COMM_SPAWN)
885     ierr = PetscHMPISpawn((PetscMPIInt) nodesize);CHKERRQ(ierr); /* worker nodes never return from here; they go directly to PetscEnd() */
886 #else
887     SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"PETSc built without MPI 2 (MPI_Comm_spawn) support, use -hmpi_merge_size instead");
888 #endif
889   } else {
890     ierr = PetscOptionsGetInt(NULL,"-hmpi_merge_size",&nodesize,&flg);CHKERRQ(ierr);
891     if (flg) {
892       ierr = PetscHMPIMerge((PetscMPIInt) nodesize,NULL,NULL);CHKERRQ(ierr);
893       if (PetscHMPIWorker) { /* if worker then never enter user code */
894         PetscInitializeCalled = PETSC_TRUE;
895         PetscEnd();
896       }
897     }
898   }
899 
900 #if defined(PETSC_HAVE_CUDA)
901   {
902     PetscMPIInt p;
903     for (p = 0; p < PetscGlobalSize; ++p) {
904       if (p == PetscGlobalRank) cublasInit();
905       ierr = MPI_Barrier(PETSC_COMM_WORLD);CHKERRQ(ierr);
906     }
907   }
908 #endif
909 
910   ierr = PetscOptionsHasName(NULL,"-python",&flg);CHKERRQ(ierr);
911   if (flg) {
912     PetscInitializeCalled = PETSC_TRUE;
913     ierr = PetscPythonInitialize(NULL,NULL);CHKERRQ(ierr);
914   }
915 
916   ierr = PetscThreadCommInitializePackage();CHKERRQ(ierr);
917 
918   /*
919       Setup building of stack frames for all function calls
920   */
921 #if defined(PETSC_USE_DEBUG)
922   PetscThreadLocalRegister((PetscThreadKey*)&petscstack); /* Creates petscstack_key if needed */
923   ierr = PetscStackCreate();CHKERRQ(ierr);
924 #endif
925 
926 #if defined(PETSC_SERIALIZE_FUNCTIONS)
927   ierr = PetscFPTCreate(10000);CHKERRQ(ierr);
928 #endif
929 
930   ierr = PetscCitationsInitialize();CHKERRQ(ierr);
931 
932   /*
933       Once we are completedly initialized then we can set this variables
934   */
935   PetscInitializeCalled = PETSC_TRUE;
936   PetscFunctionReturn(0);
937 }
938 
939 extern PetscObject *PetscObjects;
940 extern PetscInt    PetscObjectsCounts, PetscObjectsMaxCounts;
941 
942 #undef __FUNCT__
943 #define __FUNCT__ "PetscFinalize"
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 
978   PetscFunctionBegin;
979   if (!PetscInitializeCalled) {
980     printf("PetscInitialize() must be called before PetscFinalize()\n");
981     PetscFunctionReturn(PETSC_ERR_ARG_WRONGSTATE);
982   }
983   ierr = PetscInfo(NULL,"PetscFinalize() called\n");CHKERRQ(ierr);
984 
985   ierr = MPI_Comm_rank(PETSC_COMM_WORLD,&rank);CHKERRQ(ierr);
986 
987   ierr = PetscOptionsHasName(NULL,"-citations",&flg);CHKERRQ(ierr);
988   if (flg) {
989     char  *cits, filename[PETSC_MAX_PATH_LEN];
990     FILE  *fd = PETSC_STDOUT;
991 
992     ierr = PetscOptionsGetString(NULL,"-citations",filename,PETSC_MAX_PATH_LEN,NULL);CHKERRQ(ierr);
993     if (filename[0]) {
994       ierr = PetscFOpen(PETSC_COMM_WORLD,filename,"w",&fd);CHKERRQ(ierr);
995     }
996     ierr = PetscSegBufferGet(PetscCitationsList,1,&cits);CHKERRQ(ierr);
997     cits[0] = 0;
998     ierr = PetscSegBufferExtractAlloc(PetscCitationsList,&cits);CHKERRQ(ierr);
999     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"If you publish results based on this computation please cite the following:\n");CHKERRQ(ierr);
1000     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr);
1001     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"%s",cits);CHKERRQ(ierr);
1002     ierr = PetscFPrintf(PETSC_COMM_WORLD,fd,"===========================================================================\n");CHKERRQ(ierr);
1003     ierr = PetscFClose(PETSC_COMM_WORLD,fd);CHKERRQ(ierr);
1004     ierr = PetscFree(cits);CHKERRQ(ierr);
1005   }
1006   ierr = PetscSegBufferDestroy(&PetscCitationsList);CHKERRQ(ierr);
1007 
1008 #if defined(PETSC_SERIALIZE_FUNCTIONS)
1009   ierr = PetscFPTDestroy();CHKERRQ(ierr);
1010 #endif
1011 
1012 
1013 #if defined(PETSC_HAVE_SAWS)
1014   flg = PETSC_FALSE;
1015   ierr = PetscOptionsGetBool(NULL,"-options_gui",&flg,NULL);CHKERRQ(ierr);
1016   if (flg) {
1017     ierr = PetscOptionsSAWsDestroy();CHKERRQ(ierr);
1018   }
1019 #endif
1020 
1021 #if defined(PETSC_HAVE_SERVER)
1022   flg1 = PETSC_FALSE;
1023   ierr = PetscOptionsGetBool(NULL,"-server",&flg1,NULL);CHKERRQ(ierr);
1024   if (flg1) {
1025     /*  this is a crude hack, but better than nothing */
1026     ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 petscwebserver","r",NULL);CHKERRQ(ierr);
1027   }
1028 #endif
1029 
1030 #if defined(PETSC_HAVE_X)
1031   flg1 = PETSC_FALSE;
1032   ierr = PetscOptionsGetBool(NULL,"-x_virtual",&flg1,NULL);CHKERRQ(ierr);
1033   if (flg1) {
1034     /*  this is a crude hack, but better than nothing */
1035     ierr = PetscPOpen(PETSC_COMM_WORLD,NULL,"pkill -9 Xvfb","r",NULL);CHKERRQ(ierr);
1036   }
1037 #endif
1038 
1039   ierr = PetscHMPIFinalize();CHKERRQ(ierr);
1040 
1041   ierr = PetscOptionsGetBool(NULL,"-malloc_info",&flg2,NULL);CHKERRQ(ierr);
1042   if (!flg2) {
1043     flg2 = PETSC_FALSE;
1044     ierr = PetscOptionsGetBool(NULL,"-memory_info",&flg2,NULL);CHKERRQ(ierr);
1045   }
1046   if (flg2) {
1047     ierr = PetscMemoryShowUsage(PETSC_VIEWER_STDOUT_WORLD,"Summary of Memory Usage in PETSc\n");CHKERRQ(ierr);
1048   }
1049 
1050 #if defined(PETSC_USE_LOG)
1051   flg1 = PETSC_FALSE;
1052   ierr = PetscOptionsGetBool(NULL,"-get_total_flops",&flg1,NULL);CHKERRQ(ierr);
1053   if (flg1) {
1054     PetscLogDouble flops = 0;
1055     ierr = MPI_Reduce(&petsc_TotalFlops,&flops,1,MPI_DOUBLE,MPI_SUM,0,PETSC_COMM_WORLD);CHKERRQ(ierr);
1056     ierr = PetscPrintf(PETSC_COMM_WORLD,"Total flops over all processors %g\n",flops);CHKERRQ(ierr);
1057   }
1058 #endif
1059 
1060 
1061 #if defined(PETSC_USE_LOG)
1062 #if defined(PETSC_HAVE_MPE)
1063   mname[0] = 0;
1064 
1065   ierr = PetscOptionsGetString(NULL,"-log_mpe",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1066   if (flg1) {
1067     if (mname[0]) {ierr = PetscLogMPEDump(mname);CHKERRQ(ierr);}
1068     else          {ierr = PetscLogMPEDump(0);CHKERRQ(ierr);}
1069   }
1070 #endif
1071   mname[0] = 0;
1072 
1073   ierr = PetscOptionsGetString(NULL,"-log_summary",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1074   if (flg1) {
1075     PetscViewer viewer;
1076     if (mname[0]) {
1077       ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr);
1078       ierr = PetscLogView(viewer);CHKERRQ(ierr);
1079       ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1080     } else {
1081       viewer = PETSC_VIEWER_STDOUT_WORLD;
1082       ierr   = PetscLogView(viewer);CHKERRQ(ierr);
1083     }
1084   }
1085 
1086   mname[0] = 0;
1087 
1088   ierr = PetscOptionsGetString(NULL,"-log_summary_python",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1089   if (flg1) {
1090     PetscViewer viewer;
1091     if (mname[0]) {
1092       ierr = PetscViewerASCIIOpen(PETSC_COMM_WORLD,mname,&viewer);CHKERRQ(ierr);
1093       ierr = PetscLogViewPython(viewer);CHKERRQ(ierr);
1094       ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1095     } else {
1096       viewer = PETSC_VIEWER_STDOUT_WORLD;
1097       ierr   = PetscLogViewPython(viewer);CHKERRQ(ierr);
1098     }
1099   }
1100 
1101   ierr = PetscOptionsGetString(NULL,"-log_detailed",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1102   if (flg1) {
1103     if (mname[0])  {ierr = PetscLogPrintDetailed(PETSC_COMM_WORLD,mname);CHKERRQ(ierr);}
1104     else           {ierr = PetscLogPrintDetailed(PETSC_COMM_WORLD,0);CHKERRQ(ierr);}
1105   }
1106 
1107   mname[0] = 0;
1108 
1109   ierr = PetscOptionsGetString(NULL,"-log_all",mname,PETSC_MAX_PATH_LEN,&flg1);CHKERRQ(ierr);
1110   ierr = PetscOptionsGetString(NULL,"-log",mname,PETSC_MAX_PATH_LEN,&flg2);CHKERRQ(ierr);
1111   if (flg1 || flg2) {
1112     if (mname[0]) PetscLogDump(mname);
1113     else          PetscLogDump(0);
1114   }
1115 #endif
1116 
1117   /*
1118      Free all objects registered with PetscObjectRegisterDestroy() such as PETSC_VIEWER_XXX_().
1119   */
1120   ierr = PetscObjectRegisterDestroyAll();CHKERRQ(ierr);
1121 
1122   ierr = PetscStackDestroy();CHKERRQ(ierr);
1123 
1124   flg1 = PETSC_FALSE;
1125   ierr = PetscOptionsGetBool(NULL,"-no_signal_handler",&flg1,NULL);CHKERRQ(ierr);
1126   if (!flg1) { ierr = PetscPopSignalHandler();CHKERRQ(ierr);}
1127   flg1 = PETSC_FALSE;
1128   ierr = PetscOptionsGetBool(NULL,"-mpidump",&flg1,NULL);CHKERRQ(ierr);
1129   if (flg1) {
1130     ierr = PetscMPIDump(stdout);CHKERRQ(ierr);
1131   }
1132   flg1 = PETSC_FALSE;
1133   flg2 = PETSC_FALSE;
1134   /* preemptive call to avoid listing this option in options table as unused */
1135   ierr = PetscOptionsHasName(NULL,"-malloc_dump",&flg1);CHKERRQ(ierr);
1136   ierr = PetscOptionsHasName(NULL,"-objects_dump",&flg1);CHKERRQ(ierr);
1137   ierr = PetscOptionsGetBool(NULL,"-options_table",&flg2,NULL);CHKERRQ(ierr);
1138 
1139   if (flg2) {
1140     PetscViewer viewer;
1141     ierr = PetscViewerASCIIGetStdout(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr);
1142     ierr = PetscOptionsView(viewer);CHKERRQ(ierr);
1143     ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1144   }
1145 
1146   /* to prevent PETSc -options_left from warning */
1147   ierr = PetscOptionsHasName(NULL,"-nox",&flg1);CHKERRQ(ierr);
1148   ierr = PetscOptionsHasName(NULL,"-nox_warning",&flg1);CHKERRQ(ierr);
1149 
1150   if (!PetscHMPIWorker) { /* worker processes skip this because they do not usually process options */
1151     flg3 = PETSC_FALSE; /* default value is required */
1152     ierr = PetscOptionsGetBool(NULL,"-options_left",&flg3,&flg1);CHKERRQ(ierr);
1153     ierr = PetscOptionsAllUsed(&nopt);CHKERRQ(ierr);
1154     if (flg3) {
1155       if (!flg2) { /* have not yet printed the options */
1156         PetscViewer viewer;
1157         ierr = PetscViewerASCIIGetStdout(PETSC_COMM_WORLD,&viewer);CHKERRQ(ierr);
1158         ierr = PetscOptionsView(viewer);CHKERRQ(ierr);
1159         ierr = PetscViewerDestroy(&viewer);CHKERRQ(ierr);
1160       }
1161       if (!nopt) {
1162         ierr = PetscPrintf(PETSC_COMM_WORLD,"There are no unused options.\n");CHKERRQ(ierr);
1163       } else if (nopt == 1) {
1164         ierr = PetscPrintf(PETSC_COMM_WORLD,"There is one unused database option. It is:\n");CHKERRQ(ierr);
1165       } else {
1166         ierr = PetscPrintf(PETSC_COMM_WORLD,"There are %D unused database options. They are:\n",nopt);CHKERRQ(ierr);
1167       }
1168     }
1169 #if defined(PETSC_USE_DEBUG)
1170     if (nopt && !flg3 && !flg1) {
1171       ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! There are options you set that were not used!\n");CHKERRQ(ierr);
1172       ierr = PetscPrintf(PETSC_COMM_WORLD,"WARNING! could be spelling mistake, etc!\n");CHKERRQ(ierr);
1173       ierr = PetscOptionsLeft();CHKERRQ(ierr);
1174     } else if (nopt && flg3) {
1175 #else
1176     if (nopt && flg3) {
1177 #endif
1178       ierr = PetscOptionsLeft();CHKERRQ(ierr);
1179     }
1180   }
1181 
1182 #if defined(PETSC_HAVE_SAWS)
1183   ierr = PetscStackSAWsViewOff();CHKERRQ(ierr);
1184   ierr = SAWs_Finalize();CHKERRQ(ierr);
1185 #endif
1186 
1187   {
1188     PetscThreadComm tcomm_world;
1189     ierr = PetscGetThreadCommWorld(&tcomm_world);CHKERRQ(ierr);
1190     /* Free global thread communicator */
1191     ierr = PetscThreadCommDestroy(&tcomm_world);CHKERRQ(ierr);
1192   }
1193 
1194   /*
1195        List all objects the user may have forgot to free
1196   */
1197   ierr = PetscOptionsHasName(NULL,"-objects_dump",&flg1);CHKERRQ(ierr);
1198   if (flg1) {
1199     MPI_Comm local_comm;
1200     char     string[64];
1201 
1202     ierr = PetscOptionsGetString(NULL,"-objects_dump",string,64,NULL);CHKERRQ(ierr);
1203     ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRQ(ierr);
1204     ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr);
1205     ierr = PetscObjectsDump(stdout,(string[0] == 'a') ? PETSC_TRUE : PETSC_FALSE);CHKERRQ(ierr);
1206     ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr);
1207     ierr = MPI_Comm_free(&local_comm);CHKERRQ(ierr);
1208   }
1209   PetscObjectsCounts    = 0;
1210   PetscObjectsMaxCounts = 0;
1211 
1212   ierr = PetscFree(PetscObjects);CHKERRQ(ierr);
1213 
1214 #if defined(PETSC_USE_LOG)
1215   ierr = PetscLogDestroy();CHKERRQ(ierr);
1216 #endif
1217 
1218   /*
1219      Destroy any packages that registered a finalize
1220   */
1221   ierr = PetscRegisterFinalizeAll();CHKERRQ(ierr);
1222 
1223   /*
1224      Destroy all the function registration lists created
1225   */
1226   ierr = PetscFinalize_DynamicLibraries();CHKERRQ(ierr);
1227 
1228   /*
1229      Print PetscFunctionLists that have not been properly freed
1230 
1231   ierr = PetscFunctionListPrintAll();CHKERRQ(ierr);
1232   */
1233 
1234   if (petsc_history) {
1235     ierr = PetscCloseHistoryFile(&petsc_history);CHKERRQ(ierr);
1236     petsc_history = 0;
1237   }
1238 
1239   ierr = PetscInfoAllow(PETSC_FALSE,NULL);CHKERRQ(ierr);
1240 
1241   {
1242     char fname[PETSC_MAX_PATH_LEN];
1243     FILE *fd;
1244     int  err;
1245 
1246     fname[0] = 0;
1247 
1248     ierr = PetscOptionsGetString(NULL,"-malloc_dump",fname,250,&flg1);CHKERRQ(ierr);
1249     flg2 = PETSC_FALSE;
1250     ierr = PetscOptionsGetBool(NULL,"-malloc_test",&flg2,NULL);CHKERRQ(ierr);
1251 #if defined(PETSC_USE_DEBUG)
1252     if (PETSC_RUNNING_ON_VALGRIND) flg2 = PETSC_FALSE;
1253 #else
1254     flg2 = PETSC_FALSE;         /* Skip reporting for optimized builds regardless of -malloc_test */
1255 #endif
1256     if (flg1 && fname[0]) {
1257       char sname[PETSC_MAX_PATH_LEN];
1258 
1259       sprintf(sname,"%s_%d",fname,rank);
1260       fd   = fopen(sname,"w"); if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",sname);
1261       ierr = PetscMallocDump(fd);CHKERRQ(ierr);
1262       err  = fclose(fd);
1263       if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file");
1264     } else if (flg1 || flg2) {
1265       MPI_Comm local_comm;
1266 
1267       ierr = MPI_Comm_dup(MPI_COMM_WORLD,&local_comm);CHKERRQ(ierr);
1268       ierr = PetscSequentialPhaseBegin_Private(local_comm,1);CHKERRQ(ierr);
1269       ierr = PetscMallocDump(stdout);CHKERRQ(ierr);
1270       ierr = PetscSequentialPhaseEnd_Private(local_comm,1);CHKERRQ(ierr);
1271       ierr = MPI_Comm_free(&local_comm);CHKERRQ(ierr);
1272     }
1273   }
1274 
1275   {
1276     char fname[PETSC_MAX_PATH_LEN];
1277     FILE *fd = NULL;
1278 
1279     fname[0] = 0;
1280 
1281     ierr = PetscOptionsGetString(NULL,"-malloc_log",fname,250,&flg1);CHKERRQ(ierr);
1282     ierr = PetscOptionsHasName(NULL,"-malloc_log_threshold",&flg2);CHKERRQ(ierr);
1283     if (flg1 && fname[0]) {
1284       int err;
1285 
1286       if (!rank) {
1287         fd = fopen(fname,"w");
1288         if (!fd) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_FILE_OPEN,"Cannot open log file: %s",fname);
1289       }
1290       ierr = PetscMallocDumpLog(fd);CHKERRQ(ierr);
1291       if (fd) {
1292         err = fclose(fd);
1293         if (err) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SYS,"fclose() failed on file");
1294       }
1295     } else if (flg1 || flg2) {
1296       ierr = PetscMallocDumpLog(stdout);CHKERRQ(ierr);
1297     }
1298   }
1299   /* Can be destroyed only after all the options are used */
1300   ierr = PetscOptionsDestroy();CHKERRQ(ierr);
1301 
1302   PetscGlobalArgc = 0;
1303   PetscGlobalArgs = 0;
1304 
1305 #if defined(PETSC_USE_REAL___FLOAT128)
1306   ierr = MPI_Type_free(&MPIU___FLOAT128);CHKERRQ(ierr);
1307 #if defined(PETSC_HAVE_COMPLEX)
1308   ierr = MPI_Type_free(&MPIU___COMPLEX128);CHKERRQ(ierr);
1309 #endif
1310   ierr = MPI_Op_free(&MPIU_MAX);CHKERRQ(ierr);
1311   ierr = MPI_Op_free(&MPIU_MIN);CHKERRQ(ierr);
1312 #endif
1313 
1314 #if defined(PETSC_HAVE_COMPLEX)
1315 #if !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)
1316   ierr = MPI_Type_free(&MPIU_C_DOUBLE_COMPLEX);CHKERRQ(ierr);
1317   ierr = MPI_Type_free(&MPIU_C_COMPLEX);CHKERRQ(ierr);
1318 #endif
1319 #endif
1320 
1321 #if (defined(PETSC_HAVE_COMPLEX) && !defined(PETSC_HAVE_MPI_C_DOUBLE_COMPLEX)) || defined(PETSC_USE_REAL___FLOAT128)
1322   ierr = MPI_Op_free(&MPIU_SUM);CHKERRQ(ierr);
1323 #endif
1324 
1325   ierr = MPI_Type_free(&MPIU_2SCALAR);CHKERRQ(ierr);
1326 #if defined(PETSC_USE_64BIT_INDICES) || !defined(MPI_2INT)
1327   ierr = MPI_Type_free(&MPIU_2INT);CHKERRQ(ierr);
1328 #endif
1329   ierr = MPI_Op_free(&PetscMaxSum_Op);CHKERRQ(ierr);
1330   ierr = MPI_Op_free(&PetscADMax_Op);CHKERRQ(ierr);
1331   ierr = MPI_Op_free(&PetscADMin_Op);CHKERRQ(ierr);
1332 
1333   /*
1334      Destroy any known inner MPI_Comm's and attributes pointing to them
1335      Note this will not destroy any new communicators the user has created.
1336 
1337      If all PETSc objects were not destroyed those left over objects will have hanging references to
1338      the MPI_Comms that were freed; but that is ok because those PETSc objects will never be used again
1339  */
1340   {
1341     PetscCommCounter *counter;
1342     PetscMPIInt      flg;
1343     MPI_Comm         icomm;
1344     union {MPI_Comm comm; void *ptr;} ucomm;
1345     ierr = MPI_Attr_get(PETSC_COMM_SELF,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRQ(ierr);
1346     if (flg) {
1347       icomm = ucomm.comm;
1348       ierr = MPI_Attr_get(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRQ(ierr);
1349       if (!flg) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory");
1350 
1351       ierr = MPI_Attr_delete(PETSC_COMM_SELF,Petsc_InnerComm_keyval);CHKERRQ(ierr);
1352       ierr = MPI_Attr_delete(icomm,Petsc_Counter_keyval);CHKERRQ(ierr);
1353       ierr = MPI_Comm_free(&icomm);CHKERRQ(ierr);
1354     }
1355     ierr = MPI_Attr_get(PETSC_COMM_WORLD,Petsc_InnerComm_keyval,&ucomm,&flg);CHKERRQ(ierr);
1356     if (flg) {
1357       icomm = ucomm.comm;
1358       ierr = MPI_Attr_get(icomm,Petsc_Counter_keyval,&counter,&flg);CHKERRQ(ierr);
1359       if (!flg) SETERRQ(PETSC_COMM_WORLD,PETSC_ERR_ARG_CORRUPT,"Inner MPI_Comm does not have expected tag/name counter, problem with corrupted memory");
1360 
1361       ierr = MPI_Attr_delete(PETSC_COMM_WORLD,Petsc_InnerComm_keyval);CHKERRQ(ierr);
1362       ierr = MPI_Attr_delete(icomm,Petsc_Counter_keyval);CHKERRQ(ierr);
1363       ierr = MPI_Comm_free(&icomm);CHKERRQ(ierr);
1364     }
1365   }
1366 
1367   ierr = MPI_Keyval_free(&Petsc_Counter_keyval);CHKERRQ(ierr);
1368   ierr = MPI_Keyval_free(&Petsc_InnerComm_keyval);CHKERRQ(ierr);
1369   ierr = MPI_Keyval_free(&Petsc_OuterComm_keyval);CHKERRQ(ierr);
1370 
1371 #if defined(PETSC_HAVE_CUDA)
1372   {
1373     PetscInt p;
1374     for (p = 0; p < PetscGlobalSize; ++p) {
1375       if (p == PetscGlobalRank) cublasShutdown();
1376       ierr = MPI_Barrier(PETSC_COMM_WORLD);CHKERRQ(ierr);
1377     }
1378   }
1379 #endif
1380 
1381   if (PetscBeganMPI) {
1382 #if defined(PETSC_HAVE_MPI_FINALIZED)
1383     PetscMPIInt flag;
1384     ierr = MPI_Finalized(&flag);CHKERRQ(ierr);
1385     if (flag) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_LIB,"MPI_Finalize() has already been called, even though MPI_Init() was called by PetscInitialize()");
1386 #endif
1387     ierr = MPI_Finalize();CHKERRQ(ierr);
1388   }
1389 /*
1390 
1391      Note: In certain cases PETSC_COMM_WORLD is never MPI_Comm_free()ed because
1392    the communicator has some outstanding requests on it. Specifically if the
1393    flag PETSC_HAVE_BROKEN_REQUEST_FREE is set (for IBM MPI implementation). See
1394    src/vec/utils/vpscat.c. Due to this the memory allocated in PetscCommDuplicate()
1395    is never freed as it should be. Thus one may obtain messages of the form
1396    [ 1] 8 bytes PetscCommDuplicate() line 645 in src/sys/mpiu.c indicating the
1397    memory was not freed.
1398 
1399 */
1400   ierr = PetscMallocClear();CHKERRQ(ierr);
1401 
1402   PetscInitializeCalled = PETSC_FALSE;
1403   PetscFinalizeCalled   = PETSC_TRUE;
1404   PetscFunctionReturn(ierr);
1405 }
1406 
1407 #if defined(PETSC_MISSING_LAPACK_lsame_)
1408 PETSC_EXTERN int lsame_(char *a,char *b)
1409 {
1410   if (*a == *b) return 1;
1411   if (*a + 32 == *b) return 1;
1412   if (*a - 32 == *b) return 1;
1413   return 0;
1414 }
1415 #endif
1416 
1417 #if defined(PETSC_MISSING_LAPACK_lsame)
1418 PETSC_EXTERN int lsame(char *a,char *b)
1419 {
1420   if (*a == *b) return 1;
1421   if (*a + 32 == *b) return 1;
1422   if (*a - 32 == *b) return 1;
1423   return 0;
1424 }
1425 #endif
1426