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