summaryrefslogtreecommitdiffstats
path: root/Tests/Cuda/Complex/dynamic.cu
diff options
context:
space:
mode:
authorPierre Moreau <dev@pmoreau.org>2017-02-08 21:50:58 (GMT)
committerBrad King <brad.king@kitware.com>2017-02-10 18:47:05 (GMT)
commit166b3393875e4f6752907b9b06c2518dce0432e9 (patch)
tree9a1484f0b5c34c34decbc8dc4ae6796a4a43f911 /Tests/Cuda/Complex/dynamic.cu
parentcbe4d5957b526f9a9bb6954d0c6944ad7642bb90 (diff)
downloadCMake-166b3393875e4f6752907b9b06c2518dce0432e9.zip
CMake-166b3393875e4f6752907b9b06c2518dce0432e9.tar.gz
CMake-166b3393875e4f6752907b9b06c2518dce0432e9.tar.bz2
Tests/Cuda: Select a CUDA device supporting compute 3.0
Diffstat (limited to 'Tests/Cuda/Complex/dynamic.cu')
-rw-r--r--Tests/Cuda/Complex/dynamic.cu40
1 files changed, 40 insertions, 0 deletions
diff --git a/Tests/Cuda/Complex/dynamic.cu b/Tests/Cuda/Complex/dynamic.cu
index 0206bb4..2b04ac9 100644
--- a/Tests/Cuda/Complex/dynamic.cu
+++ b/Tests/Cuda/Complex/dynamic.cu
@@ -22,6 +22,46 @@ void DetermineIfValidCudaDevice()
{
}
+EXPORT int choose_cuda_device()
+{
+ int nDevices = 0;
+ cudaError_t err = cudaGetDeviceCount(&nDevices);
+ if (err != cudaSuccess)
+ {
+ std::cerr << "Failed to retrieve the number of CUDA enabled devices"
+ << std::endl;
+ return 1;
+ }
+ for (int i = 0; i < nDevices; ++i)
+ {
+ cudaDeviceProp prop;
+ cudaError_t err = cudaGetDeviceProperties(&prop, i);
+ if (err != cudaSuccess)
+ {
+ std::cerr << "Could not retrieve properties from CUDA device " << i
+ << std::endl;
+ return 1;
+ }
+ if (prop.major >= 4)
+ {
+ err = cudaSetDevice(i);
+ if (err != cudaSuccess)
+ {
+ std::cout << "Could not select CUDA device " << i << std::endl;
+ }
+ else
+ {
+ return 0;
+ }
+ }
+ }
+
+ std::cout << "Could not find a CUDA enabled card supporting compute >=3.0"
+ << std::endl;
+
+ return 1;
+}
+
EXPORT void cuda_dynamic_lib_func()
{
DetermineIfValidCudaDevice <<<1,1>>> ();