00001
00002
00003
00004
00005
00006
00007
00008 #include "mpioimpl.h"
00009
00010 #ifdef HAVE_WEAK_SYMBOLS
00011
00012 #if defined(HAVE_PRAGMA_WEAK)
00013 #pragma weak MPI_File_read_ordered_begin = PMPI_File_read_ordered_begin
00014 #elif defined(HAVE_PRAGMA_HP_SEC_DEF)
00015 #pragma _HP_SECONDARY_DEF PMPI_File_read_ordered_begin MPI_File_read_ordered_begin
00016 #elif defined(HAVE_PRAGMA_CRI_DUP)
00017 #pragma _CRI duplicate MPI_File_read_ordered_begin as PMPI_File_read_ordered_begin
00018
00019 #endif
00020
00021
00022 #define MPIO_BUILD_PROFILING
00023 #include "mpioprof.h"
00024 #endif
00025
00026
00027
00028
00029
00030
00031
00032
00033
00034
00035
00036
00037
00038
00039 int MPI_File_read_ordered_begin(MPI_File mpi_fh, void *buf, int count,
00040 MPI_Datatype datatype)
00041 {
00042 int error_code, datatype_size, nprocs, myrank, incr;
00043 int source, dest;
00044 ADIO_Offset shared_fp;
00045 ADIO_File fh;
00046 static char myname[] = "MPI_FILE_READ_ORDERED_BEGIN";
00047
00048 MPIU_THREAD_CS_ENTER(ALLFUNC,);
00049
00050 fh = MPIO_File_resolve(mpi_fh);
00051
00052
00053 MPIO_CHECK_FILE_HANDLE(fh, myname, error_code);
00054 MPIO_CHECK_COUNT(fh, count, myname, error_code);
00055 MPIO_CHECK_DATATYPE(fh, datatype, myname, error_code);
00056
00057 if (fh->split_coll_count)
00058 {
00059 error_code = MPIO_Err_create_code(MPI_SUCCESS, MPIR_ERR_RECOVERABLE,
00060 myname, __LINE__, MPI_ERR_IO,
00061 "**iosplitcoll", 0);
00062 error_code = MPIO_Err_return_file(fh, error_code);
00063 goto fn_exit;
00064 }
00065
00066
00067 fh->split_coll_count = 1;
00068
00069
00070 MPI_Type_size(datatype, &datatype_size);
00071
00072 MPIO_CHECK_INTEGRAL_ETYPE(fh, count, datatype_size, myname, error_code);
00073 MPIO_CHECK_FS_SUPPORTS_SHARED(fh, myname, error_code);
00074 MPIO_CHECK_COUNT_SIZE(fh, count, datatype_size, myname, error_code);
00075
00076
00077 ADIOI_TEST_DEFERRED(fh, myname, &error_code);
00078
00079 MPI_Comm_size(fh->comm, &nprocs);
00080 MPI_Comm_rank(fh->comm, &myrank);
00081
00082 incr = (count*datatype_size)/fh->etype_size;
00083
00084 source = myrank - 1;
00085 dest = myrank + 1;
00086 if (source < 0) source = MPI_PROC_NULL;
00087 if (dest >= nprocs) dest = MPI_PROC_NULL;
00088 MPI_Recv(NULL, 0, MPI_BYTE, source, 0, fh->comm, MPI_STATUS_IGNORE);
00089
00090 ADIO_Get_shared_fp(fh, incr, &shared_fp, &error_code);
00091
00092 if (error_code != MPI_SUCCESS)
00093 {
00094 error_code = MPIO_Err_return_file(fh, error_code);
00095 goto fn_exit;
00096 }
00097
00098
00099 MPI_Send(NULL, 0, MPI_BYTE, dest, 0, fh->comm);
00100
00101 ADIO_ReadStridedColl(fh, buf, count, datatype, ADIO_EXPLICIT_OFFSET,
00102 shared_fp, &fh->split_status, &error_code);
00103
00104
00105 if (error_code != MPI_SUCCESS)
00106 error_code = MPIO_Err_return_file(fh, error_code);
00107
00108
00109 fn_exit:
00110 MPIU_THREAD_CS_EXIT(ALLFUNC,);
00111
00112 return error_code;
00113 }