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