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 *ierr = MPI_Reduce(sendbuf,recvbuf,*count,*datatype,*op,*root,*comm); 398 } 399 400 PETSC_EXTERN void PETSC_STDCALL mpi_allreduce_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *comm,int *ierr) 401 { 402 *ierr = MPI_Allreduce(sendbuf,recvbuf,*count,*datatype,*op,*comm); 403 } 404 405 PETSC_EXTERN void PETSC_STDCALL mpi_barrier_(MPI_Comm *comm,int *ierr) 406 { 407 *ierr = MPI_SUCCESS; 408 } 409 410 PETSC_EXTERN void PETSC_STDCALL mpi_bcast_(void *buf,int *count,int *datatype,int *root,int *comm,int *ierr) 411 { 412 *ierr = MPI_SUCCESS; 413 } 414 415 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) 416 { 417 *ierr = MPI_Gather(sendbuf,*scount,*sdatatype,recvbuf,rcount,rdatatype,*root,*comm); 418 } 419 420 PETSC_EXTERN void PETSC_STDCALL mpi_allgather_(void *sendbuf,int *scount,int *sdatatype, void *recvbuf, int *rcount, int *rdatatype,int *comm,int *ierr) 421 { 422 *ierr = MPI_Allgather(sendbuf,*scount,*sdatatype,recvbuf,rcount,rdatatype,*comm); 423 } 424 425 PETSC_EXTERN void PETSC_STDCALL mpi_scan_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *comm,int *ierr) 426 { 427 *ierr = MPIUNI_Memcpy(recvbuf,sendbuf,(*count)*MPIUNI_DATASIZE[*datatype]); 428 } 429 430 PETSC_EXTERN void PETSC_STDCALL mpi_send_(void *buf,int *count,int *datatype,int *dest,int *tag,int *comm,int *ierr) 431 { 432 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 433 } 434 435 PETSC_EXTERN void PETSC_STDCALL mpi_recv_(void *buf,int *count,int *datatype,int *source,int *tag,int *comm,int status,int *ierr) 436 { 437 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 438 } 439 440 PETSC_EXTERN void PETSC_STDCALL mpi_reduce_scatter_(void *sendbuf,void *recvbuf,int *recvcounts,int *datatype,int *op,int *comm,int *ierr) 441 { 442 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 443 } 444 445 PETSC_EXTERN void PETSC_STDCALL mpi_irecv_(void *buf,int *count, int *datatype, int *source, int *tag, int *comm, int *request, int *ierr) 446 { 447 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 448 } 449 450 PETSC_EXTERN void PETSC_STDCALL mpi_isend_(void *buf,int *count,int *datatype,int *dest,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_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) 456 { 457 *ierr = MPIUNI_Memcpy(recvbuf,sendbuf,(*sendcount)*MPIUNI_DATASIZE[*sendtype]); 458 } 459 460 PETSC_EXTERN void PETSC_STDCALL mpi_test_(int *request,int *flag,int *status,int *ierr) 461 { 462 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 463 } 464 465 PETSC_EXTERN void PETSC_STDCALL mpi_waitall_(int *count,int *array_of_requests,int *array_of_statuses,int *ierr) 466 { 467 *ierr = MPI_SUCCESS; 468 } 469 470 PETSC_EXTERN void PETSC_STDCALL mpi_waitany_(int *count,int *array_of_requests,int * index, int *status,int *ierr) 471 { 472 *ierr = MPI_SUCCESS; 473 } 474 475 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) 476 { 477 *ierr = MPI_Allgatherv(sendbuf,*sendcount,*sendtype,recvbuf,recvcounts,displs,*recvtype,*comm); 478 } 479 480 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) 481 { 482 *ierr = MPI_Alltoallv(sendbuf,sendcounts,sdispls,*sendtype,recvbuf,recvcounts,rdispls,*recvtype,*comm); 483 } 484 485 PETSC_EXTERN void PETSC_STDCALL mpi_comm_create_(int *comm,int *group,int *newcomm,int *ierr) 486 { 487 *newcomm = *comm; 488 *ierr = MPI_SUCCESS; 489 } 490 491 PETSC_EXTERN void PETSC_STDCALL mpi_address_(void *location,MPIUNI_INTPTR *address,int *ierr) 492 { 493 *address = (MPIUNI_INTPTR) location; 494 *ierr = MPI_SUCCESS; 495 } 496 497 PETSC_EXTERN void PETSC_STDCALL mpi_pack_(void *inbuf,int *incount,int *datatype,void *outbuf,int *outsize,int *position,int *comm,int *ierr) 498 { 499 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 500 } 501 502 PETSC_EXTERN void PETSC_STDCALL mpi_unpack_(void *inbuf,int *insize,int *position,void *outbuf,int *outcount,int *datatype,int *comm,int *ierr) 503 { 504 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 505 } 506 507 PETSC_EXTERN void PETSC_STDCALL mpi_pack_size_(int *incount,int *datatype,int *comm,int *size,int *ierr) 508 { 509 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 510 } 511 512 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) 513 { 514 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 515 } 516 517 PETSC_EXTERN void PETSC_STDCALL mpi_type_commit_(int *datatype,int *ierr) 518 { 519 *ierr = MPI_SUCCESS; 520 } 521 522 double PETSC_STDCALL mpi_wtime_(void) 523 { 524 return 0.0; 525 } 526 527 PETSC_EXTERN void PETSC_STDCALL mpi_cancel_(int *request,int *ierr) 528 { 529 *ierr = MPI_SUCCESS; 530 } 531 532 PETSC_EXTERN void PETSC_STDCALL mpi_comm_dup_(int *comm,int *out,int *ierr) 533 { 534 *out = *comm; 535 *ierr = MPI_SUCCESS; 536 } 537 538 PETSC_EXTERN void PETSC_STDCALL mpi_comm_free_(int *comm,int *ierr) 539 { 540 *ierr = MPI_SUCCESS; 541 } 542 543 PETSC_EXTERN void PETSC_STDCALL mpi_get_count_(int *status,int *datatype,int *count,int *ierr) 544 { 545 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 546 } 547 548 /* duplicate from fortranimpl.h */ 549 #if defined(PETSC_HAVE_FORTRAN_MIXED_STR_ARG) 550 #define PETSC_MIXED_LEN(len) ,int len 551 #define PETSC_END_LEN(len) 552 #else 553 #define PETSC_MIXED_LEN(len) 554 #define PETSC_END_LEN(len) ,int len 555 #endif 556 557 PETSC_EXTERN void PETSC_STDCALL mpi_get_processor_name_(char *name PETSC_MIXED_LEN(len),int *result_len,int *ierr PETSC_END_LEN(len)) 558 { 559 MPIUNI_Memcpy(name,"localhost",9*sizeof(char)); 560 *result_len = 9; 561 *ierr = MPI_SUCCESS; 562 } 563 564 PETSC_EXTERN void PETSC_STDCALL mpi_initialized_(int *flag,int *ierr) 565 { 566 *flag = MPI_was_initialized; 567 *ierr = MPI_SUCCESS; 568 } 569 570 PETSC_EXTERN void PETSC_STDCALL mpi_iprobe_(int *source,int *tag,int *comm,int *glag,int *status,int *ierr) 571 { 572 *ierr = MPI_SUCCESS; 573 } 574 575 PETSC_EXTERN void PETSC_STDCALL mpi_probe_(int *source,int *tag,int *comm,int *flag,int *status,int *ierr) 576 { 577 *ierr = MPI_SUCCESS; 578 } 579 580 PETSC_EXTERN void PETSC_STDCALL mpi_request_free_(int *request,int *ierr) 581 { 582 *ierr = MPI_SUCCESS; 583 } 584 585 PETSC_EXTERN void PETSC_STDCALL mpi_ssend_(void *buf,int *count,int *datatype,int *dest,int *tag,int *comm,int *ierr) 586 { 587 *ierr = MPI_Abort(MPI_COMM_WORLD,0); 588 } 589 590 PETSC_EXTERN void PETSC_STDCALL mpi_wait_(int *request,int *status,int *ierr) 591 { 592 *ierr = MPI_SUCCESS; 593 } 594 595 PETSC_EXTERN void PETSC_STDCALL mpi_comm_group_(int *comm,int *group,int *ierr) 596 { 597 *ierr = MPI_SUCCESS; 598 } 599 600 PETSC_EXTERN void PETSC_STDCALL mpi_exscan_(void *sendbuf,void *recvbuf,int *count,int *datatype,int *op,int *comm,int *ierr) 601 { 602 *ierr = MPI_SUCCESS; 603 } 604 605 #endif /* MPIUNI_AVOID_MPI_NAMESPACE */ 606 607 #if defined(__cplusplus) 608 } 609 #endif 610