mirror of
https://github.com/paboyle/Grid.git
synced 2025-04-09 21:50:45 +01:00
208 lines
7.3 KiB
C++
208 lines
7.3 KiB
C++
#include <Grid/GridCore.h>
|
|
|
|
NAMESPACE_BEGIN(Grid);
|
|
uint32_t accelerator_threads=8;
|
|
uint32_t acceleratorThreads(void) {return accelerator_threads;};
|
|
void acceleratorThreads(uint32_t t) {accelerator_threads = t;};
|
|
|
|
#ifdef GRID_CUDA
|
|
cudaDeviceProp *gpu_props;
|
|
void acceleratorInit(void)
|
|
{
|
|
int nDevices = 1;
|
|
cudaGetDeviceCount(&nDevices);
|
|
gpu_props = new cudaDeviceProp[nDevices];
|
|
|
|
char * localRankStr = NULL;
|
|
int rank = 0, world_rank=0;
|
|
#define ENV_LOCAL_RANK_OMPI "OMPI_COMM_WORLD_LOCAL_RANK"
|
|
#define ENV_LOCAL_RANK_MVAPICH "MV2_COMM_WORLD_LOCAL_RANK"
|
|
#define ENV_RANK_OMPI "OMPI_COMM_WORLD_RANK"
|
|
#define ENV_RANK_MVAPICH "MV2_COMM_WORLD_RANK"
|
|
// We extract the local rank initialization using an environment variable
|
|
if ((localRankStr = getenv(ENV_LOCAL_RANK_OMPI)) != NULL)
|
|
{
|
|
rank = atoi(localRankStr);
|
|
}
|
|
if ((localRankStr = getenv(ENV_LOCAL_RANK_MVAPICH)) != NULL)
|
|
{
|
|
rank = atoi(localRankStr);
|
|
}
|
|
if ((localRankStr = getenv(ENV_RANK_OMPI )) != NULL) { world_rank = atoi(localRankStr);}
|
|
if ((localRankStr = getenv(ENV_RANK_MVAPICH)) != NULL) { world_rank = atoi(localRankStr);}
|
|
|
|
size_t totalDeviceMem=0;
|
|
for (int i = 0; i < nDevices; i++) {
|
|
|
|
#define GPU_PROP_FMT(canMapHostMemory,FMT) printf("AcceleratorCudaInit: " #canMapHostMemory ": " FMT" \n",prop.canMapHostMemory);
|
|
#define GPU_PROP(canMapHostMemory) GPU_PROP_FMT(canMapHostMemory,"%d");
|
|
cudaGetDeviceProperties(&gpu_props[i], i);
|
|
if ( world_rank == 0) {
|
|
cudaDeviceProp prop;
|
|
prop = gpu_props[i];
|
|
printf("AcceleratorCudaInit: ========================\n");
|
|
printf("AcceleratorCudaInit: Device Number : %d\n", i);
|
|
printf("AcceleratorCudaInit: ========================\n");
|
|
printf("AcceleratorCudaInit: Device identifier: %s\n", prop.name);
|
|
|
|
GPU_PROP_FMT(totalGlobalMem,"%lld");
|
|
GPU_PROP(managedMemory);
|
|
GPU_PROP(isMultiGpuBoard);
|
|
GPU_PROP(warpSize);
|
|
totalDeviceMem = prop.totalGlobalMem;
|
|
// GPU_PROP(unifiedAddressing);
|
|
// GPU_PROP(l2CacheSize);
|
|
// GPU_PROP(singleToDoublePrecisionPerfRatio);
|
|
}
|
|
}
|
|
MemoryManager::DeviceMaxBytes = (8*totalDeviceMem)/10; // Assume 80% ours
|
|
#undef GPU_PROP_FMT
|
|
#undef GPU_PROP
|
|
|
|
#ifdef GRID_IBM_SUMMIT
|
|
// IBM Jsrun makes cuda Device numbering screwy and not match rank
|
|
if ( world_rank == 0 ) printf("AcceleratorCudaInit: IBM Summit or similar - NOT setting device to node rank\n");
|
|
#else
|
|
if ( world_rank == 0 ) printf("AcceleratorCudaInit: setting device to node rank\n");
|
|
cudaSetDevice(rank);
|
|
#endif
|
|
if ( world_rank == 0 ) printf("AcceleratorCudaInit: ================================================\n");
|
|
}
|
|
#endif
|
|
|
|
#ifdef GRID_HIP
|
|
hipDeviceProp_t *gpu_props;
|
|
void acceleratorInit(void)
|
|
{
|
|
int nDevices = 1;
|
|
hipGetDeviceCount(&nDevices);
|
|
gpu_props = new hipDeviceProp_t[nDevices];
|
|
|
|
char * localRankStr = NULL;
|
|
int rank = 0, world_rank=0;
|
|
#define ENV_LOCAL_RANK_OMPI "OMPI_COMM_WORLD_LOCAL_RANK"
|
|
#define ENV_LOCAL_RANK_MVAPICH "MV2_COMM_WORLD_LOCAL_RANK"
|
|
#define ENV_RANK_OMPI "OMPI_COMM_WORLD_RANK"
|
|
#define ENV_RANK_MVAPICH "MV2_COMM_WORLD_RANK"
|
|
// We extract the local rank initialization using an environment variable
|
|
if ((localRankStr = getenv(ENV_LOCAL_RANK_OMPI)) != NULL)
|
|
{
|
|
rank = atoi(localRankStr);
|
|
}
|
|
if ((localRankStr = getenv(ENV_LOCAL_RANK_MVAPICH)) != NULL)
|
|
{
|
|
rank = atoi(localRankStr);
|
|
}
|
|
if ((localRankStr = getenv(ENV_RANK_OMPI )) != NULL) { world_rank = atoi(localRankStr);}
|
|
if ((localRankStr = getenv(ENV_RANK_MVAPICH)) != NULL) { world_rank = atoi(localRankStr);}
|
|
|
|
for (int i = 0; i < nDevices; i++) {
|
|
|
|
#define GPU_PROP_FMT(canMapHostMemory,FMT) printf("AcceleratorHipInit: " #canMapHostMemory ": " FMT" \n",prop.canMapHostMemory);
|
|
#define GPU_PROP(canMapHostMemory) GPU_PROP_FMT(canMapHostMemory,"%d");
|
|
|
|
hipGetDeviceProperties(&gpu_props[i], i);
|
|
if ( world_rank == 0) {
|
|
hipDeviceProp_t prop;
|
|
prop = gpu_props[i];
|
|
printf("AcceleratorHipInit: ========================\n");
|
|
printf("AcceleratorHipInit: Device Number : %d\n", i);
|
|
printf("AcceleratorHipInit: ========================\n");
|
|
printf("AcceleratorHipInit: Device identifier: %s\n", prop.name);
|
|
|
|
// GPU_PROP(managedMemory);
|
|
GPU_PROP(isMultiGpuBoard);
|
|
GPU_PROP(warpSize);
|
|
// GPU_PROP(unifiedAddressing);
|
|
// GPU_PROP(l2CacheSize);
|
|
// GPU_PROP(singleToDoublePrecisionPerfRatio);
|
|
}
|
|
}
|
|
#undef GPU_PROP_FMT
|
|
#undef GPU_PROP
|
|
#ifdef GRID_IBM_SUMMIT
|
|
// IBM Jsrun makes cuda Device numbering screwy and not match rank
|
|
if ( world_rank == 0 ) printf("AcceleratorHipInit: IBM Summit or similar - NOT setting device to node rank\n");
|
|
#else
|
|
if ( world_rank == 0 ) printf("AcceleratorHipInit: setting device to node rank\n");
|
|
hipSetDevice(rank);
|
|
#endif
|
|
if ( world_rank == 0 ) printf("AcceleratorHipInit: ================================================\n");
|
|
}
|
|
#endif
|
|
|
|
|
|
#ifdef GRID_SYCL
|
|
|
|
cl::sycl::queue *theGridAccelerator;
|
|
|
|
void acceleratorInit(void)
|
|
{
|
|
int nDevices = 1;
|
|
cl::sycl::gpu_selector selector;
|
|
cl::sycl::device selectedDevice { selector };
|
|
theGridAccelerator = new sycl::queue (selectedDevice);
|
|
|
|
char * localRankStr = NULL;
|
|
int rank = 0, world_rank=0;
|
|
#define ENV_LOCAL_RANK_OMPI "OMPI_COMM_WORLD_LOCAL_RANK"
|
|
#define ENV_LOCAL_RANK_MVAPICH "MV2_COMM_WORLD_LOCAL_RANK"
|
|
#define ENV_RANK_OMPI "OMPI_COMM_WORLD_RANK"
|
|
#define ENV_RANK_MVAPICH "MV2_COMM_WORLD_RANK"
|
|
// We extract the local rank initialization using an environment variable
|
|
if ((localRankStr = getenv(ENV_LOCAL_RANK_OMPI)) != NULL)
|
|
{
|
|
rank = atoi(localRankStr);
|
|
}
|
|
if ((localRankStr = getenv(ENV_LOCAL_RANK_MVAPICH)) != NULL)
|
|
{
|
|
rank = atoi(localRankStr);
|
|
}
|
|
if ((localRankStr = getenv(ENV_RANK_OMPI )) != NULL) { world_rank = atoi(localRankStr);}
|
|
if ((localRankStr = getenv(ENV_RANK_MVAPICH)) != NULL) { world_rank = atoi(localRankStr);}
|
|
|
|
auto devices = cl::sycl::device::get_devices();
|
|
for(int d = 0;d<devices.size();d++){
|
|
|
|
#define GPU_PROP_STR(prop) \
|
|
printf("AcceleratorSyclInit: " #prop ": %s \n",devices[d].get_info<cl::sycl::info::device::prop>().c_str());
|
|
|
|
#define GPU_PROP_FMT(prop,FMT) \
|
|
printf("AcceleratorSyclInit: " #prop ": " FMT" \n",devices[d].get_info<cl::sycl::info::device::prop>());
|
|
|
|
#define GPU_PROP(prop) GPU_PROP_FMT(prop,"%ld");
|
|
|
|
GPU_PROP_STR(vendor);
|
|
GPU_PROP_STR(version);
|
|
// GPU_PROP_STR(device_type);
|
|
/*
|
|
GPU_PROP(max_compute_units);
|
|
GPU_PROP(native_vector_width_char);
|
|
GPU_PROP(native_vector_width_short);
|
|
GPU_PROP(native_vector_width_int);
|
|
GPU_PROP(native_vector_width_long);
|
|
GPU_PROP(native_vector_width_float);
|
|
GPU_PROP(native_vector_width_double);
|
|
GPU_PROP(native_vector_width_half);
|
|
GPU_PROP(address_bits);
|
|
GPU_PROP(half_fp_config);
|
|
GPU_PROP(single_fp_config);
|
|
*/
|
|
// GPU_PROP(double_fp_config);
|
|
GPU_PROP(global_mem_size);
|
|
|
|
}
|
|
if ( world_rank == 0 ) {
|
|
auto name = theGridAccelerator->get_device().get_info<sycl::info::device::name>();
|
|
printf("AcceleratorSyclInit: Selected device is %s\n",name.c_str());
|
|
printf("AcceleratorSyclInit: ================================================\n");
|
|
}
|
|
}
|
|
#endif
|
|
|
|
#if (!defined(GRID_CUDA)) && (!defined(GRID_SYCL))&& (!defined(GRID_HIP))
|
|
void acceleratorInit(void){}
|
|
#endif
|
|
|
|
NAMESPACE_END(Grid);
|