/* -*- Mode: C; c-basic-offset:4 ; indent-tabs-mode:nil ; -*- */ /* * (C) 2014 by Argonne National Laboratory. * See COPYRIGHT in top-level directory. */ #include "mpi.h" #include "mpitest.h" #include #include /* Communicating a datatype built out of structs * This test was motivated by the failure of an example program for * RMA involving simple operations on a struct that included a struct * * The observed failure was a SEGV in the MPI_Get * * */ #define MAX_KEY_SIZE 64 #define MAX_VALUE_SIZE 256 typedef struct { MPI_Aint disp; int rank; void *lptr; } Rptr; typedef struct { Rptr next; char key[MAX_KEY_SIZE], value[MAX_VALUE_SIZE]; } ListElm; Rptr nullDptr = { 0, -1, 0 }; int testCases = -1; #define BYTE_ONLY 0x1 #define TWO_STRUCT 0x2 int isOneLevel = 0; int main(int argc, char **argv) { int errors = 0; Rptr headDptr; ListElm *headLptr = 0; int i, wrank; MPI_Datatype dptrType, listelmType; MPI_Win listwin; MTest_Init(&argc, &argv); MPI_Comm_rank(MPI_COMM_WORLD, &wrank); for (i = 1; i < argc; i++) { if (strcmp(argv[i], "-byteonly") == 0) { testCases = BYTE_ONLY; } else if (strcmp(argv[i], "-twostruct") == 0) { testCases = TWO_STRUCT; } else if (strcmp(argv[i], "-onelevel") == 0) { isOneLevel = 1; } else { printf("Unrecognized argument %s\n", argv[i]); } } /* Create the datatypes that we will use to move the data */ { int blens[3]; MPI_Aint displ[3]; MPI_Datatype dtypes[3]; ListElm sampleElm; blens[0] = 1; blens[1] = 1; MPI_Get_address(&nullDptr.disp, &displ[0]); MPI_Get_address(&nullDptr.rank, &displ[1]); displ[1] = displ[1] - displ[0]; displ[0] = 0; dtypes[0] = MPI_AINT; dtypes[1] = MPI_INT; MPI_Type_create_struct(2, blens, displ, dtypes, &dptrType); MPI_Type_commit(&dptrType); if (isOneLevel) { blens[0] = sizeof(nullDptr); dtypes[0] = MPI_BYTE; } else { blens[0] = 1; dtypes[0] = dptrType; } blens[1] = MAX_KEY_SIZE; dtypes[1] = MPI_CHAR; blens[2] = MAX_VALUE_SIZE; dtypes[2] = MPI_CHAR; MPI_Get_address(&sampleElm.next, &displ[0]); MPI_Get_address(&sampleElm.key[0], &displ[1]); MPI_Get_address(&sampleElm.value[0], &displ[2]); displ[2] -= displ[0]; displ[1] -= displ[0]; displ[0] = 0; for (i = 0; i < 3; i++) { MTestPrintfMsg(0, "%d:count=%d,disp=%ld\n", i, blens[i], displ[i]); } MPI_Type_create_struct(3, blens, displ, dtypes, &listelmType); MPI_Type_commit(&listelmType); } MPI_Win_create_dynamic(MPI_INFO_NULL, MPI_COMM_WORLD, &listwin); headDptr.rank = 0; if (wrank == 0) { /* Create 1 list element (the head) and initialize it */ MPI_Alloc_mem(sizeof(ListElm), MPI_INFO_NULL, &headLptr); MPI_Get_address(headLptr, &headDptr.disp); headLptr->next.rank = -1; headLptr->next.disp = (MPI_Aint) MPI_BOTTOM; headLptr->next.lptr = 0; strncpy(headLptr->key, "key1", MAX_KEY_SIZE); strncpy(headLptr->value, "value1", MAX_VALUE_SIZE); MPI_Win_attach(listwin, headLptr, sizeof(ListElm)); } MPI_Bcast(&headDptr.disp, 1, MPI_AINT, 0, MPI_COMM_WORLD); MPI_Barrier(MPI_COMM_WORLD); if (wrank == 1) { ListElm headcopy; MPI_Win_lock_all(0, listwin); /* Get head element with simple get of BYTES */ if (testCases & BYTE_ONLY) { headcopy.next.rank = 100; headcopy.next.disp = 0xefefefef; MPI_Get(&headcopy, sizeof(ListElm), MPI_BYTE, headDptr.rank, headDptr.disp, sizeof(ListElm), MPI_BYTE, listwin); MPI_Win_flush(headDptr.rank, listwin); if (headcopy.next.rank != -1 && headcopy.next.disp != (MPI_Aint) MPI_BOTTOM) { errors++; printf("MPI_BYTE: headcopy contains incorrect next:<%d,%ld>\n", headcopy.next.rank, (long) headcopy.next.disp); } } if (testCases & TWO_STRUCT) { headcopy.next.rank = 100; headcopy.next.disp = 0xefefefef; /* Get head element using struct of struct type. This is * not an identical get to the simple BYTE one above but should * work */ MPI_Get(&headcopy, 1, listelmType, headDptr.rank, headDptr.disp, 1, listelmType, listwin); MPI_Win_flush(headDptr.rank, listwin); if (headcopy.next.rank != -1 && headcopy.next.disp != (MPI_Aint) MPI_BOTTOM) { errors++; printf("ListelmType: headcopy contains incorrect next:<%d,%ld>\n", headcopy.next.rank, (long) headcopy.next.disp); } } MPI_Win_unlock_all(listwin); } MPI_Barrier(MPI_COMM_WORLD); if (wrank == 0) { MPI_Win_detach(listwin, headLptr); MPI_Free_mem(headLptr); } MPI_Win_free(&listwin); MPI_Type_free(&dptrType); MPI_Type_free(&listelmType); MTest_Finalize(errors); MPI_Finalize(); return MTestReturnValue(errors); }