-/* -*- mode: c; tab-width: 4; indent-tabs-mode: nil; c-basic-offset: 4; c-file-style: "stroustrup"; -*-
+/*
+ * This file is part of the GROMACS molecular simulation package.
*
+ * Copyright (c) 2012,2014, by the GROMACS development team, led by
+ * Mark Abraham, David van der Spoel, Berk Hess, and Erik Lindahl,
+ * and including many others, as listed in the AUTHORS file in the
+ * top-level source directory and at http://www.gromacs.org.
*
- * This source code is part of
- *
- * G R O M A C S
- *
- * GROningen MAchine for Chemical Simulations
- *
- * Written by David van der Spoel, Erik Lindahl, Berk Hess, and others.
- * Copyright (c) 1991-2000, University of Groningen, The Netherlands.
- * Copyright (c) 2001-2012, The GROMACS development team,
- * check out http://www.gromacs.org for more information.
- *
- * This program is free software; you can redistribute it and/or
- * modify it under the terms of the GNU General Public License
- * as published by the Free Software Foundation; either version 2
+ * GROMACS is free software; you can redistribute it and/or
+ * modify it under the terms of the GNU Lesser General Public License
+ * as published by the Free Software Foundation; either version 2.1
* of the License, or (at your option) any later version.
*
- * If you want to redistribute modifications, please consider that
- * scientific software is very special. Version control is crucial -
- * bugs must be traceable. We will be happy to consider code for
- * inclusion in the official distribution, but derived work must not
- * be called official GROMACS. Details are found in the README & COPYING
- * files - if they are missing, get the official version at www.gromacs.org.
+ * GROMACS is distributed in the hope that it will be useful,
+ * but WITHOUT ANY WARRANTY; without even the implied warranty of
+ * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the GNU
+ * Lesser General Public License for more details.
*
- * To help us fund GROMACS development, we humbly ask that you cite
- * the papers on the package - you can find them in the top README file.
+ * You should have received a copy of the GNU Lesser General Public
+ * License along with GROMACS; if not, see
+ * http://www.gnu.org/licenses, or write to the Free Software Foundation,
+ * Inc., 51 Franklin Street, Fifth Floor, Boston, MA 02110-1301 USA.
*
- * For more info, check our website at http://www.gromacs.org
+ * If you want to redistribute modifications to GROMACS, please
+ * consider that scientific software is very special. Version
+ * control is crucial - bugs must be traceable. We will be happy to
+ * consider code for inclusion in the official distribution, but
+ * derived work must not be called official GROMACS. Details are found
+ * in the README & COPYING files - if they are missing, get the
+ * official version at http://www.gromacs.org.
*
- * And Hey:
- * Gallium Rubidium Oxygen Manganese Argon Carbon Silicon
+ * To help us fund GROMACS development, we humbly ask that you cite
+ * the research papers on the package. Check out http://www.gromacs.org.
*/
-#include <stdlib.h>
+#include "gmxpre.h"
+
+#include "gromacs/legacyheaders/pmalloc_cuda.h"
-#include "gmx_fatal.h"
+#include <stdlib.h>
-#include "cudautils.cuh"
-#include "pmalloc_cuda.h"
+#include "gromacs/gmxlib/cuda_tools/cudautils.cuh"
+#include "gromacs/utility/cstringutil.h"
-/*! Allocates nbytes of page-locked memory.
- * This memory should always be freed using pfree (or with the page-locked
+/*! Allocates nbytes of page-locked memory.
+ * This memory should always be freed using pfree (or with the page-locked
* free functions provied by the CUDA library).
*/
void pmalloc(void **h_ptr, size_t nbytes)
CU_CHECK_PREV_ERR();
- stat = cudaMallocHost(h_ptr, nbytes, flag);
+ stat = cudaMallocHost(h_ptr, nbytes, flag);
sprintf(strbuf, "cudaMallocHost of size %d bytes failed", (int)nbytes);
- CU_RET_ERR(stat, strbuf);
+ CU_RET_ERR(stat, strbuf);
}
-/*! Allocates nbytes of page-locked memory with write-combining.
- * This memory should always be freed using pfree (or with the page-locked
+/*! Allocates nbytes of page-locked memory with write-combining.
+ * This memory should always be freed using pfree (or with the page-locked
* free functions provied by the CUDA library).
*/
void pmalloc_wc(void **h_ptr, size_t nbytes)
CU_CHECK_PREV_ERR();
- stat = cudaMallocHost(h_ptr, nbytes, flag);
+ stat = cudaMallocHost(h_ptr, nbytes, flag);
sprintf(strbuf, "cudaMallocHost of size %d bytes failed", (int)nbytes);
- CU_RET_ERR(stat, strbuf);
+ CU_RET_ERR(stat, strbuf);
}
/*! Frees page locked memory allocated with pmalloc.
- * This function can safely be called also with a pointer to a page-locked
+ * This function can safely be called also with a pointer to a page-locked
* memory allocated directly with CUDA API calls.
*/
-void pfree(void *h_ptr)
+void pfree(void *h_ptr)
{
- cudaError_t stat;
+ cudaError_t stat;
if (h_ptr == NULL)
- {
+ {
return;
}
biod.pnpi.spb.ru / alexxy / gromacs.git / blobdiff