xref: /petsc/src/sys/mpiuni/mpi.c (revision 00d931fe9835bef04c3bcd2a9a1bf118d64cc4c2)
1 /*
2       This provides a few of the MPI-uni functions that cannot be implemented
3     with C macros
4 */
5 #include <petscsys.h>
6 #if !defined(__MPIUNI_H)
7 #error "Wrong mpi.h included! require mpi.h from MPIUNI"
8 #endif
9 #if !defined(PETSC_STDCALL)
10 #define PETSC_STDCALL
11 #endif
12 
13 #define MPI_SUCCESS 0
14 #define MPI_FAILURE 1
15 
16 void *MPIUNI_TMP         = 0;
17 int  MPIUNI_DATASIZE[10] = {sizeof(int),sizeof(float),sizeof(double),2*sizeof(double),sizeof(char),2*sizeof(int),4*sizeof(double),4,8,2*sizeof(double)};
18 /*
19        With MPI Uni there are exactly four distinct communicators:
20     MPI_COMM_SELF, MPI_COMM_WORLD, and a MPI_Comm_dup() of each of these (duplicates of duplicates return the same communictor)
21 
22     MPI_COMM_SELF and MPI_COMM_WORLD are MPI_Comm_free() in MPI_Finalize() but in general with PETSc,
23      the other communicators are freed once the last PETSc object is freed (before MPI_Finalize()).
24 
25 */
26 #define MAX_ATTR 128
27 #define MAX_COMM 128
28 
29 static int MaxComm = 2;
30 
31 typedef struct {
32   void *attribute_val;
33   int  active;
34 } MPI_Attr;
35 
36 typedef struct {
37   void                *extra_state;
38   MPI_Delete_function *del;
39 } MPI_Attr_keyval;
40 
41 static MPI_Attr_keyval attr_keyval[MAX_ATTR];
42 static MPI_Attr        attr[MAX_COMM][MAX_ATTR];
43 static int             num_attr = 1,mpi_tag_ub = 100000000;
44 static void*           MPIUNIF_mpi_in_place = 0;
45 
46 #if defined(__cplusplus)
47 extern "C" {
48 #endif
49 
50 /*
51    To avoid problems with prototypes to the system memcpy() it is duplicated here
52 */
53 int MPIUNI_Memcpy(void *a,const void *b,int n)
54 {
55   int  i;
56   char *aa= (char*)a;
57   char *bb= (char*)b;
58 
59   if (a == MPI_IN_PLACE || a == MPIUNIF_mpi_in_place) return 0;
60   if (b == MPI_IN_PLACE || b == MPIUNIF_mpi_in_place) return 0;
61   for (i=0; i<n; i++) aa[i] = bb[i];
62   return 0;
63 }
64 
65 /*
66    Used to set the built-in MPI_TAG_UB attribute
67 */
68 static int Keyval_setup(void)
69 {
70   attr[MPI_COMM_WORLD-1][0].active        = 1;
71   attr[MPI_COMM_WORLD-1][0].attribute_val = &mpi_tag_ub;
72   attr[MPI_COMM_SELF-1][0].active         = 1;
73   attr[MPI_COMM_SELF-1][0].attribute_val  = &mpi_tag_ub;
74   return 0;
75 }
76 
77 int MPI_Keyval_create(MPI_Copy_function *copy_fn,MPI_Delete_function *delete_fn,int *keyval,void *extra_state)
78 {
79   if (num_attr >= MAX_ATTR) MPI_Abort(MPI_COMM_WORLD,1);
80 
81   attr_keyval[num_attr].extra_state = extra_state;
82   attr_keyval[num_attr].del         = delete_fn;
83   *keyval                           = num_attr++;
84   return 0;
85 }
86 
87 int MPI_Keyval_free(int *keyval)
88 {
89   attr_keyval[*keyval].extra_state = 0;
90   attr_keyval[*keyval].del         = 0;
91 
92   *keyval = 0;
93   return MPI_SUCCESS;
94 }
95 
96 int MPI_Attr_put(MPI_Comm comm,int keyval,void *attribute_val)
97 {
98   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
99   attr[comm-1][keyval].active        = 1;
100   attr[comm-1][keyval].attribute_val = attribute_val;
101   return MPI_SUCCESS;
102 }
103 
104 int MPI_Attr_delete(MPI_Comm comm,int keyval)
105 {
106   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
107   if (attr[comm-1][keyval].active && attr_keyval[keyval].del) {
108     void *save_attribute_val = attr[comm-1][keyval].attribute_val;
109     attr[comm-1][keyval].active        = 0;
110     attr[comm-1][keyval].attribute_val = 0;
111     (*(attr_keyval[keyval].del))(comm,keyval,save_attribute_val,attr_keyval[keyval].extra_state);
112   }
113   return MPI_SUCCESS;
114 }
115 
116 int MPI_Attr_get(MPI_Comm comm,int keyval,void *attribute_val,int *flag)
117 {
118   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
119   if (!keyval) Keyval_setup();
120   *flag                  = attr[comm-1][keyval].active;
121   *(void**)attribute_val = attr[comm-1][keyval].attribute_val;
122   return MPI_SUCCESS;
123 }
124 
125 int MPI_Comm_create(MPI_Comm comm,MPI_Group group,MPI_Comm *newcomm)
126 {
127   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
128   if (MaxComm > MAX_COMM) return MPI_FAILURE;
129   *newcomm =  MaxComm++;
130   return MPI_SUCCESS;
131 }
132 
133 int MPI_Comm_dup(MPI_Comm comm,MPI_Comm *out)
134 {
135   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
136   if (MaxComm > MAX_COMM) return MPI_FAILURE;
137   *out = MaxComm++;
138   return 0;
139 }
140 
141 int MPI_Comm_free(MPI_Comm *comm)
142 {
143   int i;
144 
145   if (*comm-1 < 0 || *comm-1 > MaxComm) return 1;
146   for (i=0; i<num_attr; i++) {
147     if (attr[*comm-1][i].active && attr_keyval[i].del) (*attr_keyval[i].del)(*comm,i,attr[*comm-1][i].attribute_val,attr_keyval[i].extra_state);
148     attr[*comm-1][i].active        = 0;
149     attr[*comm-1][i].attribute_val = 0;
150   }
151   *comm = 0;
152   return MPI_SUCCESS;
153 }
154 
155 int MPI_Comm_size(MPI_Comm comm, int *size)
156 {
157   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
158   *size=1;
159   return MPI_SUCCESS;
160 }
161 
162 int MPI_Comm_rank(MPI_Comm comm, int *rank)
163 {
164   if (comm-1 < 0 || comm-1 > MaxComm) return 1;
165   *rank=0;
166   return MPI_SUCCESS;
167 }
168 
169 int MPI_Abort(MPI_Comm comm,int errorcode)
170 {
171   abort();
172   return MPI_SUCCESS;
173 }
174 
175 /* --------------------------------------------------------------------------*/
176 
177 static int MPI_was_initialized = 0;
178 static int MPI_was_finalized   = 0;
179 
180 int MPI_Init(int *argc, char ***argv)
181 {
182   if (MPI_was_initialized) return 1;
183   if (MPI_was_finalized) return 1;
184   MPI_was_initialized = 1;
185   return 0;
186 }
187 
188 int MPI_Finalize(void)
189 {
190   MPI_Comm comm;
191   if (MPI_was_finalized) return 1;
192   if (!MPI_was_initialized) return 1;
193   comm = MPI_COMM_WORLD;
194   MPI_Comm_free(&comm);
195   comm = MPI_COMM_SELF;
196   MPI_Comm_free(&comm);
197   MPI_was_finalized = 1;
198   return 0;
199 }
200 
201 int MPI_Initialized(int *flag)
202 {
203   *flag = MPI_was_initialized;
204   return 0;
205 }
206 
207 int MPI_Finalized(int *flag)
208 {
209   *flag = MPI_was_finalized;
210   return 0;
211 }
212 
213 /* -------------------     Fortran versions of several routines ------------------ */
214 
215 #if defined(PETSC_HAVE_FORTRAN_CAPS)
216 #define mpiunisetcommonblock_ MPIUNISETCOMMONBLOCK
217 #define mpiunisetfortranbasepointers_  MPIUNISETFORTRANBASEPOINTERS
218 #define mpi_init_             MPI_INIT
219 #define mpi_finalize_         MPI_FINALIZE
220 #define mpi_comm_size_        MPI_COMM_SIZE
221 #define mpi_comm_rank_        MPI_COMM_RANK
222 #define mpi_abort_            MPI_ABORT
223 #define mpi_reduce_           MPI_REDUCE
224 #define mpi_allreduce_        MPI_ALLREDUCE
225 #define mpi_barrier_          MPI_BARRIER
226 #define mpi_bcast_            MPI_BCAST
227 #define mpi_gather_           MPI_GATHER
228 #define mpi_allgather_        MPI_ALLGATHER
229 #define mpi_comm_split_       MPI_COMM_SPLIT
230 #define mpi_scan_             MPI_SCAN
231 #define mpi_send_             MPI_SEND
232 #define mpi_recv_             MPI_RECV
233 #define mpi_reduce_scatter_   MPI_REDUCE_SCATTER
234 #define mpi_irecv_            MPI_IRECV
235 #define mpi_isend_            MPI_ISEND
236 #define mpi_sendrecv_         MPI_SENDRECV
237 #define mpi_test_             MPI_TEST
238 #define mpi_waitall_          MPI_WAITALL
239 #define mpi_waitany_          MPI_WAITANY
240 #define mpi_allgatherv_       MPI_ALLGATHERV
241 #define mpi_alltoallv_        MPI_ALLTOALLV
242 #define mpi_comm_create_      MPI_COMM_CREATE
243 #define mpi_address_          MPI_ADDRESS
244 #define mpi_pack_             MPI_PACK
245 #define mpi_unpack_           MPI_UNPACK
246 #define mpi_pack_size_        MPI_PACK_SIZE
247 #define mpi_type_struct_      MPI_TYPE_STRUCT
248 #define mpi_type_commit_      MPI_TYPE_COMMIT
249 #define mpi_wtime_            MPI_WTIME
250 #define mpi_cancel_           MPI_CANCEL
251 #define mpi_comm_dup_         MPI_COMM_DUP
252 #define mpi_comm_free_        MPI_COMM_FREE
253 #define mpi_get_count_        MPI_GET_COUNT
254 #define mpi_get_processor_name_ MPI_GET_PROCESSOR_NAME
255 #define mpi_initialized_      MPI_INITIALIZED
256 #define mpi_iprobe_           MPI_IPROBE
257 #define mpi_probe_            MPI_PROBE
258 #define mpi_request_free_     MPI_REQUEST_FREE
259 #define mpi_ssend_            MPI_SSEND
260 #define mpi_wait_             MPI_WAIT
261 #define mpi_comm_group_       MPI_COMM_GROUP
262 #define mpi_exscan_           MPI_EXSCAN
263 #elif !defined(PETSC_HAVE_FORTRAN_UNDERSCORE)
264 #define mpiunisetcommonblock_ mpiunisetcommonblock
265 #define mpiunisetfortranbasepointers_  mpiunisetfortranbasepointers
266 #define mpi_init_             mpi_init
267 #define mpi_finalize_         mpi_finalize
268 #define mpi_comm_size_        mpi_comm_size
269 #define mpi_comm_rank_        mpi_comm_rank
270 #define mpi_abort_            mpi_abort
271 #define mpi_reduce_           mpi_reduce
272 #define mpi_allreduce_        mpi_allreduce
273 #define mpi_barrier_          mpi_barrier
274 #define mpi_bcast_            mpi_bcast
275 #define mpi_gather_           mpi_gather
276 #define mpi_allgather_        mpi_allgather
277 #define mpi_comm_split_       mpi_comm_split
278 #define mpi_scan_             mpi_scan
279 #define mpi_send_             mpi_send
280 #define mpi_recv_             mpi_recv
281 #define mpi_reduce_scatter_   mpi_reduce_scatter
282 #define mpi_irecv_            mpi_irecv
283 #define mpi_isend_            mpi_isend
284 #define mpi_sendrecv_         mpi_sendrecv
285 #define mpi_test_             mpi_test
286 #define mpi_waitall_          mpi_waitall
287 #define mpi_waitany_          mpi_waitany
288 #define mpi_allgatherv_       mpi_allgatherv
289 #define mpi_alltoallv_        mpi_alltoallv
290 #define mpi_comm_create_      mpi_comm_create
291 #define mpi_address_          mpi_address
292 #define mpi_pack_             mpi_pack
293 #define mpi_unpack_           mpi_unpack
294 #define mpi_pack_size_        mpi_pack_size
295 #define mpi_type_struct_      mpi_type_struct
296 #define mpi_type_commit_      mpi_type_commit
297 #define mpi_wtime_            mpi_wtime
298 #define mpi_cancel_           mpi_cancel
299 #define mpi_comm_dup_         mpi_comm_dup
300 #define mpi_comm_free_        mpi_comm_free
301 #define mpi_get_count_        mpi_get_count
302 #define mpi_get_processor_name_ mpi_get_processor_name
303 #define mpi_initialized_      mpi_initialized
304 #define mpi_iprobe_           mpi_iprobe
305 #define mpi_probe_            mpi_probe
306 #define mpi_request_free_     mpi_request_free
307 #define mpi_ssend_            mpi_ssend
308 #define mpi_wait_             mpi_wait
309 #define mpi_comm_group_       mpi_comm_group
310 #define mpi_exscan_           mpi_exscan
311 #endif
312 
313 #if defined(PETSC_HAVE_FORTRAN_UNDERSCORE_UNDERSCORE)
314 #define mpi_init_             mpi_init__
315 #define mpi_finalize_         mpi_finalize__
316 #define mpi_comm_size_        mpi_comm_size__
317 #define mpi_comm_rank_        mpi_comm_rank__
318 #define mpi_abort_            mpi_abort__
319 #define mpi_reduce_           mpi_reduce__
320 #define mpi_allreduce_        mpi_allreduce__
321 #define mpi_barrier_          mpi_barrier__
322 #define mpi_bcast_            mpi_bcast__
323 #define mpi_gather_           mpi_gather__
324 #define mpi_allgather_        mpi_allgather__
325 #define mpi_comm_split_       mpi_comm_split__
326 #define mpi_scan_             mpi_scan__
327 #define mpi_send_             mpi_send__
328 #define mpi_recv_             mpi_recv__
329 #define mpi_reduce_scatter_   mpi_reduce_scatter__
330 #define mpi_irecv_            mpi_irecv__
331 #define mpi_isend_            mpi_isend__
332 #define mpi_sendrecv_         mpi_sendrecv__
333 #define mpi_test_             mpi_test__
334 #define mpi_waitall_          mpi_waitall__
335 #define mpi_waitany_          mpi_waitany__
336 #define mpi_allgatherv_       mpi_allgatherv__
337 #define mpi_alltoallv_        mpi_alltoallv__
338 #define mpi_comm_create_      mpi_comm_create__
339 #define mpi_address_          mpi_address__
340 #define mpi_pack_             mpi_pack__
341 #define mpi_unpack_           mpi_unpack__
342 #define mpi_pack_size_        mpi_pack_size__
343 #define mpi_type_struct_      mpi_type_struct__
344 #define mpi_type_commit_      mpi_type_commit__
345 #define mpi_wtime_            mpi_wtime__
346 #define mpi_cancel_           mpi_cancel__
347 #define mpi_comm_dup_         mpi_comm_dup__
348 #define mpi_comm_free_        mpi_comm_free__
349 #define mpi_get_count_        mpi_get_count__
350 #define mpi_get_processor_name_ mpi_get_processor_name__
351 #define mpi_initialized_      mpi_initialized__
352 #define mpi_iprobe_           mpi_iprobe__
353 #define mpi_probe_            mpi_probe__
354 #define mpi_request_free_     mpi_request_free__
355 #define mpi_ssend_            mpi_ssend__
356 #define mpi_wait_             mpi_wait__
357 #define mpi_comm_group_       mpi_comm_group__
358 #define mpi_exscan_           mpi_exscan__
359 #endif
360 
361 /* Do not build fortran interface if MPI namespace colision is to be avoided */
362 #if defined(MPIUNI_FORTRAN_BINDING)
363 
364 PETSC_EXTERN void PETSC_STDCALL mpiunisetcommonblock_(void);
365 
366 PETSC_EXTERN void PETSC_STDCALL mpiunisetfortranbasepointers_(void *f_mpi_in_place)
367 {
368   MPIUNIF_mpi_in_place   = f_mpi_in_place;
369 }
370 
371 PETSC_EXTERN void PETSC_STDCALL   mpi_init_(int *ierr)
372 {
373   mpiunisetcommonblock_();
374   *ierr = MPI_Init((int*)0, (char***)0);
375 }
376 
377 PETSC_EXTERN void PETSC_STDCALL   mpi_finalize_(int *ierr)
378 {
379   *ierr = MPI_Finalize();
380 }
381 
382 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_size_(MPI_Comm *comm,int *size,int *ierr)
383 {
384   *size = 1;
385   *ierr = 0;
386 }
387 
388 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_rank_(MPI_Comm *comm,int *rank,int *ierr)
389 {
390   *rank = 0;
391   *ierr = MPI_SUCCESS;
392 }
393 
394 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_split_(MPI_Comm *comm,int *color,int *key, MPI_Comm *newcomm, int *ierr)
395 {
396   *newcomm = *comm;
397   *ierr    = MPI_SUCCESS;
398 }
399 
400 PETSC_EXTERN void PETSC_STDCALL  mpi_abort_(MPI_Comm *comm,int *errorcode,int *ierr)
401 {
402   abort();
403   *ierr = MPI_SUCCESS;
404 }
405 
406 PETSC_EXTERN void PETSC_STDCALL  mpi_reduce_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *root,int *comm,int *ierr)
407 {
408   *ierr = MPI_Reduce(sendbuf,recvbuf,*count,*datatype,*op,*root,*comm);
409 }
410 
411 PETSC_EXTERN void PETSC_STDCALL  mpi_allreduce_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *comm,int *ierr)
412 {
413   *ierr = MPI_Allreduce(sendbuf,recvbuf,*count,*datatype,*op,*comm);
414 }
415 
416 PETSC_EXTERN void PETSC_STDCALL  mpi_barrier_(MPI_Comm *comm,int *ierr)
417 {
418   *ierr = MPI_SUCCESS;
419 }
420 
421 PETSC_EXTERN void PETSC_STDCALL  mpi_bcast_(void *buf,int *count,int *datatype,int *root,int *comm,int *ierr)
422 {
423   *ierr = MPI_SUCCESS;
424 }
425 
426 PETSC_EXTERN void PETSC_STDCALL  mpi_gather_(void *sendbuf,int *scount,int *sdatatype, void *recvbuf, int *rcount, int *rdatatype, int *root,int *comm,int *ierr)
427 {
428   *ierr = MPI_Gather(sendbuf,*scount,*sdatatype,recvbuf,rcount,rdatatype,*root,*comm);
429 }
430 
431 PETSC_EXTERN void PETSC_STDCALL  mpi_allgather_(void *sendbuf,int *scount,int *sdatatype, void *recvbuf, int *rcount, int *rdatatype,int *comm,int *ierr)
432 {
433   *ierr = MPI_Allgather(sendbuf,*scount,*sdatatype,recvbuf,rcount,rdatatype,*comm);
434 }
435 
436 PETSC_EXTERN void PETSC_STDCALL  mpi_scan_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *comm,int *ierr)
437 {
438   *ierr = MPIUNI_Memcpy(recvbuf,sendbuf,(*count)*MPIUNI_DATASIZE[*datatype]);
439 }
440 
441 PETSC_EXTERN void PETSC_STDCALL  mpi_send_(void *buf,int *count,int *datatype,int *dest,int *tag,int *comm,int *ierr)
442 {
443   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
444 }
445 
446 PETSC_EXTERN void PETSC_STDCALL  mpi_recv_(void *buf,int *count,int *datatype,int *source,int *tag,int *comm,int status,int *ierr)
447 {
448   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
449 }
450 
451 PETSC_EXTERN void PETSC_STDCALL  mpi_reduce_scatter_(void *sendbuf,void *recvbuf,int *recvcounts,int *datatype,int *op,int *comm,int *ierr)
452 {
453   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
454 }
455 
456 PETSC_EXTERN void PETSC_STDCALL  mpi_irecv_(void *buf,int *count, int *datatype, int *source, int *tag, int *comm, int *request, int *ierr)
457 {
458   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
459 }
460 
461 PETSC_EXTERN void PETSC_STDCALL  mpi_isend_(void *buf,int *count,int *datatype,int *dest,int *tag,int *comm,int *request, int *ierr)
462 {
463   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
464 }
465 
466 PETSC_EXTERN void PETSC_STDCALL  mpi_sendrecv_(void *sendbuf,int *sendcount,int *sendtype,int *dest,int *sendtag,void *recvbuf,int *recvcount,int *recvtype,int *source,int *recvtag,int *comm,int *status,int *ierr)
467 {
468   *ierr = MPIUNI_Memcpy(recvbuf,sendbuf,(*sendcount)*MPIUNI_DATASIZE[*sendtype]);
469 }
470 
471 PETSC_EXTERN void PETSC_STDCALL  mpi_test_(int *request,int *flag,int *status,int *ierr)
472 {
473   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
474 }
475 
476 PETSC_EXTERN void PETSC_STDCALL  mpi_waitall_(int *count,int *array_of_requests,int *array_of_statuses,int *ierr)
477 {
478   *ierr = MPI_SUCCESS;
479 }
480 
481 PETSC_EXTERN void PETSC_STDCALL  mpi_waitany_(int *count,int *array_of_requests,int * index, int *status,int *ierr)
482 {
483   *ierr = MPI_SUCCESS;
484 }
485 
486 PETSC_EXTERN void PETSC_STDCALL  mpi_allgatherv_(void *sendbuf,int *sendcount,int *sendtype,void *recvbuf,int *recvcounts,int *displs,int *recvtype,int *comm,int *ierr)
487 {
488   *ierr = MPI_Allgatherv(sendbuf,*sendcount,*sendtype,recvbuf,recvcounts,displs,*recvtype,*comm);
489 }
490 
491 PETSC_EXTERN void PETSC_STDCALL  mpi_alltoallv_(void *sendbuf,int *sendcounts,int *sdispls,int *sendtype,void *recvbuf,int *recvcounts,int *rdispls,int *recvtype,int *comm,int *ierr)
492 {
493   *ierr = MPI_Alltoallv(sendbuf,sendcounts,sdispls,*sendtype,recvbuf,recvcounts,rdispls,*recvtype,*comm);
494 }
495 
496 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_create_(int *comm,int *group,int *newcomm,int *ierr)
497 {
498   *newcomm =  *comm;
499   *ierr    = MPI_SUCCESS;
500 }
501 
502 PETSC_EXTERN void PETSC_STDCALL  mpi_address_(void *location,MPIUNI_INTPTR *address,int *ierr)
503 {
504   *address =  (MPIUNI_INTPTR) location;
505   *ierr    = MPI_SUCCESS;
506 }
507 
508 PETSC_EXTERN void PETSC_STDCALL  mpi_pack_(void *inbuf,int *incount,int *datatype,void *outbuf,int *outsize,int *position,int *comm,int *ierr)
509 {
510   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
511 }
512 
513 PETSC_EXTERN void PETSC_STDCALL  mpi_unpack_(void *inbuf,int *insize,int *position,void *outbuf,int *outcount,int *datatype,int *comm,int *ierr)
514 {
515   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
516 }
517 
518 PETSC_EXTERN void PETSC_STDCALL  mpi_pack_size_(int *incount,int *datatype,int *comm,int *size,int *ierr)
519 {
520   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
521 }
522 
523 PETSC_EXTERN void PETSC_STDCALL  mpi_type_struct_(int *count,int *array_of_blocklengths,int * array_of_displaments,int *array_of_types,int *newtype,int *ierr)
524 {
525   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
526 }
527 
528 PETSC_EXTERN void PETSC_STDCALL  mpi_type_commit_(int *datatype,int *ierr)
529 {
530   *ierr = MPI_SUCCESS;
531 }
532 
533 double PETSC_STDCALL mpi_wtime_(void)
534 {
535   return 0.0;
536 }
537 
538 PETSC_EXTERN void PETSC_STDCALL  mpi_cancel_(int *request,int *ierr)
539 {
540   *ierr = MPI_SUCCESS;
541 }
542 
543 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_dup_(int *comm,int *out,int *ierr)
544 {
545   *out  = *comm;
546   *ierr = MPI_SUCCESS;
547 }
548 
549 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_free_(int *comm,int *ierr)
550 {
551   *ierr = MPI_SUCCESS;
552 }
553 
554 PETSC_EXTERN void PETSC_STDCALL  mpi_get_count_(int *status,int *datatype,int *count,int *ierr)
555 {
556   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
557 }
558 
559 /* duplicate from fortranimpl.h */
560 #if defined(PETSC_HAVE_FORTRAN_MIXED_STR_ARG)
561 #define PETSC_MIXED_LEN(len) ,int len
562 #define PETSC_END_LEN(len)
563 #else
564 #define PETSC_MIXED_LEN(len)
565 #define PETSC_END_LEN(len)   ,int len
566 #endif
567 
568 PETSC_EXTERN void PETSC_STDCALL  mpi_get_processor_name_(char *name PETSC_MIXED_LEN(len),int *result_len,int *ierr PETSC_END_LEN(len))
569 {
570   MPIUNI_Memcpy(name,"localhost",9*sizeof(char));
571   *result_len = 9;
572   *ierr       = MPI_SUCCESS;
573 }
574 
575 PETSC_EXTERN void PETSC_STDCALL  mpi_initialized_(int *flag,int *ierr)
576 {
577   *flag = MPI_was_initialized;
578   *ierr = MPI_SUCCESS;
579 }
580 
581 PETSC_EXTERN void PETSC_STDCALL  mpi_iprobe_(int *source,int *tag,int *comm,int *glag,int *status,int *ierr)
582 {
583   *ierr = MPI_SUCCESS;
584 }
585 
586 PETSC_EXTERN void PETSC_STDCALL  mpi_probe_(int *source,int *tag,int *comm,int *flag,int *status,int *ierr)
587 {
588   *ierr = MPI_SUCCESS;
589 }
590 
591 PETSC_EXTERN void PETSC_STDCALL  mpi_request_free_(int *request,int *ierr)
592 {
593   *ierr = MPI_SUCCESS;
594 }
595 
596 PETSC_EXTERN void PETSC_STDCALL  mpi_ssend_(void *buf,int *count,int *datatype,int *dest,int *tag,int *comm,int *ierr)
597 {
598   *ierr = MPI_Abort(MPI_COMM_WORLD,0);
599 }
600 
601 PETSC_EXTERN void PETSC_STDCALL  mpi_wait_(int *request,int *status,int *ierr)
602 {
603   *ierr = MPI_SUCCESS;
604 }
605 
606 PETSC_EXTERN void PETSC_STDCALL  mpi_comm_group_(int *comm,int *group,int *ierr)
607 {
608   *ierr = MPI_SUCCESS;
609 }
610 
611 PETSC_EXTERN void PETSC_STDCALL  mpi_exscan_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *comm,int *ierr)
612 {
613   *ierr = MPI_SUCCESS;
614 }
615 
616 #endif /* MPIUNI_AVOID_MPI_NAMESPACE */
617 
618 #if defined(__cplusplus)
619 }
620 #endif
621