From 419efdb66a85933d40d9b7858abc5764f5e667cb Mon Sep 17 00:00:00 2001 From: Ed Hartnett Date: Mon, 8 Jan 2018 18:26:18 -0700 Subject: [PATCH] removed varm functions --- src/clib/CMakeLists.txt | 2 +- src/clib/pio.h | 62 -- src/clib/pio_varm.c | 1849 --------------------------------------- 3 files changed, 1 insertion(+), 1912 deletions(-) delete mode 100644 src/clib/pio_varm.c diff --git a/src/clib/CMakeLists.txt b/src/clib/CMakeLists.txt index 1a0d7e17773..53ef0daa37e 100644 --- a/src/clib/CMakeLists.txt +++ b/src/clib/CMakeLists.txt @@ -8,7 +8,7 @@ project (PIOC C) add_library (pioc topology.c pio_file.c pioc_support.c pio_lists.c pioc.c pioc_sc.c pio_spmd.c pio_rearrange.c pio_nc4.c bget.c - pio_nc.c pio_put_nc.c pio_get_nc.c pio_getput_int.c pio_msg.c pio_varm.c + pio_nc.c pio_put_nc.c pio_get_nc.c pio_getput_int.c pio_msg.c pio_darray.c pio_darray_int.c) # set up include-directories diff --git a/src/clib/pio.h b/src/clib/pio.h index 02a51a56de5..f3878e75225 100644 --- a/src/clib/pio.h +++ b/src/clib/pio.h @@ -1140,68 +1140,6 @@ extern "C" { const PIO_Offset *count, const PIO_Offset *stride, const unsigned long long *op); - /* Varm functions are deprecated and should be used with extreme - * caution or not at all. Varm functions are not supported in - * async mode. */ - int PIOc_put_varm(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, const void *buf, - PIO_Offset bufcount, MPI_Datatype buftype); - int PIOc_get_varm_schar(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, signed char *buf); - int PIOc_put_varm_uchar(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, - const unsigned char *op); - int PIOc_put_varm_short(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, const short *op); - int PIOc_get_varm_short(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, short *buf); - int PIOc_get_varm_ulonglong(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, unsigned long long *buf); - int PIOc_get_varm_ushort(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, unsigned short *buf); - int PIOc_get_varm_longlong(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, long long *buf); - int PIOc_put_varm_text(int ncid, int varid, const PIO_Offset *start, - const PIO_Offset *count, const PIO_Offset *stride, - const PIO_Offset *imap, const char *op); - int PIOc_put_varm_ushort(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, const unsigned short *op); - int PIOc_put_varm_ulonglong(int ncid, int varid, const PIO_Offset *start, - const PIO_Offset *count, const PIO_Offset *stride, - const PIO_Offset *imap, const unsigned long long *op); - int PIOc_put_varm_int(int ncid, int varid, const PIO_Offset *start, - const PIO_Offset *count, const PIO_Offset *stride, - const PIO_Offset *imap, const int *op); - int PIOc_put_varm_float(int ncid, int varid, const PIO_Offset *start, - const PIO_Offset *count, const PIO_Offset *stride, - const PIO_Offset *imap, const float *op); - int PIOc_put_varm_long(int ncid, int varid, const PIO_Offset *start, - const PIO_Offset *count, const PIO_Offset *stride, - const PIO_Offset *imap, const long *op); - int PIOc_put_varm_uint(int ncid, int varid, const PIO_Offset *start, - const PIO_Offset *count, const PIO_Offset *stride, - const PIO_Offset *imap, const unsigned int *op); - int PIOc_put_varm_double(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, const double *op); - int PIOc_put_varm_schar(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, const signed char *op); - int PIOc_put_varm_longlong(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, const long long *op); - int PIOc_get_varm_double(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, double *buf); - int PIOc_get_varm_text(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, char *buf); - int PIOc_get_varm_int(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, int *buf); - int PIOc_get_varm_uint(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, unsigned int *buf); - int PIOc_get_varm(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, void *buf, - PIO_Offset bufcount, MPI_Datatype buftype); - int PIOc_get_varm_float(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, float *buf); - int PIOc_get_varm_long(int ncid, int varid, const PIO_Offset *start, const PIO_Offset *count, - const PIO_Offset *stride, const PIO_Offset *imap, long *buf); #if defined(__cplusplus) } #endif diff --git a/src/clib/pio_varm.c b/src/clib/pio_varm.c deleted file mode 100644 index 6554fb463f3..00000000000 --- a/src/clib/pio_varm.c +++ /dev/null @@ -1,1849 +0,0 @@ -#include -#include -#include - -/// -/// PIO interface to nc_put_varm -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const void *buf, PIO_Offset bufcount, MPI_Datatype buftype) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm(file->fh, varid, start, count, stride, imap, buf, bufcount, buftype, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_uchar -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_uchar (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const unsigned char *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_uchar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_uchar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_uchar(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_short -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_short (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const short *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_short(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_short(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_short(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} -/// -/// PIO interface to nc_put_varm_text -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_text (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const char *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_text(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_text(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_text(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_ushort -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_ushort (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const unsigned short *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_ushort(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_ushort(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_ushort(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_ulonglong -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_ulonglong (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const unsigned long long *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_ulonglong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_ulonglong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_ulonglong(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} -/// -/// PIO interface to nc_put_varm_int -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_int (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const int *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_int(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_int(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_int(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_float -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_float (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const float *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_float(file->fh, varid,(size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_float(file->fh, varid,(size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_float(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} -/// -/// PIO interface to nc_put_varm_long -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_long (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const long *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_long(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_long(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_long(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_uint -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_uint (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const unsigned int *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_uint(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_uint(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_uint(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_double -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_double (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const double *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_double(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_double(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_double(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} -/// -/// PIO interface to nc_put_varm_schar -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_schar (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const signed char *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_schar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_schar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_schar(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -/// -/// PIO interface to nc_put_varm_longlong -/// -/// This routine is called collectively by all tasks in the communicator ios.union_comm. -/// -/// Refer to the netcdf documentation. -/// -int PIOc_put_varm_longlong (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], const long long *op) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; -#ifdef _PNETCDF - var_desc_t *vdesc; - int *request; -#endif /* _PNETCDF */ - - ierr = PIO_NOERR; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_var_par_access(file->fh, varid, NC_COLLECTIVE); - ierr = nc_put_varm_longlong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - if (ios->io_rank==0){ - ierr = nc_put_varm_longlong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, op);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: - if ((ierr = get_var_desc(varid, &file->varlist, &vdesc))) - return pio_err(ios, file, ierr, __FILE__, __LINE__); - - if (vdesc->nreqs%PIO_REQUEST_ALLOC_CHUNK == 0 ){ - vdesc->request = realloc(vdesc->request, - sizeof(int)*(vdesc->nreqs+PIO_REQUEST_ALLOC_CHUNK)); - } - request = vdesc->request+vdesc->nreqs; - - if (ios->io_rank==0){ - ierr = ncmpi_bput_varm_longlong(file->fh, varid, start, count, stride, imap, op, request);; - }else{ - *request = PIO_REQ_NULL; - } - vdesc->nreqs++; - flush_output_buffer(file, false, 0); - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - return ierr; -} - -int PIOc_get_varm_uchar (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], unsigned char *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_UNSIGNED_CHAR; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_uchar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_uchar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_uchar(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_uchar_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_schar (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], signed char *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_CHAR; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_schar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_schar(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_schar(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_schar_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_double (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], double *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_DOUBLE; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_double(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_double(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_double(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_double_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_text (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], char *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_CHAR; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_text(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_text(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_text(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_text_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_int (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], int *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_INT; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_int(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_int(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_int(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_int_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_uint (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], unsigned int *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_UNSIGNED; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_uint(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_uint(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_uint(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_uint_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], void *buf, PIO_Offset bufcount, MPI_Datatype buftype) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibufcnt = bufcount; - ibuftype = buftype; - ierr = PIO_NOERR; - - /* Sorry, but varm functions are not supported by the async interface. */ - if (ios->async) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm(file->fh, varid, start, count, stride, imap, buf, bufcount, buftype);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_all(file->fh, varid, start, count, stride, imap, buf, bufcount, buftype);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_float (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], float *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_FLOAT; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_float(file->fh, varid,(size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_float(file->fh, varid,(size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_float(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_float_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_long (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], long *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_LONG; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_long(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_long(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_long(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_long_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_ushort (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], unsigned short *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_UNSIGNED_SHORT; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_ushort(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_ushort(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_ushort(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_ushort_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_longlong (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], long long *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_LONG_LONG; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_longlong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_longlong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_longlong(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_longlong_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_short (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], short *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_SHORT; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_short(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_short(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_short(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_short_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -} - -int PIOc_get_varm_ulonglong (int ncid, int varid, const PIO_Offset start[], const PIO_Offset count[], const PIO_Offset stride[], const PIO_Offset imap[], unsigned long long *buf) -{ - int ierr; - iosystem_desc_t *ios; - file_desc_t *file; - MPI_Datatype ibuftype; - int ndims; - int ibufcnt; - bool bcast = false; - - /* Get file info. */ - if ((ierr = pio_get_file(ncid, &file))) - return ierr; - ios = file->iosystem; - ibuftype = MPI_UNSIGNED_LONG_LONG; - ierr = PIOc_inq_varndims(ncid, varid, &ndims); - ibufcnt = 1; - for(int i=0;iasync) - return PIO_EINVAL; - - if (ios->ioproc){ - switch(file->iotype){ -#ifdef _NETCDF4 - case PIO_IOTYPE_NETCDF4P: - ierr = nc_get_varm_ulonglong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - break; - case PIO_IOTYPE_NETCDF4C: -#endif - case PIO_IOTYPE_NETCDF: - bcast = true; - if (ios->iomaster == MPI_ROOT){ - ierr = nc_get_varm_ulonglong(file->fh, varid, (size_t *) start, (size_t *) count, (ptrdiff_t *) stride, (ptrdiff_t *) imap, buf);; - } - break; -#ifdef _PNETCDF - case PIO_IOTYPE_PNETCDF: -#ifdef PNET_READ_AND_BCAST - ncmpi_begin_indep_data(file->fh); - if (ios->iomaster == MPI_ROOT){ - ierr = ncmpi_get_varm_ulonglong(file->fh, varid, start, count, stride, imap, buf);; - }; - ncmpi_end_indep_data(file->fh); - bcast=true; -#else - ierr = ncmpi_get_varm_ulonglong_all(file->fh, varid, start, count, stride, imap, buf);; -#endif - break; -#endif - default: - return pio_err(ios, file, PIO_EBADIOTYPE, __FILE__, __LINE__); - } - } - - ierr = check_netcdf(file, ierr, __FILE__,__LINE__); - - if (ios->async || bcast || - (ios->num_iotasks < ios->num_comptasks)){ - MPI_Bcast(buf, ibufcnt, ibuftype, ios->ioroot, ios->my_comm); - } - - return ierr; -}