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 <config.h>
-#include <pio.h>
-#include <pio_internal.h>
-
-///
-/// PIO interface to nc_put_varm
-///
-/// This routine is called collectively by all tasks in the communicator ios.union_comm.
-///
-/// Refer to the <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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 <A HREF="http://www.unidata.ucar.edu/software/netcdf/docs/netcdf_documentation.html"> netcdf documentation. </A>
-///
-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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;i<ndims;i++){
-        ibufcnt *= count[i]/stride[i];
-    }
-    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_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;
-}