X-Git-Url: http://info.iut-bm.univ-fcomte.fr/pub/gitweb/simgrid.git/blobdiff_plain/a2f1b23687f04169144f4ffb4f20dc4fc5c28395..1687df79d61a9418bba830bbd0ab7de16e457090:/src/smpi/colls/allgather-smp-simple.c diff --git a/src/smpi/colls/allgather-smp-simple.c b/src/smpi/colls/allgather-smp-simple.c index c8f0c68d6b..e54c75b5b9 100644 --- a/src/smpi/colls/allgather-smp-simple.c +++ b/src/smpi/colls/allgather-smp-simple.c @@ -1,7 +1,10 @@ -#include "colls.h" -#ifndef NUM_CORE -#define NUM_CORE 8 -#endif +/* Copyright (c) 2013-2014. The SimGrid Team. + * All rights reserved. */ + +/* This program is free software; you can redistribute it and/or modify it + * under the terms of the license (GNU LGPL) which comes with this package. */ + +#include "colls_private.h" int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, MPI_Datatype stype, void *recv_buf, @@ -9,16 +12,27 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, MPI_Comm comm) { int src, dst, comm_size, rank; - MPI_Comm_size(comm, &comm_size); - MPI_Comm_rank(comm, &rank); + comm_size = smpi_comm_size(comm); + + if(smpi_comm_get_leaders_comm(comm)==MPI_COMM_NULL){ + smpi_comm_init_smp(comm); + } + int num_core=1; + if (smpi_comm_is_uniform(comm)){ + num_core = smpi_comm_size(smpi_comm_get_intra_comm(comm)); + } + + if(comm_size%num_core) + THROWF(arg_error,0, "allgather SMP simple algorithm can't be used with non multiple of NUM_CORE=%d number of processes ! ", num_core); + + rank = smpi_comm_rank(comm); MPI_Aint rextent, sextent; - MPI_Type_extent(rtype, &rextent); - MPI_Type_extent(stype, &sextent); - int tag = 50; + rextent = smpi_datatype_get_extent(rtype); + sextent = smpi_datatype_get_extent(stype); + int tag = COLL_TAG_ALLGATHER; MPI_Status status; int i, send_offset, recv_offset; int intra_rank, inter_rank; - int num_core = NUM_CORE; intra_rank = rank % num_core; inter_rank = rank / num_core; int inter_comm_size = (comm_size + num_core - 1) / num_core; @@ -30,7 +44,7 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, } //INTRA-SMP-ALLGATHER recv_offset = rank * rextent * rcount; - MPI_Sendrecv(send_buf, scount, stype, rank, tag, + smpi_mpi_sendrecv(send_buf, scount, stype, rank, tag, ((char *) recv_buf + recv_offset), rcount, rtype, rank, tag, comm, &status); for (i = 1; i < num_core_in_current_smp; i++) { @@ -43,7 +57,7 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, (num_core_in_current_smp); recv_offset = src * rextent * rcount; - MPI_Sendrecv(send_buf, scount, stype, dst, tag, + smpi_mpi_sendrecv(send_buf, scount, stype, dst, tag, ((char *) recv_buf + recv_offset), rcount, rtype, src, tag, comm, &status); @@ -57,10 +71,10 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, if (intra_rank == 0) { MPI_Request *reqs, *req_ptr; int num_req = (inter_comm_size - 1) * 2; - reqs = (MPI_Request *) malloc(num_req * sizeof(MPI_Request)); + reqs = (MPI_Request *) xbt_malloc(num_req * sizeof(MPI_Request)); req_ptr = reqs; MPI_Status *stat; - stat = (MPI_Status *) malloc(num_req * sizeof(MPI_Status)); + stat = (MPI_Status *) xbt_malloc(num_req * sizeof(MPI_Status)); for (i = 1; i < inter_comm_size; i++) { @@ -68,11 +82,11 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, src = ((inter_rank - i + inter_comm_size) % inter_comm_size) * num_core; //send_offset = (rank * sextent * scount); recv_offset = (src * sextent * scount); - // MPI_Sendrecv((recv_buf+send_offset), (scount * num_core), stype, dst, tag, + // smpi_mpi_sendrecv((recv_buf+send_offset), (scount * num_core), stype, dst, tag, // (recv_buf+recv_offset), (rcount * num_core), rtype, src, tag, comm, &status); //MPIC_Isend((recv_buf+send_offset), (scount * num_core), stype, dst, tag, comm, req_ptr++); - MPI_Irecv(((char *) recv_buf + recv_offset), (rcount * num_core), rtype, - src, tag, comm, req_ptr++); + *(req_ptr++) = smpi_mpi_irecv(((char *) recv_buf + recv_offset), (rcount * num_core), rtype, + src, tag, comm); } for (i = 1; i < inter_comm_size; i++) { @@ -80,13 +94,13 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, //src = ((inter_rank-i+inter_comm_size)%inter_comm_size) * num_core; send_offset = (rank * sextent * scount); //recv_offset = (src * sextent * scount); - // MPI_Sendrecv((recv_buf+send_offset), (scount * num_core), stype, dst, tag, + // smpi_mpi_sendrecv((recv_buf+send_offset), (scount * num_core), stype, dst, tag, // (recv_buf+recv_offset), (rcount * num_core), rtype, src, tag, comm, &status); - MPI_Isend(((char *) recv_buf + send_offset), (scount * num_core), stype, - dst, tag, comm, req_ptr++); + *(req_ptr++) = smpi_mpi_isend(((char *) recv_buf + send_offset), (scount * num_core), stype, + dst, tag, comm); //MPIC_Irecv((recv_buf+recv_offset), (rcount * num_core), rtype, src, tag, comm, req_ptr++); } - MPI_Waitall(num_req, reqs, stat); + smpi_mpi_waitall(num_req, reqs, stat); free(reqs); free(stat); @@ -96,11 +110,11 @@ int smpi_coll_tuned_allgather_smp_simple(void *send_buf, int scount, if (intra_rank == 0) { for (i = 1; i < num_core_in_current_smp; i++) { //printf("rank = %d, num = %d send to %d\n",rank, num_core_in_current_smp, (rank + i)); - MPI_Send(recv_buf, (scount * comm_size), stype, (rank + i), tag, comm); + smpi_mpi_send(recv_buf, (scount * comm_size), stype, (rank + i), tag, comm); } } else { //printf("rank = %d recv from %d\n",rank, (inter_rank * num_core)); - MPI_Recv(recv_buf, (rcount * comm_size), rtype, (inter_rank * num_core), + smpi_mpi_recv(recv_buf, (rcount * comm_size), rtype, (inter_rank * num_core), tag, comm, &status); }