src/smpi/smpi_f77.cpp

   1 /* Copyright (c) 2010-2015. The SimGrid Team.
   2  * All rights reserved.                                                     */
   3
   4 /* This program is free software; you can redistribute it and/or modify it
   5  * under the terms of the license (GNU LGPL) which comes with this package. */
   6
   7 #include <limits.h>
   8 #include <stdio.h>
   9 #include "smpi_mpi_dt_private.h"
  10 #include "private.h"
  11 #include "xbt.h"
  12
  13 static xbt_dict_t comm_lookup = NULL;
  14 static xbt_dict_t group_lookup = NULL;
  15 static xbt_dict_t request_lookup = NULL;
  16 static xbt_dict_t datatype_lookup = NULL;
  17 static xbt_dict_t op_lookup = NULL;
  18 static xbt_dict_t win_lookup = NULL;
  19 static xbt_dict_t info_lookup = NULL;
  20
  21 static int running_processes = 0;
  22
  23 #if defined(__alpha__) || defined(__sparc64__) || defined(__x86_64__) || defined(__ia64__)
  24 typedef int integer;
  25 typedef unsigned int uinteger;
  26 #else
  27 typedef long int integer;
  28 typedef unsigned long int uinteger;
  29 #endif
  30
  31 /* Bindings for MPI special values */
  32   struct s_smpi_common {
  33     integer _MPI_IN_PLACE;
  34     integer _MPI_BOTTOM;
  35     integer _MPI_STATUS_IGNORE;
  36     integer _MPI_STATUSES_IGNORE;
  37   } smpi_;
  38
  39 /* Convert between Fortran and C */
  40 #define FORT_ADDR(addr, val)                                         \
  41   (((void *)(addr) == (void*) &(smpi_._ ## val))                  \
  42    ? (val) : (void *)(addr))
  43 #define FORT_BOTTOM(addr)          FORT_ADDR(addr, MPI_BOTTOM)
  44 #define FORT_IN_PLACE(addr)        FORT_ADDR(addr, MPI_IN_PLACE)
  45 #define FORT_STATUS_IGNORE(addr)   static_cast<MPI_Status*>(FORT_ADDR(addr, MPI_STATUS_IGNORE))
  46 #define FORT_STATUSES_IGNORE(addr) static_cast<MPI_Status*>(FORT_ADDR(addr, MPI_STATUSES_IGNORE))
  47
  48 #define KEY_SIZE (sizeof(int) * 2 + 1)
  49
  50 static char* get_key(char* key, int id) {
  51   snprintf(key, KEY_SIZE, "%x",id);
  52   return key;
  53 }
  54
  55 static char* get_key_id(char* key, int id) {
  56   snprintf(key, KEY_SIZE, "%x_%d",id, smpi_process_index());
  57   return key;
  58 }
  59
  60 static void smpi_init_fortran_types(){
  61    if(comm_lookup == NULL){
  62      comm_lookup = xbt_dict_new_homogeneous(NULL);
  63      smpi_comm_c2f(MPI_COMM_WORLD);
  64      group_lookup = xbt_dict_new_homogeneous(NULL);
  65      request_lookup = xbt_dict_new_homogeneous(NULL);
  66      datatype_lookup = xbt_dict_new_homogeneous(NULL);
  67      win_lookup = xbt_dict_new_homogeneous(NULL);
  68      info_lookup = xbt_dict_new_homogeneous(NULL);
  69      smpi_type_c2f(MPI_BYTE);//MPI_BYTE
  70      smpi_type_c2f(MPI_CHAR);//MPI_CHARACTER
  71 #if defined(__alpha__) || defined(__sparc64__) || defined(__x86_64__) || defined(__ia64__)
  72      smpi_type_c2f(MPI_INT);//MPI_LOGICAL
  73      smpi_type_c2f(MPI_INT);//MPI_INTEGER
  74 #else
  75      smpi_type_c2f(MPI_LONG);//MPI_LOGICAL
  76      smpi_type_c2f(MPI_LONG);//MPI_INTEGER
  77 #endif
  78      smpi_type_c2f(MPI_INT8_T);//MPI_INTEGER1
  79      smpi_type_c2f(MPI_INT16_T);//MPI_INTEGER2
  80      smpi_type_c2f(MPI_INT32_T);//MPI_INTEGER4
  81      smpi_type_c2f(MPI_INT64_T);//MPI_INTEGER8
  82      smpi_type_c2f(MPI_FLOAT);//MPI_REAL
  83      smpi_type_c2f(MPI_FLOAT);//MPI_REAL4
  84      smpi_type_c2f(MPI_DOUBLE);//MPI_REAL8
  85      smpi_type_c2f(MPI_DOUBLE);//MPI_DOUBLE_PRECISION
  86      smpi_type_c2f(MPI_C_FLOAT_COMPLEX);//MPI_COMPLEX
  87      smpi_type_c2f(MPI_C_DOUBLE_COMPLEX);//MPI_DOUBLE_COMPLEX
  88 #if defined(__alpha__) || defined(__sparc64__) || defined(__x86_64__) || defined(__ia64__)
  89      smpi_type_c2f(MPI_2INT);//MPI_2INTEGER
  90 #else
  91      smpi_type_c2f(MPI_2LONG);//MPI_2INTEGER
  92 #endif
  93      smpi_type_c2f(MPI_UINT8_T);//MPI_LOGICAL1
  94      smpi_type_c2f(MPI_UINT16_T);//MPI_LOGICAL2
  95      smpi_type_c2f(MPI_UINT32_T);//MPI_LOGICAL4
  96      smpi_type_c2f(MPI_UINT64_T);//MPI_LOGICAL8
  97      smpi_type_c2f(MPI_2FLOAT);//MPI_2REAL
  98      smpi_type_c2f(MPI_2DOUBLE);//MPI_2DOUBLE_PRECISION
  99      smpi_type_c2f(MPI_PTR);//MPI_AINT
 100      smpi_type_c2f(MPI_UINT64_T);//MPI_OFFSET
 101      smpi_type_c2f(MPI_UINT64_T);//MPI_COUNT
 102      smpi_type_c2f(MPI_DATATYPE_NULL);//MPI_REAL16
 103      smpi_type_c2f(MPI_DATATYPE_NULL);//MPI_COMPLEX8
 104      smpi_type_c2f(MPI_DATATYPE_NULL);//MPI_COMPLEX16
 105      smpi_type_c2f(MPI_DATATYPE_NULL);//MPI_COMPLEX32
 106      smpi_type_c2f(MPI_DATATYPE_NULL);//MPI_PACKED
 107      op_lookup = xbt_dict_new_homogeneous(NULL);
 108      smpi_op_c2f(MPI_MAX);
 109      smpi_op_c2f(MPI_MIN);
 110      smpi_op_c2f(MPI_MAXLOC);
 111      smpi_op_c2f(MPI_MINLOC);
 112      smpi_op_c2f(MPI_SUM);
 113      smpi_op_c2f(MPI_PROD);
 114      smpi_op_c2f(MPI_LAND);
 115      smpi_op_c2f(MPI_LOR);
 116      smpi_op_c2f(MPI_LXOR);
 117      smpi_op_c2f(MPI_BAND);
 118      smpi_op_c2f(MPI_BOR);
 119      smpi_op_c2f(MPI_BXOR);
 120    }
 121 }
 122
 123 int smpi_comm_c2f(MPI_Comm comm) {
 124   static int comm_id = 0;
 125   char key[KEY_SIZE];
 126   xbt_dict_set(comm_lookup, comm==MPI_COMM_WORLD? get_key(key, comm_id) : get_key_id(key, comm_id), comm, NULL);
 127   comm_id++;
 128   return comm_id-1;
 129 }
 130
 131 static void free_comm(int comm) {
 132   char key[KEY_SIZE];
 133   xbt_dict_remove(comm_lookup, comm==0? get_key(key, comm) : get_key_id(key, comm));
 134 }
 135
 136 MPI_Comm smpi_comm_f2c(int comm) {
 137   smpi_init_fortran_types();
 138   if(comm == -2) {
 139     return MPI_COMM_SELF;
 140   } else if(comm==0){
 141     return MPI_COMM_WORLD;
 142   } else if(comm_lookup != NULL && comm >= 0) {
 143       char key[KEY_SIZE];
 144       MPI_Comm tmp =  static_cast<MPI_Comm>(xbt_dict_get_or_null(comm_lookup,get_key_id(key, comm)));
 145       return tmp != NULL ? tmp : MPI_COMM_NULL ;
 146   } else {
 147     return MPI_COMM_NULL;
 148   }
 149 }
 150
 151 int smpi_group_c2f(MPI_Group group) {
 152   static int group_id = 0;
 153   char key[KEY_SIZE];
 154   xbt_dict_set(group_lookup, get_key(key, group_id), group, NULL);
 155   group_id++;
 156   return group_id-1;
 157 }
 158
 159 MPI_Group smpi_group_f2c(int group) {
 160   smpi_init_fortran_types();
 161   if(group == -2) {
 162     return MPI_GROUP_EMPTY;
 163   } else if(group_lookup != NULL && group >= 0) {
 164     char key[KEY_SIZE];
 165     return static_cast<MPI_Group>(xbt_dict_get_or_null(group_lookup, get_key(key, group)));
 166   } else {
 167     return MPI_GROUP_NULL;
 168   }
 169 }
 170
 171 static void free_group(int group) {
 172   char key[KEY_SIZE];
 173   xbt_dict_remove(group_lookup, get_key(key, group));
 174 }
 175
 176 int smpi_request_c2f(MPI_Request req) {
 177   static int request_id = 0;
 178   char key[KEY_SIZE];
 179   xbt_dict_set(request_lookup, get_key_id(key, request_id), req, NULL);
 180   request_id++;
 181   return request_id-1;
 182 }
 183
 184 MPI_Request smpi_request_f2c(int req) {
 185   smpi_init_fortran_types();
 186   char key[KEY_SIZE];
 187   if(req==MPI_FORTRAN_REQUEST_NULL)
 188     return MPI_REQUEST_NULL;
 189   return static_cast<MPI_Request>(xbt_dict_get(request_lookup, get_key_id(key, req)));
 190 }
 191
 192 static void free_request(int request) {
 193   char key[KEY_SIZE];
 194   if(request!=MPI_FORTRAN_REQUEST_NULL)
 195   xbt_dict_remove(request_lookup, get_key_id(key, request));
 196 }
 197
 198 int smpi_type_c2f(MPI_Datatype datatype) {
 199   static int datatype_id = 0;
 200   char key[KEY_SIZE];
 201   xbt_dict_set(datatype_lookup, get_key(key, datatype_id), datatype, NULL);
 202   datatype_id++;
 203   return datatype_id-1;
 204 }
 205
 206 MPI_Datatype smpi_type_f2c(int datatype) {
 207   smpi_init_fortran_types();
 208   char key[KEY_SIZE];
 209   return datatype >= 0 ? static_cast<MPI_Datatype>(xbt_dict_get_or_null(datatype_lookup, get_key(key, datatype))): MPI_DATATYPE_NULL;
 210 }
 211
 212 static void free_datatype(int datatype) {
 213   char key[KEY_SIZE];
 214   xbt_dict_remove(datatype_lookup, get_key(key, datatype));
 215 }
 216
 217 int smpi_op_c2f(MPI_Op op) {
 218   static int op_id = 0;
 219   char key[KEY_SIZE];
 220   xbt_dict_set(op_lookup, get_key(key, op_id), op, NULL);
 221   op_id++;
 222   return op_id-1;
 223 }
 224
 225 MPI_Op smpi_op_f2c(int op) {
 226   smpi_init_fortran_types();
 227   char key[KEY_SIZE];
 228    return op >= 0 ? static_cast<MPI_Op>(xbt_dict_get_or_null(op_lookup,  get_key(key, op))): MPI_OP_NULL;
 229 }
 230
 231 static void free_op(int op) {
 232   char key[KEY_SIZE];
 233   xbt_dict_remove(op_lookup, get_key(key, op));
 234 }
 235
 236 int smpi_win_c2f(MPI_Win win) {
 237   static int win_id = 0;
 238   char key[KEY_SIZE];
 239   xbt_dict_set(win_lookup, get_key(key, win_id), win, NULL);
 240   win_id++;
 241   return win_id-1;
 242 }
 243
 244 MPI_Win smpi_win_f2c(int win) {
 245   smpi_init_fortran_types();
 246   char key[KEY_SIZE];
 247    return win >= 0 ? static_cast<MPI_Win>(xbt_dict_get_or_null(win_lookup,  get_key(key, win))) : MPI_WIN_NULL;
 248 }
 249
 250 static void free_win(int win) {
 251   char key[KEY_SIZE];
 252   xbt_dict_remove(win_lookup, get_key(key, win));
 253 }
 254
 255 int smpi_info_c2f(MPI_Info info) {
 256   static int info_id = 0;
 257   char key[KEY_SIZE];
 258   xbt_dict_set(info_lookup, get_key(key, info_id), info, NULL);
 259   info_id++;
 260   return info_id-1;
 261 }
 262
 263 MPI_Info smpi_info_f2c(int info) {
 264   smpi_init_fortran_types();
 265   char key[KEY_SIZE];
 266    return info >= 0 ? static_cast<MPI_Info>(xbt_dict_get_or_null(info_lookup,  get_key(key, info))) : MPI_INFO_NULL;
 267 }
 268
 269 static void free_info(int info) {
 270   char key[KEY_SIZE];
 271   xbt_dict_remove(info_lookup, get_key(key, info));
 272 }
 273
 274 void mpi_init_(int* ierr) {
 275     smpi_init_fortran_types();
 276    *ierr = MPI_Init(NULL, NULL);
 277    running_processes++;
 278 }
 279
 280 void mpi_finalize_(int* ierr) {
 281    *ierr = MPI_Finalize();
 282    running_processes--;
 283    if(running_processes==0){
 284      xbt_dict_free(&op_lookup);
 285      xbt_dict_free(&datatype_lookup);
 286      xbt_dict_free(&request_lookup);
 287      xbt_dict_free(&group_lookup);
 288      xbt_dict_free(&comm_lookup);
 289      xbt_dict_free(&win_lookup);
 290      xbt_dict_free(&info_lookup);
 291    }
 292 }
 293
 294 void mpi_abort_(int* comm, int* errorcode, int* ierr) {
 295   *ierr = MPI_Abort(smpi_comm_f2c(*comm), *errorcode);
 296 }
 297
 298 void mpi_comm_rank_(int* comm, int* rank, int* ierr) {
 299    *ierr = MPI_Comm_rank(smpi_comm_f2c(*comm), rank);
 300 }
 301
 302 void mpi_comm_size_(int* comm, int* size, int* ierr) {
 303    *ierr = MPI_Comm_size(smpi_comm_f2c(*comm), size);
 304 }
 305
 306 double mpi_wtime_(void) {
 307    return MPI_Wtime();
 308 }
 309
 310 double mpi_wtick_(void) {
 311   return MPI_Wtick();
 312 }
 313
 314 void mpi_comm_dup_(int* comm, int* newcomm, int* ierr) {
 315   MPI_Comm tmp;
 316
 317   *ierr = MPI_Comm_dup(smpi_comm_f2c(*comm), &tmp);
 318   if(*ierr == MPI_SUCCESS) {
 319     *newcomm = smpi_comm_c2f(tmp);
 320   }
 321 }
 322
 323 void mpi_comm_create_(int* comm, int* group, int* newcomm, int* ierr) {
 324   MPI_Comm tmp;
 325
 326   *ierr = MPI_Comm_create(smpi_comm_f2c(*comm),smpi_group_f2c(*group), &tmp);
 327   if(*ierr == MPI_SUCCESS) {
 328     *newcomm = smpi_comm_c2f(tmp);
 329   }
 330 }
 331
 332 void mpi_comm_free_(int* comm, int* ierr) {
 333   MPI_Comm tmp = smpi_comm_f2c(*comm);
 334
 335   *ierr = MPI_Comm_free(&tmp);
 336
 337   if(*ierr == MPI_SUCCESS) {
 338     free_comm(*comm);
 339   }
 340 }
 341
 342 void mpi_comm_split_(int* comm, int* color, int* key, int* comm_out, int* ierr) {
 343   MPI_Comm tmp;
 344
 345   *ierr = MPI_Comm_split(smpi_comm_f2c(*comm), *color, *key, &tmp);
 346   if(*ierr == MPI_SUCCESS) {
 347     *comm_out = smpi_comm_c2f(tmp);
 348   }
 349 }
 350
 351 void mpi_group_incl_(int* group, int* n, int* ranks, int* group_out, int* ierr) {
 352   MPI_Group tmp;
 353
 354   *ierr = MPI_Group_incl(smpi_group_f2c(*group), *n, ranks, &tmp);
 355   if(*ierr == MPI_SUCCESS) {
 356     *group_out = smpi_group_c2f(tmp);
 357   }
 358 }
 359
 360 void mpi_comm_group_(int* comm, int* group_out,  int* ierr) {
 361   MPI_Group tmp;
 362
 363   *ierr = MPI_Comm_group(smpi_comm_f2c(*comm), &tmp);
 364   if(*ierr == MPI_SUCCESS) {
 365     *group_out = smpi_group_c2f(tmp);
 366   }
 367 }
 368
 369 void mpi_initialized_(int* flag, int* ierr){
 370   *ierr = MPI_Initialized(flag);
 371 }
 372
 373 void mpi_send_init_(void *buf, int* count, int* datatype, int* dst, int* tag, int* comm, int* request, int* ierr) {
 374   MPI_Request req;
 375   buf = static_cast<char *>(FORT_BOTTOM(buf));
 376   *ierr = MPI_Send_init(buf, *count, smpi_type_f2c(*datatype), *dst, *tag, smpi_comm_f2c(*comm), &req);
 377   if(*ierr == MPI_SUCCESS) {
 378     *request = smpi_request_c2f(req);
 379   }
 380 }
 381
 382 void mpi_isend_(void *buf, int* count, int* datatype, int* dst, int* tag, int* comm, int* request, int* ierr) {
 383   MPI_Request req;
 384   buf = static_cast<char *>(FORT_BOTTOM(buf));
 385   *ierr = MPI_Isend(buf, *count, smpi_type_f2c(*datatype), *dst, *tag, smpi_comm_f2c(*comm), &req);
 386   if(*ierr == MPI_SUCCESS) {
 387     *request = smpi_request_c2f(req);
 388   }
 389 }
 390
 391 void mpi_irsend_(void *buf, int* count, int* datatype, int* dst, int* tag, int* comm, int* request, int* ierr) {
 392   MPI_Request req;
 393   buf = static_cast<char *>(FORT_BOTTOM(buf));
 394   *ierr = MPI_Irsend(buf, *count, smpi_type_f2c(*datatype), *dst, *tag, smpi_comm_f2c(*comm), &req);
 395   if(*ierr == MPI_SUCCESS) {
 396     *request = smpi_request_c2f(req);
 397   }
 398 }
 399
 400 void mpi_send_(void* buf, int* count, int* datatype, int* dst, int* tag, int* comm, int* ierr) {
 401   buf = static_cast<char *>(FORT_BOTTOM(buf));
 402    *ierr = MPI_Send(buf, *count, smpi_type_f2c(*datatype), *dst, *tag, smpi_comm_f2c(*comm));
 403 }
 404
 405 void mpi_rsend_(void* buf, int* count, int* datatype, int* dst, int* tag, int* comm, int* ierr) {
 406   buf = static_cast<char *>(FORT_BOTTOM(buf));
 407    *ierr = MPI_Rsend(buf, *count, smpi_type_f2c(*datatype), *dst, *tag, smpi_comm_f2c(*comm));
 408 }
 409
 410 void mpi_sendrecv_(void* sendbuf, int* sendcount, int* sendtype, int* dst, int* sendtag, void *recvbuf, int* recvcount,
 411                    int* recvtype, int* src, int* recvtag, int* comm, MPI_Status* status, int* ierr) {
 412   sendbuf = static_cast<char *>( FORT_BOTTOM(sendbuf));
 413   recvbuf = static_cast<char *>( FORT_BOTTOM(recvbuf));
 414    *ierr = MPI_Sendrecv(sendbuf, *sendcount, smpi_type_f2c(*sendtype), *dst, *sendtag, recvbuf, *recvcount,
 415                         smpi_type_f2c(*recvtype), *src, *recvtag, smpi_comm_f2c(*comm), FORT_STATUS_IGNORE(status));
 416 }
 417
 418 void mpi_recv_init_(void *buf, int* count, int* datatype, int* src, int* tag, int* comm, int* request, int* ierr) {
 419   MPI_Request req;
 420   buf = static_cast<char *>( FORT_BOTTOM(buf));
 421   *ierr = MPI_Recv_init(buf, *count, smpi_type_f2c(*datatype), *src, *tag, smpi_comm_f2c(*comm), &req);
 422   if(*ierr == MPI_SUCCESS) {
 423     *request = smpi_request_c2f(req);
 424   }
 425 }
 426
 427 void mpi_irecv_(void *buf, int* count, int* datatype, int* src, int* tag, int* comm, int* request, int* ierr) {
 428   MPI_Request req;
 429   buf = static_cast<char *>( FORT_BOTTOM(buf));
 430   *ierr = MPI_Irecv(buf, *count, smpi_type_f2c(*datatype), *src, *tag, smpi_comm_f2c(*comm), &req);
 431   if(*ierr == MPI_SUCCESS) {
 432     *request = smpi_request_c2f(req);
 433   }
 434 }
 435
 436 void mpi_recv_(void* buf, int* count, int* datatype, int* src, int* tag, int* comm, MPI_Status* status, int* ierr) {
 437   buf = static_cast<char *>( FORT_BOTTOM(buf));
 438   *ierr = MPI_Recv(buf, *count, smpi_type_f2c(*datatype), *src, *tag, smpi_comm_f2c(*comm), status);
 439 }
 440
 441 void mpi_start_(int* request, int* ierr) {
 442   MPI_Request req = smpi_request_f2c(*request);
 443
 444   *ierr = MPI_Start(&req);
 445 }
 446
 447 void mpi_startall_(int* count, int* requests, int* ierr) {
 448   MPI_Request* reqs;
 449   int i;
 450
 451   reqs = xbt_new(MPI_Request, *count);
 452   for(i = 0; i < *count; i++) {
 453     reqs[i] = smpi_request_f2c(requests[i]);
 454   }
 455   *ierr = MPI_Startall(*count, reqs);
 456   xbt_free(reqs);
 457 }
 458
 459 void mpi_wait_(int* request, MPI_Status* status, int* ierr) {
 460    MPI_Request req = smpi_request_f2c(*request);
 461
 462    *ierr = MPI_Wait(&req, FORT_STATUS_IGNORE(status));
 463    if(req==MPI_REQUEST_NULL){
 464      free_request(*request);
 465      *request=MPI_FORTRAN_REQUEST_NULL;
 466    }
 467 }
 468
 469 void mpi_waitany_(int* count, int* requests, int* index, MPI_Status* status, int* ierr) {
 470   MPI_Request* reqs;
 471   int i;
 472
 473   reqs = xbt_new(MPI_Request, *count);
 474   for(i = 0; i < *count; i++) {
 475     reqs[i] = smpi_request_f2c(requests[i]);
 476   }
 477   *ierr = MPI_Waitany(*count, reqs, index, status);
 478   if(reqs[*index]==MPI_REQUEST_NULL){
 479       free_request(requests[*index]);
 480       requests[*index]=MPI_FORTRAN_REQUEST_NULL;
 481   }
 482   xbt_free(reqs);
 483 }
 484
 485 void mpi_waitall_(int* count, int* requests, MPI_Status* status, int* ierr) {
 486   MPI_Request* reqs;
 487   int i;
 488
 489   reqs = xbt_new(MPI_Request, *count);
 490   for(i = 0; i < *count; i++) {
 491     reqs[i] = smpi_request_f2c(requests[i]);
 492   }
 493   *ierr = MPI_Waitall(*count, reqs, FORT_STATUSES_IGNORE(status));
 494   for(i = 0; i < *count; i++) {
 495       if(reqs[i]==MPI_REQUEST_NULL){
 496           free_request(requests[i]);
 497           requests[i]=MPI_FORTRAN_REQUEST_NULL;
 498       }
 499   }
 500
 501   xbt_free(reqs);
 502 }
 503
 504 void mpi_barrier_(int* comm, int* ierr) {
 505   *ierr = MPI_Barrier(smpi_comm_f2c(*comm));
 506 }
 507
 508 void mpi_bcast_(void *buf, int* count, int* datatype, int* root, int* comm, int* ierr) {
 509   *ierr = MPI_Bcast(buf, *count, smpi_type_f2c(*datatype), *root, smpi_comm_f2c(*comm));
 510 }
 511
 512 void mpi_reduce_(void* sendbuf, void* recvbuf, int* count, int* datatype, int* op, int* root, int* comm, int* ierr) {
 513   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 514   sendbuf = static_cast<char *>( FORT_BOTTOM(sendbuf));
 515   recvbuf = static_cast<char *>( FORT_BOTTOM(recvbuf));
 516   *ierr = MPI_Reduce(sendbuf, recvbuf, *count, smpi_type_f2c(*datatype), smpi_op_f2c(*op), *root, smpi_comm_f2c(*comm));
 517 }
 518
 519 void mpi_allreduce_(void* sendbuf, void* recvbuf, int* count, int* datatype, int* op, int* comm, int* ierr) {
 520   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 521   *ierr = MPI_Allreduce(sendbuf, recvbuf, *count, smpi_type_f2c(*datatype), smpi_op_f2c(*op), smpi_comm_f2c(*comm));
 522 }
 523
 524 void mpi_reduce_scatter_(void* sendbuf, void* recvbuf, int* recvcounts, int* datatype, int* op, int* comm, int* ierr) {
 525   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 526   *ierr = MPI_Reduce_scatter(sendbuf, recvbuf, recvcounts, smpi_type_f2c(*datatype),
 527                         smpi_op_f2c(*op), smpi_comm_f2c(*comm));
 528 }
 529
 530 void mpi_scatter_(void* sendbuf, int* sendcount, int* sendtype, void* recvbuf, int* recvcount, int* recvtype,
 531                    int* root, int* comm, int* ierr) {
 532   recvbuf = static_cast<char *>( FORT_IN_PLACE(recvbuf));
 533   *ierr = MPI_Scatter(sendbuf, *sendcount, smpi_type_f2c(*sendtype),
 534                       recvbuf, *recvcount, smpi_type_f2c(*recvtype), *root, smpi_comm_f2c(*comm));
 535 }
 536
 537 void mpi_scatterv_(void* sendbuf, int* sendcounts, int* displs, int* sendtype,
 538                    void* recvbuf, int* recvcount, int* recvtype, int* root, int* comm, int* ierr) {
 539   recvbuf = static_cast<char *>( FORT_IN_PLACE(recvbuf));
 540   *ierr = MPI_Scatterv(sendbuf, sendcounts, displs, smpi_type_f2c(*sendtype),
 541                       recvbuf, *recvcount, smpi_type_f2c(*recvtype), *root, smpi_comm_f2c(*comm));
 542 }
 543
 544 void mpi_gather_(void* sendbuf, int* sendcount, int* sendtype, void* recvbuf, int* recvcount, int* recvtype,
 545                   int* root, int* comm, int* ierr) {
 546   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 547   sendbuf = static_cast<char *>( FORT_BOTTOM(sendbuf));
 548   recvbuf = static_cast<char *>( FORT_BOTTOM(recvbuf));
 549   *ierr = MPI_Gather(sendbuf, *sendcount, smpi_type_f2c(*sendtype),
 550                      recvbuf, *recvcount, smpi_type_f2c(*recvtype), *root, smpi_comm_f2c(*comm));
 551 }
 552
 553 void mpi_gatherv_(void* sendbuf, int* sendcount, int* sendtype,
 554                   void* recvbuf, int* recvcounts, int* displs, int* recvtype, int* root, int* comm, int* ierr) {
 555   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 556   sendbuf = static_cast<char *>( FORT_BOTTOM(sendbuf));
 557   recvbuf = static_cast<char *>( FORT_BOTTOM(recvbuf));
 558   *ierr = MPI_Gatherv(sendbuf, *sendcount, smpi_type_f2c(*sendtype),
 559                      recvbuf, recvcounts, displs, smpi_type_f2c(*recvtype), *root, smpi_comm_f2c(*comm));
 560 }
 561
 562 void mpi_allgather_(void* sendbuf, int* sendcount, int* sendtype, void* recvbuf, int* recvcount, int* recvtype,
 563                      int* comm, int* ierr) {
 564   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 565   *ierr = MPI_Allgather(sendbuf, *sendcount, smpi_type_f2c(*sendtype),
 566                         recvbuf, *recvcount, smpi_type_f2c(*recvtype), smpi_comm_f2c(*comm));
 567 }
 568
 569 void mpi_allgatherv_(void* sendbuf, int* sendcount, int* sendtype,
 570                      void* recvbuf, int* recvcounts,int* displs, int* recvtype, int* comm, int* ierr) {
 571   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
 572   *ierr = MPI_Allgatherv(sendbuf, *sendcount, smpi_type_f2c(*sendtype),
 573                         recvbuf, recvcounts, displs, smpi_type_f2c(*recvtype), smpi_comm_f2c(*comm));
 574 }
 575
 576 void mpi_scan_(void* sendbuf, void* recvbuf, int* count, int* datatype, int* op, int* comm, int* ierr) {
 577   *ierr = MPI_Scan(sendbuf, recvbuf, *count, smpi_type_f2c(*datatype),
 578                    smpi_op_f2c(*op), smpi_comm_f2c(*comm));
 579 }
 580
 581 void mpi_alltoall_(void* sendbuf, int* sendcount, int* sendtype,
 582                     void* recvbuf, int* recvcount, int* recvtype, int* comm, int* ierr) {
 583   *ierr = MPI_Alltoall(sendbuf, *sendcount, smpi_type_f2c(*sendtype),
 584                        recvbuf, *recvcount, smpi_type_f2c(*recvtype), smpi_comm_f2c(*comm));
 585 }
 586
 587 void mpi_alltoallv_(void* sendbuf, int* sendcounts, int* senddisps, int* sendtype,
 588                     void* recvbuf, int* recvcounts, int* recvdisps, int* recvtype, int* comm, int* ierr) {
 589   *ierr = MPI_Alltoallv(sendbuf, sendcounts, senddisps, smpi_type_f2c(*sendtype),
 590                        recvbuf, recvcounts, recvdisps, smpi_type_f2c(*recvtype), smpi_comm_f2c(*comm));
 591 }
 592
 593 void mpi_test_ (int * request, int *flag, MPI_Status * status, int* ierr){
 594   MPI_Request req = smpi_request_f2c(*request);
 595   *ierr= MPI_Test(&req, flag, FORT_STATUS_IGNORE(status));
 596   if(req==MPI_REQUEST_NULL){
 597       free_request(*request);
 598       *request=MPI_FORTRAN_REQUEST_NULL;
 599   }
 600 }
 601
 602 void mpi_testall_ (int* count, int * requests,  int *flag, MPI_Status * statuses, int* ierr){
 603   MPI_Request* reqs;
 604   int i;
 605   reqs = xbt_new(MPI_Request, *count);
 606   for(i = 0; i < *count; i++) {
 607     reqs[i] = smpi_request_f2c(requests[i]);
 608   }
 609   *ierr= MPI_Testall(*count, reqs, flag, FORT_STATUSES_IGNORE(statuses));
 610   for(i = 0; i < *count; i++) {
 611     if(reqs[i]==MPI_REQUEST_NULL){
 612         free_request(requests[i]);
 613         requests[i]=MPI_FORTRAN_REQUEST_NULL;
 614     }
 615   }
 616 }
 617
 618 void mpi_get_processor_name_(char *name, int *resultlen, int* ierr){
 619   *ierr = MPI_Get_processor_name(name, resultlen);
 620 }
 621
 622 void mpi_get_count_(MPI_Status * status, int* datatype, int *count, int* ierr){
 623   *ierr = MPI_Get_count(FORT_STATUS_IGNORE(status), smpi_type_f2c(*datatype), count);
 624 }
 625
 626 void mpi_attr_get_(int* comm, int* keyval, void* attr_value, int* flag, int* ierr ){
 627   *ierr = MPI_Attr_get(smpi_comm_f2c(*comm), *keyval, attr_value, flag);
 628 }
 629
 630 void mpi_type_extent_(int* datatype, MPI_Aint * extent, int* ierr){
 631   *ierr= MPI_Type_extent(smpi_type_f2c(*datatype),  extent);
 632 }
 633
 634 void mpi_type_commit_(int* datatype,  int* ierr){
 635   MPI_Datatype tmp= smpi_type_f2c(*datatype);
 636   *ierr= MPI_Type_commit(&tmp);
 637 }
 638
 639 void mpi_type_vector_(int* count, int* blocklen, int* stride, int* old_type, int* newtype,  int* ierr){
 640   MPI_Datatype tmp;
 641   *ierr= MPI_Type_vector(*count, *blocklen, *stride, smpi_type_f2c(*old_type), &tmp);
 642   if(*ierr == MPI_SUCCESS) {
 643     *newtype = smpi_type_c2f(tmp);
 644   }
 645 }
 646
 647 void mpi_type_create_vector_(int* count, int* blocklen, int* stride, int* old_type, int* newtype,  int* ierr){
 648   MPI_Datatype tmp;
 649   *ierr= MPI_Type_vector(*count, *blocklen, *stride, smpi_type_f2c(*old_type), &tmp);
 650   if(*ierr == MPI_SUCCESS) {
 651     *newtype = smpi_type_c2f(tmp);
 652   }
 653 }
 654
 655 void mpi_type_hvector_(int* count, int* blocklen, MPI_Aint* stride, int* old_type, int* newtype,  int* ierr){
 656   MPI_Datatype tmp;
 657   *ierr= MPI_Type_hvector (*count, *blocklen, *stride, smpi_type_f2c(*old_type), &tmp);
 658   if(*ierr == MPI_SUCCESS) {
 659     *newtype = smpi_type_c2f(tmp);
 660   }
 661 }
 662
 663 void mpi_type_create_hvector_(int* count, int* blocklen, MPI_Aint* stride, int* old_type, int* newtype,  int* ierr){
 664   MPI_Datatype tmp;
 665   *ierr= MPI_Type_hvector(*count, *blocklen, *stride, smpi_type_f2c(*old_type), &tmp);
 666   if(*ierr == MPI_SUCCESS) {
 667     *newtype = smpi_type_c2f(tmp);
 668   }
 669 }
 670
 671 void mpi_type_free_(int* datatype, int* ierr){
 672   MPI_Datatype tmp= smpi_type_f2c(*datatype);
 673   *ierr= MPI_Type_free (&tmp);
 674   if(*ierr == MPI_SUCCESS) {
 675     free_datatype(*datatype);
 676   }
 677 }
 678
 679 void mpi_type_ub_(int* datatype, MPI_Aint * disp, int* ierr){
 680   *ierr= MPI_Type_ub(smpi_type_f2c(*datatype), disp);
 681 }
 682
 683 void mpi_type_lb_(int* datatype, MPI_Aint * extent, int* ierr){
 684   *ierr= MPI_Type_extent(smpi_type_f2c(*datatype), extent);
 685 }
 686
 687 void mpi_type_size_(int* datatype, int *size, int* ierr)
 688 {
 689   *ierr = MPI_Type_size(smpi_type_f2c(*datatype), size);
 690 }
 691
 692 void mpi_error_string_(int* errorcode, char* string, int* resultlen, int* ierr){
 693   *ierr = MPI_Error_string(*errorcode, string, resultlen);
 694 }
 695
 696 void mpi_win_fence_( int* assert,  int* win, int* ierr){
 697   *ierr =  MPI_Win_fence(* assert, smpi_win_f2c(*win));
 698 }
 699
 700 void mpi_win_free_( int* win, int* ierr){
 701   MPI_Win tmp = smpi_win_f2c(*win);
 702   *ierr =  MPI_Win_free(&tmp);
 703   if(*ierr == MPI_SUCCESS) {
 704     free_win(*win);
 705   }
 706 }
 707
 708 void mpi_win_create_( int *base, MPI_Aint* size, int* disp_unit, int* info, int* comm, int *win, int* ierr){
 709   MPI_Win tmp;
 710   *ierr =  MPI_Win_create( static_cast<void*>(base), *size, *disp_unit, smpi_info_f2c(*info), smpi_comm_f2c(*comm),&tmp);
 711  if(*ierr == MPI_SUCCESS) {
 712    *win = smpi_win_c2f(tmp);
 713  }
 714 }
 715
 716 void mpi_win_post_(int* group, int assert, int* win, int* ierr){
 717   *ierr =  MPI_Win_post(smpi_group_f2c(*group), assert, smpi_win_f2c(*win));
 718 }
 719
 720 void mpi_win_start_(int* group, int assert, int* win, int* ierr){
 721   *ierr =  MPI_Win_start(smpi_group_f2c(*group), assert, smpi_win_f2c(*win));
 722 }
 723
 724 void mpi_win_complete_(int* win, int* ierr){
 725   *ierr =  MPI_Win_complete(smpi_win_f2c(*win));
 726 }
 727
 728 void mpi_win_wait_(int* win, int* ierr){
 729   *ierr =  MPI_Win_wait(smpi_win_f2c(*win));
 730 }
 731
 732 void mpi_win_set_name_ (int*  win, char * name, int* ierr, int size){
 733   //handle trailing blanks
 734   while(name[size-1]==' ')
 735     size--;
 736   while(*name==' '){//handle leading blanks
 737     size--;
 738     name++;
 739   }
 740   char* tname = xbt_new(char,size+1);
 741   strncpy(tname, name, size);
 742   tname[size]='\0';
 743   *ierr = MPI_Win_set_name(smpi_win_f2c(*win), tname);
 744   xbt_free(tname);
 745 }
 746
 747 void mpi_win_get_name_ (int*  win, char * name, int* len, int* ierr){
 748   *ierr = MPI_Win_get_name(smpi_win_f2c(*win),name,len);
 749   if(*len>0)
 750     name[*len]=' ';//blank padding, not \0
 751 }
 752
 753 void mpi_info_create_( int *info, int* ierr){
 754   MPI_Info tmp;
 755   *ierr =  MPI_Info_create(&tmp);
 756   if(*ierr == MPI_SUCCESS) {
 757     *info = smpi_info_c2f(tmp);
 758   }
 759 }
 760
 761 void mpi_info_set_( int *info, char *key, char *value, int* ierr, unsigned int keylen, unsigned int valuelen){
 762   //handle trailing blanks
 763   while(key[keylen-1]==' ')
 764     keylen--;
 765   while(*key==' '){//handle leading blanks
 766     keylen--;
 767     key++;
 768   }
 769   char* tkey = xbt_new(char,keylen+1);
 770   strncpy(tkey, key, keylen);
 771   tkey[keylen]='\0';
 772
 773   while(value[valuelen-1]==' ')
 774     valuelen--;
 775   while(*value==' '){//handle leading blanks
 776     valuelen--;
 777     value++;
 778   }
 779   char* tvalue = xbt_new(char,valuelen+1);
 780   strncpy(tvalue, value, valuelen);
 781
 782   tvalue[valuelen]='\0';
 783   *ierr =  MPI_Info_set( smpi_info_f2c(*info), tkey, tvalue);
 784   xbt_free(tkey);
 785 }
 786
 787 void mpi_info_get_ (int* info,char *key,int* valuelen, char *value, int *flag, int* ierr, unsigned int keylen ){
 788   while(key[keylen-1]==' ')
 789     keylen--;
 790   while(*key==' '){//handle leading blanks
 791     keylen--;
 792     key++;
 793   }
 794   char* tkey = xbt_new(char,keylen+1);
 795   strncpy(tkey, key, keylen);
 796   tkey[keylen]='\0';
 797   *ierr = MPI_Info_get(smpi_info_f2c(*info),tkey,*valuelen, value, flag);
 798   xbt_free(tkey);
 799   if(*flag==true){
 800     int replace=0;
 801     int i=0;
 802     for (i=0; i<*valuelen; i++){
 803       if(value[i]=='\0')
 804         replace=1;
 805       if(replace)
 806         value[i]=' ';
 807     }
 808   }
 809 }
 810
 811 void mpi_info_free_(int* info, int* ierr){
 812   MPI_Info tmp = smpi_info_f2c(*info);
 813   *ierr =  MPI_Info_free(&tmp);
 814   if(*ierr == MPI_SUCCESS) {
 815     free_info(*info);
 816   }
 817 }
 818
 819 void mpi_get_( int *origin_addr, int* origin_count, int* origin_datatype, int *target_rank,
 820     MPI_Aint* target_disp, int *target_count, int* tarsmpi_type_f2c, int* win, int* ierr){
 821   *ierr =  MPI_Get( static_cast<void*>(origin_addr),*origin_count, smpi_type_f2c(*origin_datatype),*target_rank,
 822       *target_disp, *target_count,smpi_type_f2c(*tarsmpi_type_f2c), smpi_win_f2c(*win));
 823 }
 824
 825 void mpi_accumulate_( int *origin_addr, int* origin_count, int* origin_datatype, int *target_rank,
 826     MPI_Aint* target_disp, int *target_count, int* tarsmpi_type_f2c, int* op, int* win, int* ierr){
 827   *ierr =  MPI_Accumulate( static_cast<void *>(origin_addr),*origin_count, smpi_type_f2c(*origin_datatype),*target_rank,
 828       *target_disp, *target_count,smpi_type_f2c(*tarsmpi_type_f2c), smpi_op_f2c(*op), smpi_win_f2c(*win));
 829 }
 830
 831 void mpi_put_( int *origin_addr, int* origin_count, int* origin_datatype, int *target_rank,
 832     MPI_Aint* target_disp, int *target_count, int* tarsmpi_type_f2c, int* win, int* ierr){
 833   *ierr =  MPI_Put( static_cast<void *>(origin_addr),*origin_count, smpi_type_f2c(*origin_datatype),*target_rank,
 834       *target_disp, *target_count,smpi_type_f2c(*tarsmpi_type_f2c), smpi_win_f2c(*win));
 835 }
 836
 837 //following are automatically generated, and have to be checked
 838 void mpi_finalized_ (int * flag, int* ierr){
 839
 840  *ierr = MPI_Finalized(flag);
 841 }
 842
 843 void mpi_init_thread_ (int* required, int *provided, int* ierr){
 844   smpi_init_fortran_types();
 845   *ierr = MPI_Init_thread(NULL, NULL,*required, provided);
 846   running_processes++;
 847 }
 848
 849 void mpi_query_thread_ (int *provided, int* ierr){
 850
 851  *ierr = MPI_Query_thread(provided);
 852 }
 853
 854 void mpi_is_thread_main_ (int *flag, int* ierr){
 855
 856  *ierr = MPI_Is_thread_main(flag);
 857 }
 858
 859 void mpi_address_ (void *location, MPI_Aint * address, int* ierr){
 860
 861  *ierr = MPI_Address(location, address);
 862 }
 863
 864 void mpi_get_address_ (void *location, MPI_Aint * address, int* ierr){
 865
 866  *ierr = MPI_Get_address(location, address);
 867 }
 868
 869 void mpi_type_dup_ (int*  datatype, int* newdatatype, int* ierr){
 870  MPI_Datatype tmp;
 871  *ierr = MPI_Type_dup(smpi_type_f2c(*datatype), &tmp);
 872  if(*ierr == MPI_SUCCESS) {
 873    *newdatatype = smpi_type_c2f(tmp);
 874  }
 875 }
 876
 877 void mpi_type_set_name_ (int*  datatype, char * name, int* ierr, int size){
 878  char* tname = xbt_new(char, size+1);
 879  strncpy(tname, name, size);
 880  tname[size]='\0';
 881  *ierr = MPI_Type_set_name(smpi_type_f2c(*datatype), tname);
 882  xbt_free(tname);
 883 }
 884
 885 void mpi_type_get_name_ (int*  datatype, char * name, int* len, int* ierr){
 886  *ierr = MPI_Type_get_name(smpi_type_f2c(*datatype),name,len);
 887   if(*len>0)
 888     name[*len]=' ';
 889 }
 890
 891 void mpi_type_get_attr_ (int* type, int* type_keyval, void *attribute_val, int* flag, int* ierr){
 892
 893  *ierr = MPI_Type_get_attr ( smpi_type_f2c(*type), *type_keyval, attribute_val,flag);
 894 }
 895
 896 void mpi_type_set_attr_ (int* type, int* type_keyval, void *attribute_val, int* ierr){
 897
 898  *ierr = MPI_Type_set_attr ( smpi_type_f2c(*type), *type_keyval, attribute_val);
 899 }
 900
 901 void mpi_type_delete_attr_ (int* type, int* type_keyval, int* ierr){
 902
 903  *ierr = MPI_Type_delete_attr ( smpi_type_f2c(*type),  *type_keyval);
 904 }
 905
 906 void mpi_type_create_keyval_ (void* copy_fn, void*  delete_fn, int* keyval, void* extra_state, int* ierr){
 907
 908  *ierr = MPI_Type_create_keyval(reinterpret_cast<MPI_Type_copy_attr_function*>(copy_fn), reinterpret_cast<MPI_Type_delete_attr_function*>(delete_fn),
 909                                 keyval,  extra_state) ;
 910 }
 911
 912 void mpi_type_free_keyval_ (int* keyval, int* ierr) {
 913  *ierr = MPI_Type_free_keyval( keyval);
 914 }
 915
 916 void mpi_pcontrol_ (int* level , int* ierr){
 917  *ierr = MPI_Pcontrol(*static_cast<const int*>(level));
 918 }
 919
 920 void mpi_type_get_extent_ (int* datatype, MPI_Aint * lb, MPI_Aint * extent, int* ierr){
 921
 922  *ierr = MPI_Type_get_extent(smpi_type_f2c(*datatype), lb, extent);
 923 }
 924
 925 void mpi_type_get_true_extent_ (int* datatype, MPI_Aint * lb, MPI_Aint * extent, int* ierr){
 926
 927  *ierr = MPI_Type_get_true_extent(smpi_type_f2c(*datatype), lb, extent);
 928 }
 929
 930 void mpi_op_create_ (void * function, int* commute, int* op, int* ierr){
 931   MPI_Op tmp;
 932  *ierr = MPI_Op_create(reinterpret_cast<MPI_User_function*>(function),*commute, &tmp);
 933  if(*ierr == MPI_SUCCESS) {
 934    *op = smpi_op_c2f(tmp);
 935  }
 936 }
 937
 938 void mpi_op_free_ (int* op, int* ierr){
 939   MPI_Op tmp=smpi_op_f2c(*op);
 940   *ierr = MPI_Op_free(& tmp);
 941   if(*ierr == MPI_SUCCESS) {
 942     free_op(*op);
 943   }
 944 }
 945
 946 void mpi_group_free_ (int* group, int* ierr){
 947  MPI_Group tmp=smpi_group_f2c(*group);
 948  *ierr = MPI_Group_free(&tmp);
 949  if(*ierr == MPI_SUCCESS) {
 950    free_group(*group);
 951  }
 952 }
 953
 954 void mpi_group_size_ (int* group, int *size, int* ierr){
 955
 956  *ierr = MPI_Group_size(smpi_group_f2c(*group), size);
 957 }
 958
 959 void mpi_group_rank_ (int* group, int *rank, int* ierr){
 960
 961  *ierr = MPI_Group_rank(smpi_group_f2c(*group), rank);
 962 }
 963
 964 void mpi_group_translate_ranks_ (int* group1, int* n, int *ranks1, int* group2, int *ranks2, int* ierr)
 965 {
 966
 967  *ierr = MPI_Group_translate_ranks(smpi_group_f2c(*group1), *n, ranks1, smpi_group_f2c(*group2), ranks2);
 968 }
 969
 970 void mpi_group_compare_ (int* group1, int* group2, int *result, int* ierr){
 971
 972  *ierr = MPI_Group_compare(smpi_group_f2c(*group1), smpi_group_f2c(*group2), result);
 973 }
 974
 975 void mpi_group_union_ (int* group1, int* group2, int* newgroup, int* ierr){
 976  MPI_Group tmp;
 977  *ierr = MPI_Group_union(smpi_group_f2c(*group1), smpi_group_f2c(*group2), &tmp);
 978  if(*ierr == MPI_SUCCESS) {
 979    *newgroup = smpi_group_c2f(tmp);
 980  }
 981 }
 982
 983 void mpi_group_intersection_ (int* group1, int* group2, int* newgroup, int* ierr){
 984  MPI_Group tmp;
 985  *ierr = MPI_Group_intersection(smpi_group_f2c(*group1), smpi_group_f2c(*group2), &tmp);
 986  if(*ierr == MPI_SUCCESS) {
 987    *newgroup = smpi_group_c2f(tmp);
 988  }
 989 }
 990
 991 void mpi_group_difference_ (int* group1, int* group2, int* newgroup, int* ierr){
 992  MPI_Group tmp;
 993  *ierr = MPI_Group_difference(smpi_group_f2c(*group1), smpi_group_f2c(*group2), &tmp);
 994  if(*ierr == MPI_SUCCESS) {
 995    *newgroup = smpi_group_c2f(tmp);
 996  }
 997 }
 998
 999 void mpi_group_excl_ (int* group, int* n, int *ranks, int* newgroup, int* ierr){
1000   MPI_Group tmp;
1001  *ierr = MPI_Group_excl(smpi_group_f2c(*group), *n, ranks, &tmp);
1002  if(*ierr == MPI_SUCCESS) {
1003    *newgroup = smpi_group_c2f(tmp);
1004  }
1005 }
1006
1007 void mpi_group_range_incl_ (int* group, int* n, int ranges[][3], int* newgroup, int* ierr)
1008 {
1009   MPI_Group tmp;
1010  *ierr = MPI_Group_range_incl(smpi_group_f2c(*group), *n, ranges, &tmp);
1011  if(*ierr == MPI_SUCCESS) {
1012    *newgroup = smpi_group_c2f(tmp);
1013  }
1014 }
1015
1016 void mpi_group_range_excl_ (int* group, int* n, int ranges[][3], int* newgroup, int* ierr)
1017 {
1018  MPI_Group tmp;
1019  *ierr = MPI_Group_range_excl(smpi_group_f2c(*group), *n, ranges, &tmp);
1020  if(*ierr == MPI_SUCCESS) {
1021    *newgroup = smpi_group_c2f(tmp);
1022  }
1023 }
1024
1025 void mpi_comm_get_attr_ (int* comm, int* comm_keyval, void *attribute_val, int *flag, int* ierr){
1026
1027  *ierr = MPI_Comm_get_attr (smpi_comm_f2c(*comm), *comm_keyval, attribute_val, flag);
1028 }
1029
1030 void mpi_comm_set_attr_ (int* comm, int* comm_keyval, void *attribute_val, int* ierr){
1031
1032  *ierr = MPI_Comm_set_attr ( smpi_comm_f2c(*comm), *comm_keyval, attribute_val);
1033 }
1034
1035 void mpi_comm_delete_attr_ (int* comm, int* comm_keyval, int* ierr){
1036
1037  *ierr = MPI_Comm_delete_attr (smpi_comm_f2c(*comm),  *comm_keyval);
1038 }
1039
1040 void mpi_comm_create_keyval_ (void* copy_fn, void* delete_fn, int* keyval, void* extra_state, int* ierr){
1041
1042  *ierr = MPI_Comm_create_keyval(reinterpret_cast<MPI_Comm_copy_attr_function*>(copy_fn),  reinterpret_cast<MPI_Comm_delete_attr_function*>(delete_fn),
1043          keyval,  extra_state) ;
1044 }
1045
1046 void mpi_comm_free_keyval_ (int* keyval, int* ierr) {
1047  *ierr = MPI_Comm_free_keyval( keyval);
1048 }
1049
1050 void mpi_comm_get_name_ (int* comm, char* name, int* len, int* ierr){
1051  *ierr = MPI_Comm_get_name(smpi_comm_f2c(*comm), name, len);
1052   if(*len>0)
1053     name[*len]=' ';
1054 }
1055
1056 void mpi_comm_compare_ (int* comm1, int* comm2, int *result, int* ierr){
1057
1058  *ierr = MPI_Comm_compare(smpi_comm_f2c(*comm1), smpi_comm_f2c(*comm2), result);
1059 }
1060
1061 void mpi_comm_disconnect_ (int* comm, int* ierr){
1062  MPI_Comm tmp=smpi_comm_f2c(*comm);
1063  *ierr = MPI_Comm_disconnect(&tmp);
1064  if(*ierr == MPI_SUCCESS) {
1065    free_comm(*comm);
1066  }
1067 }
1068
1069 void mpi_request_free_ (int* request, int* ierr){
1070   MPI_Request tmp=smpi_request_f2c(*request);
1071  *ierr = MPI_Request_free(&tmp);
1072  if(*ierr == MPI_SUCCESS) {
1073    free_request(*request);
1074  }
1075 }
1076
1077 void mpi_sendrecv_replace_ (void *buf, int* count, int* datatype, int* dst, int* sendtag, int* src, int* recvtag,
1078                             int* comm, MPI_Status* status, int* ierr)
1079 {
1080  *ierr = MPI_Sendrecv_replace(buf, *count, smpi_type_f2c(*datatype), *dst, *sendtag, *src,
1081  *recvtag, smpi_comm_f2c(*comm), FORT_STATUS_IGNORE(status));
1082 }
1083
1084 void mpi_testany_ (int* count, int* requests, int *index, int *flag, MPI_Status* status, int* ierr)
1085 {
1086   MPI_Request* reqs;
1087   int i;
1088
1089   reqs = xbt_new(MPI_Request, *count);
1090   for(i = 0; i < *count; i++) {
1091     reqs[i] = smpi_request_f2c(requests[i]);
1092   }
1093   *ierr = MPI_Testany(*count, reqs, index, flag, FORT_STATUS_IGNORE(status));
1094   if(*index!=MPI_UNDEFINED && reqs[*index]==MPI_REQUEST_NULL){
1095     free_request(requests[*index]);
1096     requests[*index]=MPI_FORTRAN_REQUEST_NULL;
1097   }
1098   xbt_free(reqs);
1099 }
1100
1101 void mpi_waitsome_ (int* incount, int* requests, int *outcount, int *indices, MPI_Status* status, int* ierr)
1102 {
1103   MPI_Request* reqs;
1104   int i;
1105
1106   reqs = xbt_new(MPI_Request, *incount);
1107   for(i = 0; i < *incount; i++) {
1108     reqs[i] = smpi_request_f2c(requests[i]);
1109   }
1110   *ierr = MPI_Waitsome(*incount, reqs, outcount, indices, status);
1111   for(i=0;i<*outcount;i++){
1112     if(reqs[indices[i]]==MPI_REQUEST_NULL){
1113         free_request(requests[indices[i]]);
1114         requests[indices[i]]=MPI_FORTRAN_REQUEST_NULL;
1115     }
1116   }
1117   xbt_free(reqs);
1118 }
1119
1120 void mpi_reduce_local_ (void *inbuf, void *inoutbuf, int* count, int* datatype, int* op, int* ierr){
1121
1122  *ierr = MPI_Reduce_local(inbuf, inoutbuf, *count, smpi_type_f2c(*datatype), smpi_op_f2c(*op));
1123 }
1124
1125 void mpi_reduce_scatter_block_ (void *sendbuf, void *recvbuf, int* recvcount, int* datatype, int* op, int* comm,
1126                                 int* ierr)
1127 {
1128   sendbuf = static_cast<char *>( FORT_IN_PLACE(sendbuf));
1129  *ierr = MPI_Reduce_scatter_block(sendbuf, recvbuf, *recvcount, smpi_type_f2c(*datatype), smpi_op_f2c(*op),
1130                                   smpi_comm_f2c(*comm));
1131 }
1132
1133 void mpi_pack_size_ (int* incount, int* datatype, int* comm, int* size, int* ierr) {
1134  *ierr = MPI_Pack_size(*incount, smpi_type_f2c(*datatype), smpi_comm_f2c(*comm), size);
1135 }
1136
1137 void mpi_cart_coords_ (int* comm, int* rank, int* maxdims, int* coords, int* ierr) {
1138  *ierr = MPI_Cart_coords(smpi_comm_f2c(*comm), *rank, *maxdims, coords);
1139 }
1140
1141 void mpi_cart_create_ (int* comm_old, int* ndims, int* dims, int* periods, int* reorder, int*  comm_cart, int* ierr) {
1142   MPI_Comm tmp;
1143  *ierr = MPI_Cart_create(smpi_comm_f2c(*comm_old), *ndims, dims, periods, *reorder, &tmp);
1144  if(*ierr == MPI_SUCCESS) {
1145    *comm_cart = smpi_comm_c2f(tmp);
1146  }
1147 }
1148
1149 void mpi_cart_get_ (int* comm, int* maxdims, int* dims, int* periods, int* coords, int* ierr) {
1150  *ierr = MPI_Cart_get(smpi_comm_f2c(*comm), *maxdims, dims, periods, coords);
1151 }
1152
1153 void mpi_cart_map_ (int* comm_old, int* ndims, int* dims, int* periods, int* newrank, int* ierr) {
1154  *ierr = MPI_Cart_map(smpi_comm_f2c(*comm_old), *ndims, dims, periods, newrank);
1155 }
1156
1157 void mpi_cart_rank_ (int* comm, int* coords, int* rank, int* ierr) {
1158  *ierr = MPI_Cart_rank(smpi_comm_f2c(*comm), coords, rank);
1159 }
1160
1161 void mpi_cart_shift_ (int* comm, int* direction, int* displ, int* source, int* dest, int* ierr) {
1162  *ierr = MPI_Cart_shift(smpi_comm_f2c(*comm), *direction, *displ, source, dest);
1163 }
1164
1165 void mpi_cart_sub_ (int* comm, int* remain_dims, int*  comm_new, int* ierr) {
1166  MPI_Comm tmp;
1167  *ierr = MPI_Cart_sub(smpi_comm_f2c(*comm), remain_dims, &tmp);
1168  if(*ierr == MPI_SUCCESS) {
1169    *comm_new = smpi_comm_c2f(tmp);
1170  }
1171 }
1172
1173 void mpi_cartdim_get_ (int* comm, int* ndims, int* ierr) {
1174  *ierr = MPI_Cartdim_get(smpi_comm_f2c(*comm), ndims);
1175 }
1176
1177 void mpi_graph_create_ (int* comm_old, int* nnodes, int* index, int* edges, int* reorder, int*  comm_graph, int* ierr) {
1178   MPI_Comm tmp;
1179  *ierr = MPI_Graph_create(smpi_comm_f2c(*comm_old), *nnodes, index, edges, *reorder, &tmp);
1180  if(*ierr == MPI_SUCCESS) {
1181    *comm_graph = smpi_comm_c2f(tmp);
1182  }
1183 }
1184
1185 void mpi_graph_get_ (int* comm, int* maxindex, int* maxedges, int* index, int* edges, int* ierr) {
1186  *ierr = MPI_Graph_get(smpi_comm_f2c(*comm), *maxindex, *maxedges, index, edges);
1187 }
1188
1189 void mpi_graph_map_ (int* comm_old, int* nnodes, int* index, int* edges, int* newrank, int* ierr) {
1190  *ierr = MPI_Graph_map(smpi_comm_f2c(*comm_old), *nnodes, index, edges, newrank);
1191 }
1192
1193 void mpi_graph_neighbors_ (int* comm, int* rank, int* maxneighbors, int* neighbors, int* ierr) {
1194  *ierr = MPI_Graph_neighbors(smpi_comm_f2c(*comm), *rank, *maxneighbors, neighbors);
1195 }
1196
1197 void mpi_graph_neighbors_count_ (int* comm, int* rank, int* nneighbors, int* ierr) {
1198  *ierr = MPI_Graph_neighbors_count(smpi_comm_f2c(*comm), *rank, nneighbors);
1199 }
1200
1201 void mpi_graphdims_get_ (int* comm, int* nnodes, int* nedges, int* ierr) {
1202  *ierr = MPI_Graphdims_get(smpi_comm_f2c(*comm), nnodes, nedges);
1203 }
1204
1205 void mpi_topo_test_ (int* comm, int* top_type, int* ierr) {
1206  *ierr = MPI_Topo_test(smpi_comm_f2c(*comm), top_type);
1207 }
1208
1209 void mpi_error_class_ (int* errorcode, int* errorclass, int* ierr) {
1210  *ierr = MPI_Error_class(*errorcode, errorclass);
1211 }
1212
1213 void mpi_errhandler_create_ (void* function, void* errhandler, int* ierr) {
1214  *ierr = MPI_Errhandler_create(reinterpret_cast<MPI_Handler_function*>(function), static_cast<MPI_Errhandler*>(errhandler));
1215 }
1216
1217 void mpi_errhandler_free_ (void* errhandler, int* ierr) {
1218  *ierr = MPI_Errhandler_free(static_cast<MPI_Errhandler*>(errhandler));
1219 }
1220
1221 void mpi_errhandler_get_ (int* comm, void* errhandler, int* ierr) {
1222  *ierr = MPI_Errhandler_get(smpi_comm_f2c(*comm), static_cast<MPI_Errhandler*>(errhandler));
1223 }
1224
1225 void mpi_errhandler_set_ (int* comm, void* errhandler, int* ierr) {
1226  *ierr = MPI_Errhandler_set(smpi_comm_f2c(*comm), *static_cast<MPI_Errhandler*>(errhandler));
1227 }
1228
1229 void mpi_comm_set_errhandler_ (int* comm, void* errhandler, int* ierr) {
1230  *ierr = MPI_Errhandler_set(smpi_comm_f2c(*comm), *static_cast<MPI_Errhandler*>(errhandler));
1231 }
1232
1233 void mpi_comm_get_errhandler_ (int* comm, void* errhandler, int* ierr) {
1234  *ierr = MPI_Errhandler_set(smpi_comm_f2c(*comm), static_cast<MPI_Errhandler*>(errhandler));
1235 }
1236
1237 void mpi_type_contiguous_ (int* count, int* old_type, int*  newtype, int* ierr) {
1238   MPI_Datatype tmp;
1239   *ierr = MPI_Type_contiguous(*count, smpi_type_f2c(*old_type), &tmp);
1240   if(*ierr == MPI_SUCCESS) {
1241     *newtype = smpi_type_c2f(tmp);
1242   }
1243 }
1244
1245 void mpi_cancel_ (int* request, int* ierr) {
1246   MPI_Request tmp=smpi_request_f2c(*request);
1247  *ierr = MPI_Cancel(&tmp);
1248 }
1249
1250 void mpi_buffer_attach_ (void* buffer, int* size, int* ierr) {
1251  *ierr = MPI_Buffer_attach(buffer, *size);
1252 }
1253
1254 void mpi_buffer_detach_ (void* buffer, int* size, int* ierr) {
1255  *ierr = MPI_Buffer_detach(buffer, size);
1256 }
1257
1258 void mpi_testsome_ (int* incount, int*  requests, int* outcount, int* indices, MPI_Status*  statuses, int* ierr) {
1259   MPI_Request* reqs;
1260   int i;
1261
1262   reqs = xbt_new(MPI_Request, *incount);
1263   for(i = 0; i < *incount; i++) {
1264     reqs[i] = smpi_request_f2c(requests[i]);
1265     indices[i]=0;
1266   }
1267   *ierr = MPI_Testsome(*incount, reqs, outcount, indices, FORT_STATUSES_IGNORE(statuses));
1268   for(i=0;i<*incount;i++){
1269     if(indices[i] && reqs[indices[i]]==MPI_REQUEST_NULL){
1270       free_request(requests[indices[i]]);
1271       requests[indices[i]]=MPI_FORTRAN_REQUEST_NULL;
1272     }
1273   }
1274   xbt_free(reqs);
1275 }
1276
1277 void mpi_comm_test_inter_ (int* comm, int* flag, int* ierr) {
1278  *ierr = MPI_Comm_test_inter(smpi_comm_f2c(*comm), flag);
1279 }
1280
1281 void mpi_unpack_ (void* inbuf, int* insize, int* position, void* outbuf, int* outcount, int* type, int* comm,
1282                   int* ierr) {
1283  *ierr = MPI_Unpack(inbuf, *insize, position, outbuf, *outcount, smpi_type_f2c(*type), smpi_comm_f2c(*comm));
1284 }
1285
1286 void mpi_pack_external_size_ (char *datarep, int* incount, int* datatype, MPI_Aint *size, int* ierr){
1287  *ierr = MPI_Pack_external_size(datarep, *incount, smpi_type_f2c(*datatype), size);
1288 }
1289
1290 void mpi_pack_external_ (char *datarep, void *inbuf, int* incount, int* datatype, void *outbuf, MPI_Aint* outcount,
1291                          MPI_Aint *position, int* ierr){
1292  *ierr = MPI_Pack_external(datarep, inbuf, *incount, smpi_type_f2c(*datatype), outbuf, *outcount, position);
1293 }
1294
1295 void mpi_unpack_external_ ( char *datarep, void *inbuf, MPI_Aint* insize, MPI_Aint *position, void *outbuf,
1296                             int* outcount, int* datatype, int* ierr){
1297  *ierr = MPI_Unpack_external( datarep, inbuf, *insize, position, outbuf, *outcount, smpi_type_f2c(*datatype));
1298 }
1299
1300 void mpi_type_hindexed_ (int* count, int* blocklens, MPI_Aint* indices, int* old_type, int*  newtype, int* ierr) {
1301   MPI_Datatype tmp;
1302   *ierr = MPI_Type_hindexed(*count, blocklens, indices, smpi_type_f2c(*old_type), &tmp);
1303   if(*ierr == MPI_SUCCESS) {
1304     *newtype = smpi_type_c2f(tmp);
1305   }
1306 }
1307
1308 void mpi_type_create_hindexed_(int* count, int* blocklens, MPI_Aint* indices, int* old_type, int*  newtype, int* ierr){
1309   MPI_Datatype tmp;
1310   *ierr = MPI_Type_create_hindexed(*count, blocklens, indices, smpi_type_f2c(*old_type), &tmp);
1311   if(*ierr == MPI_SUCCESS) {
1312     *newtype = smpi_type_c2f(tmp);
1313   }
1314 }
1315
1316 void mpi_type_create_hindexed_block_ (int* count, int* blocklength, MPI_Aint* indices, int* old_type, int*  newtype,
1317                                       int* ierr) {
1318   MPI_Datatype tmp;
1319   *ierr = MPI_Type_create_hindexed_block(*count, *blocklength, indices, smpi_type_f2c(*old_type), &tmp);
1320   if(*ierr == MPI_SUCCESS) {
1321     *newtype = smpi_type_c2f(tmp);
1322   }
1323 }
1324
1325 void mpi_type_indexed_ (int* count, int* blocklens, int* indices, int* old_type, int*  newtype, int* ierr) {
1326   MPI_Datatype tmp;
1327   *ierr = MPI_Type_indexed(*count, blocklens, indices, smpi_type_f2c(*old_type), &tmp);
1328   if(*ierr == MPI_SUCCESS) {
1329     *newtype = smpi_type_c2f(tmp);
1330   }
1331 }
1332
1333 void mpi_type_create_indexed_block_ (int* count, int* blocklength, int* indices,  int* old_type,  int*newtype,
1334                                      int* ierr){
1335   MPI_Datatype tmp;
1336   *ierr = MPI_Type_create_indexed_block(*count, *blocklength, indices, smpi_type_f2c(*old_type), &tmp);
1337   if(*ierr == MPI_SUCCESS) {
1338     *newtype = smpi_type_c2f(tmp);
1339   }
1340 }
1341
1342 void mpi_type_struct_ (int* count, int* blocklens, MPI_Aint* indices, int* old_types, int*  newtype, int* ierr) {
1343   MPI_Datatype tmp;
1344   int i=0;
1345   MPI_Datatype* types = static_cast<MPI_Datatype*>(xbt_malloc(*count*sizeof(MPI_Datatype)));
1346   for(i=0; i< *count; i++){
1347     types[i] = smpi_type_f2c(old_types[i]);
1348   }
1349   *ierr = MPI_Type_struct(*count, blocklens, indices, types, &tmp);
1350   if(*ierr == MPI_SUCCESS) {
1351     *newtype = smpi_type_c2f(tmp);
1352   }
1353   xbt_free(types);
1354 }
1355
1356 void mpi_type_create_struct_(int* count, int* blocklens, MPI_Aint* indices, int*  old_types, int*  newtype, int* ierr){
1357   MPI_Datatype tmp;
1358   int i=0;
1359   MPI_Datatype* types = static_cast<MPI_Datatype*>(xbt_malloc(*count*sizeof(MPI_Datatype)));
1360   for(i=0; i< *count; i++){
1361     types[i] = smpi_type_f2c(old_types[i]);
1362   }
1363   *ierr = MPI_Type_create_struct(*count, blocklens, indices, types, &tmp);
1364   if(*ierr == MPI_SUCCESS) {
1365     *newtype = smpi_type_c2f(tmp);
1366   }
1367   xbt_free(types);
1368 }
1369
1370 void mpi_ssend_ (void* buf, int* count, int* datatype, int* dest, int* tag, int* comm, int* ierr) {
1371  *ierr = MPI_Ssend(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm));
1372 }
1373
1374 void mpi_ssend_init_ (void* buf, int* count, int* datatype, int* dest, int* tag, int* comm, int* request, int* ierr) {
1375   MPI_Request tmp;
1376  *ierr = MPI_Ssend_init(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm), &tmp);
1377  if(*ierr == MPI_SUCCESS) {
1378    *request = smpi_request_c2f(tmp);
1379  }
1380 }
1381
1382 void mpi_intercomm_create_ (int* local_comm, int *local_leader, int* peer_comm, int* remote_leader, int* tag,
1383                             int* comm_out, int* ierr) {
1384   MPI_Comm tmp;
1385   *ierr = MPI_Intercomm_create(smpi_comm_f2c(*local_comm), *local_leader,smpi_comm_f2c(*peer_comm), *remote_leader,
1386                                *tag, &tmp);
1387   if(*ierr == MPI_SUCCESS) {
1388     *comm_out = smpi_comm_c2f(tmp);
1389   }
1390 }
1391
1392 void mpi_intercomm_merge_ (int* comm, int* high, int*  comm_out, int* ierr) {
1393  MPI_Comm tmp;
1394  *ierr = MPI_Intercomm_merge(smpi_comm_f2c(*comm), *high, &tmp);
1395  if(*ierr == MPI_SUCCESS) {
1396    *comm_out = smpi_comm_c2f(tmp);
1397  }
1398 }
1399
1400 void mpi_bsend_ (void* buf, int* count, int* datatype, int *dest, int* tag, int* comm, int* ierr) {
1401  *ierr = MPI_Bsend(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm));
1402 }
1403
1404 void mpi_bsend_init_ (void* buf, int* count, int* datatype, int *dest, int* tag, int* comm, int*  request, int* ierr) {
1405   MPI_Request tmp;
1406   *ierr = MPI_Bsend_init(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm), &tmp);
1407  if(*ierr == MPI_SUCCESS) {
1408    *request = smpi_request_c2f(tmp);
1409  }
1410 }
1411
1412 void mpi_ibsend_ (void* buf, int* count, int* datatype, int *dest, int* tag, int* comm, int*  request, int* ierr) {
1413   MPI_Request tmp;
1414   *ierr = MPI_Ibsend(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm), &tmp);
1415  if(*ierr == MPI_SUCCESS) {
1416    *request = smpi_request_c2f(tmp);
1417  }
1418 }
1419
1420 void mpi_comm_remote_group_ (int* comm, int*  group, int* ierr) {
1421   MPI_Group tmp;
1422  *ierr = MPI_Comm_remote_group(smpi_comm_f2c(*comm), &tmp);
1423  if(*ierr == MPI_SUCCESS) {
1424    *group = smpi_group_c2f(tmp);
1425  }
1426 }
1427
1428 void mpi_comm_remote_size_ (int* comm, int* size, int* ierr) {
1429  *ierr = MPI_Comm_remote_size(smpi_comm_f2c(*comm), size);
1430 }
1431
1432 void mpi_issend_ (void* buf, int* count, int* datatype, int *dest, int* tag, int* comm, int*  request, int* ierr) {
1433   MPI_Request tmp;
1434   *ierr = MPI_Issend(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm), &tmp);
1435  if(*ierr == MPI_SUCCESS) {
1436    *request = smpi_request_c2f(tmp);
1437  }
1438 }
1439
1440 void mpi_probe_ (int* source, int* tag, int* comm, MPI_Status*  status, int* ierr) {
1441  *ierr = MPI_Probe(*source, *tag, smpi_comm_f2c(*comm), FORT_STATUS_IGNORE(status));
1442 }
1443
1444 void mpi_attr_delete_ (int* comm, int* keyval, int* ierr) {
1445  *ierr = MPI_Attr_delete(smpi_comm_f2c(*comm), *keyval);
1446 }
1447
1448 void mpi_attr_put_ (int* comm, int* keyval, void* attr_value, int* ierr) {
1449  *ierr = MPI_Attr_put(smpi_comm_f2c(*comm), *keyval, attr_value);
1450 }
1451
1452 void mpi_rsend_init_ (void* buf, int* count, int* datatype, int *dest, int* tag, int* comm, int*  request, int* ierr) {
1453   MPI_Request tmp;
1454   *ierr = MPI_Rsend_init(buf, *count, smpi_type_f2c(*datatype), *dest, *tag, smpi_comm_f2c(*comm), &tmp);
1455  if(*ierr == MPI_SUCCESS) {
1456    *request = smpi_request_c2f(tmp);
1457  }
1458 }
1459
1460 void mpi_keyval_create_ (void* copy_fn, void* delete_fn, int* keyval, void* extra_state, int* ierr) {
1461  *ierr = MPI_Keyval_create(reinterpret_cast<MPI_Copy_function*>(copy_fn),reinterpret_cast<MPI_Delete_function*>(delete_fn), keyval, extra_state);
1462 }
1463
1464 void mpi_keyval_free_ (int* keyval, int* ierr) {
1465  *ierr = MPI_Keyval_free(keyval);
1466 }
1467
1468 void mpi_test_cancelled_ (MPI_Status*  status, int* flag, int* ierr) {
1469  *ierr = MPI_Test_cancelled(status, flag);
1470 }
1471
1472 void mpi_pack_ (void* inbuf, int* incount, int* type, void* outbuf, int* outcount, int* position, int* comm, int* ierr) {
1473  *ierr = MPI_Pack(inbuf, *incount, smpi_type_f2c(*type), outbuf, *outcount, position, smpi_comm_f2c(*comm));
1474 }
1475
1476 void mpi_get_elements_ (MPI_Status*  status, int* datatype, int* elements, int* ierr) {
1477  *ierr = MPI_Get_elements(status, smpi_type_f2c(*datatype), elements);
1478 }
1479
1480 void mpi_dims_create_ (int* nnodes, int* ndims, int* dims, int* ierr) {
1481  *ierr = MPI_Dims_create(*nnodes, *ndims, dims);
1482 }
1483
1484 void mpi_iprobe_ (int* source, int* tag, int* comm, int* flag, MPI_Status*  status, int* ierr) {
1485  *ierr = MPI_Iprobe(*source, *tag, smpi_comm_f2c(*comm), flag, status);
1486 }
1487
1488 void mpi_type_get_envelope_ ( int* datatype, int *num_integers, int *num_addresses, int *num_datatypes, int *combiner,
1489                               int* ierr){
1490  *ierr = MPI_Type_get_envelope(  smpi_type_f2c(*datatype), num_integers,
1491  num_addresses, num_datatypes, combiner);
1492 }
1493
1494 void mpi_type_get_contents_ (int* datatype, int* max_integers, int* max_addresses, int* max_datatypes,
1495                              int* array_of_integers, MPI_Aint* array_of_addresses,
1496  int* array_of_datatypes, int* ierr){
1497  *ierr = MPI_Type_get_contents(smpi_type_f2c(*datatype), *max_integers, *max_addresses,*max_datatypes,
1498                                array_of_integers, array_of_addresses, reinterpret_cast<MPI_Datatype*>(array_of_datatypes));
1499 }
1500
1501 void mpi_type_create_darray_ (int* size, int* rank, int* ndims, int* array_of_gsizes, int* array_of_distribs,
1502                               int* array_of_dargs, int* array_of_psizes,
1503  int* order, int* oldtype, int*newtype, int* ierr) {
1504   MPI_Datatype tmp;
1505   *ierr = MPI_Type_create_darray(*size, *rank, *ndims,  array_of_gsizes,
1506   array_of_distribs,  array_of_dargs,  array_of_psizes,
1507   *order,  smpi_type_f2c(*oldtype), &tmp) ;
1508   if(*ierr == MPI_SUCCESS) {
1509     *newtype = smpi_type_c2f(tmp);
1510   }
1511 }
1512
1513 void mpi_type_create_resized_ (int* oldtype,MPI_Aint* lb, MPI_Aint* extent, int*newtype, int* ierr){
1514   MPI_Datatype tmp;
1515   *ierr = MPI_Type_create_resized(smpi_type_f2c(*oldtype),*lb, *extent, &tmp);
1516   if(*ierr == MPI_SUCCESS) {
1517     *newtype = smpi_type_c2f(tmp);
1518   }
1519 }
1520
1521 void mpi_type_create_subarray_ (int* ndims,int *array_of_sizes, int *array_of_subsizes, int *array_of_starts,
1522                                 int* order, int* oldtype, int*newtype, int* ierr){
1523   MPI_Datatype tmp;
1524   *ierr = MPI_Type_create_subarray(*ndims,array_of_sizes, array_of_subsizes, array_of_starts, *order,
1525                                    smpi_type_f2c(*oldtype), &tmp);
1526   if(*ierr == MPI_SUCCESS) {
1527     *newtype = smpi_type_c2f(tmp);
1528   }
1529 }
1530
1531 void mpi_type_match_size_ (int* typeclass,int* size,int* datatype, int* ierr){
1532   MPI_Datatype tmp;
1533   *ierr = MPI_Type_match_size(*typeclass,*size,&tmp);
1534   if(*ierr == MPI_SUCCESS) {
1535     *datatype = smpi_type_c2f(tmp);
1536   }
1537 }
1538
1539 void mpi_alltoallw_ ( void *sendbuf, int *sendcnts, int *sdispls, int* sendtypes, void *recvbuf, int *recvcnts,
1540                       int *rdispls, int* recvtypes, int* comm, int* ierr){
1541  *ierr = MPI_Alltoallw( sendbuf, sendcnts, sdispls, reinterpret_cast<MPI_Datatype*>(sendtypes), recvbuf, recvcnts, rdispls,
1542                         reinterpret_cast<MPI_Datatype*>(recvtypes), smpi_comm_f2c(*comm));
1543 }
1544
1545 void mpi_exscan_ (void *sendbuf, void *recvbuf, int* count, int* datatype, int* op, int* comm, int* ierr){
1546  *ierr = MPI_Exscan(sendbuf, recvbuf, *count, smpi_type_f2c(*datatype), smpi_op_f2c(*op), smpi_comm_f2c(*comm));
1547 }
1548
1549 void mpi_comm_set_name_ (int* comm, char* name, int* ierr, int size){
1550  char* tname = xbt_new(char, size+1);
1551  strncpy(tname, name, size);
1552  tname[size]='\0';
1553  *ierr = MPI_Comm_set_name (smpi_comm_f2c(*comm), tname);
1554  xbt_free(tname);
1555 }
1556
1557 void mpi_comm_dup_with_info_ (int* comm, int* info, int* newcomm, int* ierr){
1558   MPI_Comm tmp;
1559   *ierr = MPI_Comm_dup_with_info(smpi_comm_f2c(*comm),smpi_info_f2c(*info),&tmp);
1560   if(*ierr == MPI_SUCCESS) {
1561     *newcomm = smpi_comm_c2f(tmp);
1562   }
1563 }
1564
1565 void mpi_comm_split_type_ (int* comm, int* split_type, int* key, int* info, int* newcomm, int* ierr){
1566   MPI_Comm tmp;
1567   *ierr = MPI_Comm_split_type(smpi_comm_f2c(*comm), *split_type, *key, smpi_info_f2c(*info), &tmp);
1568   if(*ierr == MPI_SUCCESS) {
1569     *newcomm = smpi_comm_c2f(tmp);
1570   }
1571 }
1572
1573 void mpi_comm_set_info_ (int* comm, int* info, int* ierr){
1574  *ierr = MPI_Comm_set_info (smpi_comm_f2c(*comm), smpi_info_f2c(*info));
1575 }
1576
1577 void mpi_comm_get_info_ (int* comm, int* info, int* ierr){
1578  MPI_Info tmp;
1579  *ierr = MPI_Comm_get_info (smpi_comm_f2c(*comm), &tmp);
1580  if(*ierr==MPI_SUCCESS){
1581    *info = smpi_info_c2f(tmp);
1582  }
1583 }
1584
1585 void mpi_comm_create_errhandler_ ( void *function, void *errhandler, int* ierr){
1586  *ierr = MPI_Comm_create_errhandler( reinterpret_cast<MPI_Comm_errhandler_fn*>(function), static_cast<MPI_Errhandler*>(errhandler));
1587 }
1588
1589 void mpi_add_error_class_ ( int *errorclass, int* ierr){
1590  *ierr = MPI_Add_error_class( errorclass);
1591 }
1592
1593 void mpi_add_error_code_ (  int* errorclass, int *errorcode, int* ierr){
1594  *ierr = MPI_Add_error_code(*errorclass, errorcode);
1595 }
1596
1597 void mpi_add_error_string_ ( int* errorcode, char *string, int* ierr){
1598  *ierr = MPI_Add_error_string(*errorcode, string);
1599 }
1600
1601 void mpi_comm_call_errhandler_ (int* comm,int* errorcode, int* ierr){
1602  *ierr = MPI_Comm_call_errhandler(smpi_comm_f2c(*comm), *errorcode);
1603 }
1604
1605 void mpi_info_dup_ (int* info, int* newinfo, int* ierr){
1606  MPI_Info tmp;
1607  *ierr = MPI_Info_dup(smpi_info_f2c(*info), &tmp);
1608  if(*ierr==MPI_SUCCESS){
1609    *newinfo= smpi_info_c2f(tmp);
1610  }
1611 }
1612
1613 void mpi_info_get_valuelen_ ( int* info, char *key, int *valuelen, int *flag, int* ierr, unsigned int keylen){
1614   while(key[keylen-1]==' ')
1615     keylen--;
1616   while(*key==' '){//handle leading blanks
1617     keylen--;
1618     key++;
1619   }
1620   char* tkey = xbt_new(char, keylen+1);
1621   strncpy(tkey, key, keylen);
1622   tkey[keylen]='\0';
1623   *ierr = MPI_Info_get_valuelen( smpi_info_f2c(*info), tkey, valuelen, flag);
1624   xbt_free(tkey);
1625 }
1626
1627 void mpi_info_delete_ (int* info, char *key, int* ierr, unsigned int keylen){
1628   while(key[keylen-1]==' ')
1629     keylen--;
1630   while(*key==' '){//handle leading blanks
1631     keylen--;
1632     key++;
1633   }
1634   char* tkey = xbt_new(char, keylen+1);
1635   strncpy(tkey, key, keylen);
1636   tkey[keylen]='\0';
1637   *ierr = MPI_Info_delete(smpi_info_f2c(*info), tkey);
1638   xbt_free(tkey);
1639 }
1640
1641 void mpi_info_get_nkeys_ ( int* info, int *nkeys, int* ierr){
1642  *ierr = MPI_Info_get_nkeys(  smpi_info_f2c(*info), nkeys);
1643 }
1644
1645 void mpi_info_get_nthkey_ ( int* info, int* n, char *key, int* ierr, unsigned int keylen){
1646   *ierr = MPI_Info_get_nthkey( smpi_info_f2c(*info), *n, key);
1647   unsigned int i = 0;
1648   for (i=strlen(key); i<keylen; i++)
1649     key[i]=' ';
1650 }
1651
1652 void mpi_get_version_ (int *version,int *subversion, int* ierr){
1653  *ierr = MPI_Get_version (version,subversion);
1654 }
1655
1656 void mpi_get_library_version_ (char *version,int *len, int* ierr){
1657  *ierr = MPI_Get_library_version (version,len);
1658 }
1659
1660 void mpi_request_get_status_ ( int* request, int *flag, MPI_Status* status, int* ierr){
1661  *ierr = MPI_Request_get_status( smpi_request_f2c(*request), flag, status);
1662 }
1663
1664 void mpi_grequest_start_ ( void *query_fn, void *free_fn, void *cancel_fn, void *extra_state, int*request, int* ierr){
1665   MPI_Request tmp;
1666   *ierr = MPI_Grequest_start( reinterpret_cast<MPI_Grequest_query_function*>(query_fn), reinterpret_cast<MPI_Grequest_free_function*>(free_fn),
1667                               reinterpret_cast<MPI_Grequest_cancel_function*>(cancel_fn), extra_state, &tmp);
1668  if(*ierr == MPI_SUCCESS) {
1669    *request = smpi_request_c2f(tmp);
1670  }
1671 }
1672
1673 void mpi_grequest_complete_ ( int* request, int* ierr){
1674  *ierr = MPI_Grequest_complete( smpi_request_f2c(*request));
1675 }
1676
1677 void mpi_status_set_cancelled_ (MPI_Status* status,int* flag, int* ierr){
1678  *ierr = MPI_Status_set_cancelled(status,*flag);
1679 }
1680
1681 void mpi_status_set_elements_ ( MPI_Status* status, int* datatype, int* count, int* ierr){
1682  *ierr = MPI_Status_set_elements( status, smpi_type_f2c(*datatype), *count);
1683 }
1684
1685 void mpi_comm_connect_ ( char *port_name, int* info, int* root, int* comm, int*newcomm, int* ierr){
1686   MPI_Comm tmp;
1687   *ierr = MPI_Comm_connect( port_name, *reinterpret_cast<MPI_Info*>(info), *root, smpi_comm_f2c(*comm), &tmp);
1688   if(*ierr == MPI_SUCCESS) {
1689     *newcomm = smpi_comm_c2f(tmp);
1690   }
1691 }
1692
1693 void mpi_publish_name_ ( char *service_name, int* info, char *port_name, int* ierr){
1694  *ierr = MPI_Publish_name( service_name, *reinterpret_cast<MPI_Info*>(info), port_name);
1695 }
1696
1697 void mpi_unpublish_name_ ( char *service_name, int* info, char *port_name, int* ierr){
1698  *ierr = MPI_Unpublish_name( service_name, *reinterpret_cast<MPI_Info*>(info), port_name);
1699 }
1700
1701 void mpi_lookup_name_ ( char *service_name, int* info, char *port_name, int* ierr){
1702  *ierr = MPI_Lookup_name( service_name, *reinterpret_cast<MPI_Info*>(info), port_name);
1703 }
1704
1705 void mpi_comm_join_ ( int* fd, int* intercomm, int* ierr){
1706   MPI_Comm tmp;
1707   *ierr = MPI_Comm_join( *fd, &tmp);
1708   if(*ierr == MPI_SUCCESS) {
1709     *intercomm = smpi_comm_c2f(tmp);
1710   }
1711 }
1712
1713 void mpi_open_port_ ( int* info, char *port_name, int* ierr){
1714  *ierr = MPI_Open_port( *reinterpret_cast<MPI_Info*>(info),port_name);
1715 }
1716
1717 void mpi_close_port_ ( char *port_name, int* ierr){
1718  *ierr = MPI_Close_port( port_name);
1719 }
1720
1721 void mpi_comm_accept_ ( char *port_name, int* info, int* root, int* comm, int*newcomm, int* ierr){
1722   MPI_Comm tmp;
1723   *ierr = MPI_Comm_accept( port_name, *reinterpret_cast<MPI_Info*>(info), *root, smpi_comm_f2c(*comm), &tmp);
1724   if(*ierr == MPI_SUCCESS) {
1725     *newcomm = smpi_comm_c2f(tmp);
1726   }
1727 }
1728
1729 void mpi_comm_spawn_ ( char *command, char *argv, int* maxprocs, int* info, int* root, int* comm, int* intercomm,
1730                        int* array_of_errcodes, int* ierr){
1731   MPI_Comm tmp;
1732   *ierr = MPI_Comm_spawn( command, NULL, *maxprocs, *reinterpret_cast<MPI_Info*>(info), *root, smpi_comm_f2c(*comm), &tmp,
1733                           array_of_errcodes);
1734   if(*ierr == MPI_SUCCESS) {
1735     *intercomm = smpi_comm_c2f(tmp);
1736   }
1737 }
1738
1739 void mpi_comm_spawn_multiple_ ( int* count, char *array_of_commands, char** array_of_argv, int* array_of_maxprocs,
1740                                 int* array_of_info, int* root,
1741  int* comm, int* intercomm, int* array_of_errcodes, int* ierr){
1742  MPI_Comm tmp;
1743  *ierr = MPI_Comm_spawn_multiple(* count, &array_of_commands, &array_of_argv, array_of_maxprocs,
1744  reinterpret_cast<MPI_Info*>(array_of_info), *root, smpi_comm_f2c(*comm), &tmp, array_of_errcodes);
1745  if(*ierr == MPI_SUCCESS) {
1746    *intercomm = smpi_comm_c2f(tmp);
1747  }
1748 }
1749
1750 void mpi_comm_get_parent_ ( int* parent, int* ierr){
1751   MPI_Comm tmp;
1752   *ierr = MPI_Comm_get_parent( &tmp);
1753   if(*ierr == MPI_SUCCESS) {
1754     *parent = smpi_comm_c2f(tmp);
1755   }
1756 }