Skip to content

Commit

Permalink
added 64-bit MPI gather into SSC helper
Browse files Browse the repository at this point in the history
  • Loading branch information
@JasonRuonanWang
JasonRuonanWang committed Aug 8, 2020
1 parent b093a43 commit 89b219d
Show file tree
Hide file tree
Showing 2 changed files with 197 additions and 0 deletions.
180 changes: 180 additions & 0 deletions source/adios2/engine/ssc/SscHelper.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -281,6 +281,186 @@ bool AreSameDims(const Dims &a, const Dims &b)
return true;
}

void MPI_Gatherv64(const void *sendbuf, uint64_t sendcount,
MPI_Datatype sendtype, void *recvbuf,
const uint64_t *recvcounts, const uint64_t *displs,
MPI_Datatype recvtype, int root, MPI_Comm comm,
const int chunksize)
{

int mpiSize;
int mpiRank;
MPI_Comm_size(comm, &mpiSize);
MPI_Comm_rank(comm, &mpiRank);

int recvTypeSize;
int sendTypeSize;

MPI_Type_size(recvtype, &recvTypeSize);
MPI_Type_size(sendtype, &sendTypeSize);

std::vector<MPI_Request> requests;
if (mpiRank == root)
{
for (int i = 0; i < mpiSize; ++i)
{
uint64_t recvcount = recvcounts[i];
while (recvcount > 0)
{
requests.emplace_back();
if (recvcount > chunksize)
{
MPI_Irecv(reinterpret_cast<char *>(recvbuf) +
(displs[i] + recvcounts[i] - recvcount) *
recvTypeSize,
chunksize, recvtype, i, 0, comm,
&requests.back());
recvcount -= chunksize;
}
else
{
MPI_Irecv(reinterpret_cast<char *>(recvbuf) +
(displs[i] + recvcounts[i] - recvcount) *
recvTypeSize,
static_cast<int>(recvcount), recvtype, i, 0, comm,
&requests.back());
recvcount = 0;
}
}
}
}

uint64_t sendcountvar = sendcount;

while (sendcountvar > 0)
{
requests.emplace_back();
if (sendcountvar > chunksize)
{
MPI_Isend(reinterpret_cast<const char *>(sendbuf) +
(sendcount - sendcountvar) * sendTypeSize,
chunksize, sendtype, root, 0, comm, &requests.back());
sendcountvar -= chunksize;
}
else
{
MPI_Isend(reinterpret_cast<const char *>(sendbuf) +
(sendcount - sendcountvar) * sendTypeSize,
static_cast<int>(sendcountvar), sendtype, root, 0, comm,
&requests.back());
sendcountvar = 0;
}
}

MPI_Waitall(requests.size(), requests.data(), MPI_STATUSES_IGNORE);
}

void MPI_Gatherv64OneSidedPull(const void *sendbuf, uint64_t sendcount,
MPI_Datatype sendtype, void *recvbuf,
const uint64_t *recvcounts,
const uint64_t *displs, MPI_Datatype recvtype,
int root, MPI_Comm comm, const int chunksize)
{

int mpiSize;
int mpiRank;
MPI_Comm_size(comm, &mpiSize);
MPI_Comm_rank(comm, &mpiRank);

int recvTypeSize;
int sendTypeSize;

MPI_Type_size(recvtype, &recvTypeSize);
MPI_Type_size(sendtype, &sendTypeSize);

MPI_Win win;
MPI_Win_create(const_cast<void *>(sendbuf), sendcount * sendTypeSize,
sendTypeSize, MPI_INFO_NULL, comm, &win);

if (mpiRank == root)
{
for (int i = 0; i < mpiSize; ++i)
{
uint64_t recvcount = recvcounts[i];
while (recvcount > 0)
{
if (recvcount > chunksize)
{
MPI_Get(reinterpret_cast<char *>(recvbuf) +
(displs[i] + recvcounts[i] - recvcount) *
recvTypeSize,
chunksize, recvtype, i, recvcounts[i] - recvcount,
chunksize, recvtype, win);
recvcount -= chunksize;
}
else
{
MPI_Get(reinterpret_cast<char *>(recvbuf) +
(displs[i] + recvcounts[i] - recvcount) *
recvTypeSize,
static_cast<int>(recvcount), recvtype, i,
recvcounts[i] - recvcount,
static_cast<int>(recvcount), recvtype, win);
recvcount = 0;
}
}
}
}

MPI_Win_free(&win);
}

void MPI_Gatherv64OneSidedPush(const void *sendbuf, uint64_t sendcount,
MPI_Datatype sendtype, void *recvbuf,
const uint64_t *recvcounts,
const uint64_t *displs, MPI_Datatype recvtype,
int root, MPI_Comm comm, const int chunksize)
{

int mpiSize;
int mpiRank;
MPI_Comm_size(comm, &mpiSize);
MPI_Comm_rank(comm, &mpiRank);

int recvTypeSize;
int sendTypeSize;

MPI_Type_size(recvtype, &recvTypeSize);
MPI_Type_size(sendtype, &sendTypeSize);

uint64_t recvsize = displs[mpiSize - 1] + recvcounts[mpiSize - 1];

MPI_Win win;
MPI_Win_create(recvbuf, recvsize * recvTypeSize, recvTypeSize,
MPI_INFO_NULL, comm, &win);

uint64_t sendcountvar = sendcount;

while (sendcountvar > 0)
{
if (sendcountvar > chunksize)
{
MPI_Put(reinterpret_cast<const char *>(sendbuf) +
(sendcount - sendcountvar) * sendTypeSize,
chunksize, sendtype, root,
displs[mpiRank] + sendcount - sendcountvar, chunksize,
sendtype, win);
sendcountvar -= chunksize;
}
else
{
MPI_Put(reinterpret_cast<const char *>(sendbuf) +
(sendcount - sendcountvar) * sendTypeSize,
sendcountvar, sendtype, root,
displs[mpiRank] + sendcount - sendcountvar, sendcountvar,
sendtype, win);
sendcountvar = 0;
}
}

MPI_Win_free(&win);
}

void PrintDims(const Dims &dims, const std::string &label)
{
std::cout << label;
Expand Down
17 changes: 17 additions & 0 deletions source/adios2/engine/ssc/SscHelper.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -15,6 +15,7 @@
#include "adios2/core/IO.h"
#include "nlohmann/json.hpp"
#include <map>
#include <mpi.h>
#include <vector>

namespace adios2
Expand Down Expand Up @@ -70,6 +71,22 @@ void JsonToBlockVecVec(const nlohmann::json &input, BlockVecVec &output);
void JsonToBlockVecVec(const std::vector<char> &input, BlockVecVec &output);
void JsonToBlockVecVec(const std::string &input, BlockVecVec &output);

void MPI_Gatherv64OneSidedPush(
const void *sendbuf, uint64_t sendcount, MPI_Datatype sendtype,
void *recvbuf, const uint64_t *recvcounts, const uint64_t *displs,
MPI_Datatype recvtype, int root, MPI_Comm comm,
const int chunksize = std::numeric_limits<int>::max());
void MPI_Gatherv64OneSidedPull(
const void *sendbuf, uint64_t sendcount, MPI_Datatype sendtype,
void *recvbuf, const uint64_t *recvcounts, const uint64_t *displs,
MPI_Datatype recvtype, int root, MPI_Comm comm,
const int chunksize = std::numeric_limits<int>::max());
void MPI_Gatherv64(const void *sendbuf, uint64_t sendcount,
MPI_Datatype sendtype, void *recvbuf,
const uint64_t *recvcounts, const uint64_t *displs,
MPI_Datatype recvtype, int root, MPI_Comm comm,
const int chunksize = std::numeric_limits<int>::max());

bool AreSameDims(const Dims &a, const Dims &b);

} // end namespace ssc
Expand Down

0 comments on commit 89b219d

Please sign in to comment.