summaryrefslogtreecommitdiffstats
path: root/Tests/Cuda/Complex
diff options
context:
space:
mode:
authorBrad King <brad.king@kitware.com>2017-02-14 15:16:32 (GMT)
committerBrad King <brad.king@kitware.com>2017-02-14 15:21:48 (GMT)
commit33a65941fa5d7c12d79f9a4e002fed418ba6adc7 (patch)
treed3b7927977111ac2d90f233d4f8623feafefe7d9 /Tests/Cuda/Complex
parentfa5188d0edf081396ca0134d07cd8706549ddede (diff)
downloadCMake-33a65941fa5d7c12d79f9a4e002fed418ba6adc7.zip
CMake-33a65941fa5d7c12d79f9a4e002fed418ba6adc7.tar.gz
CMake-33a65941fa5d7c12d79f9a4e002fed418ba6adc7.tar.bz2
Tests: Run clang-format on CUDA code
Diffstat (limited to 'Tests/Cuda/Complex')
-rw-r--r--Tests/Cuda/Complex/dynamic.cu49
-rw-r--r--Tests/Cuda/Complex/file1.cu2
-rw-r--r--Tests/Cuda/Complex/file2.cu14
-rw-r--r--Tests/Cuda/Complex/file3.cu30
-rw-r--r--Tests/Cuda/Complex/mixed.cu30
5 files changed, 49 insertions, 76 deletions
diff --git a/Tests/Cuda/Complex/dynamic.cu b/Tests/Cuda/Complex/dynamic.cu
index 2b04ac9..f677868 100644
--- a/Tests/Cuda/Complex/dynamic.cu
+++ b/Tests/Cuda/Complex/dynamic.cu
@@ -1,7 +1,7 @@
-#include <string>
#include <cuda.h>
#include <iostream>
+#include <string>
#ifdef _WIN32
#define EXPORT __declspec(dllexport)
@@ -16,9 +16,7 @@ EXPORT int __host__ cuda_dynamic_host_func(int x)
return dynamic_base_func(x);
}
-static
-__global__
-void DetermineIfValidCudaDevice()
+static __global__ void DetermineIfValidCudaDevice()
{
}
@@ -26,35 +24,28 @@ EXPORT int choose_cuda_device()
{
int nDevices = 0;
cudaError_t err = cudaGetDeviceCount(&nDevices);
- if (err != cudaSuccess)
- {
+ 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)
- {
+ }
+ for (int i = 0; i < nDevices; ++i) {
cudaDeviceProp prop;
cudaError_t err = cudaGetDeviceProperties(&prop, i);
- if (err != cudaSuccess)
- {
+ 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;
- }
+ }
+ 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;
@@ -64,17 +55,15 @@ EXPORT int choose_cuda_device()
EXPORT void cuda_dynamic_lib_func()
{
- DetermineIfValidCudaDevice <<<1,1>>> ();
+ DetermineIfValidCudaDevice<<<1, 1>>>();
cudaError_t err = cudaGetLastError();
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "DetermineIfValidCudaDevice [SYNC] failed: "
<< cudaGetErrorString(err) << std::endl;
- }
+ }
err = cudaDeviceSynchronize();
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "DetermineIfValidCudaDevice [ASYNC] failed: "
<< cudaGetErrorString(cudaGetLastError()) << std::endl;
- }
+ }
}
diff --git a/Tests/Cuda/Complex/file1.cu b/Tests/Cuda/Complex/file1.cu
index a2e8bf3..1ce63bf 100644
--- a/Tests/Cuda/Complex/file1.cu
+++ b/Tests/Cuda/Complex/file1.cu
@@ -5,6 +5,6 @@ result_type __device__ file1_func(int x)
{
result_type r;
r.input = x;
- r.sum = x*x;
+ r.sum = x * x;
return r;
}
diff --git a/Tests/Cuda/Complex/file2.cu b/Tests/Cuda/Complex/file2.cu
index 6b8b06b..74f3558 100644
--- a/Tests/Cuda/Complex/file2.cu
+++ b/Tests/Cuda/Complex/file2.cu
@@ -5,16 +5,12 @@ result_type __device__ file1_func(int x);
result_type_dynamic __device__ file2_func(int x)
{
- if(x!=42)
- {
+ if (x != 42) {
const result_type r = file1_func(x);
- const result_type_dynamic rd { r.input, r.sum, true };
+ const result_type_dynamic rd{ r.input, r.sum, true };
return rd;
- }
- else
- {
- const result_type_dynamic rd { x, x*x*x, false };
+ } else {
+ const result_type_dynamic rd{ x, x * x * x, false };
return rd;
- }
-
+ }
}
diff --git a/Tests/Cuda/Complex/file3.cu b/Tests/Cuda/Complex/file3.cu
index bd8198d..d055b42 100644
--- a/Tests/Cuda/Complex/file3.cu
+++ b/Tests/Cuda/Complex/file3.cu
@@ -7,9 +7,7 @@
result_type __device__ file1_func(int x);
result_type_dynamic __device__ file2_func(int x);
-static
-__global__
-void file3_kernel(result_type* r, int x)
+static __global__ void file3_kernel(result_type* r, int x)
{
*r = file1_func(x);
result_type_dynamic rd = file2_func(x);
@@ -19,36 +17,32 @@ int file3_launch_kernel(int x)
{
result_type* r;
cudaError_t err = cudaMallocManaged(&r, sizeof(result_type));
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "file3_launch_kernel: cudaMallocManaged failed: "
<< cudaGetErrorString(err) << std::endl;
return x;
- }
+ }
- file3_kernel <<<1,1>>> (r,x);
+ file3_kernel<<<1, 1>>>(r, x);
err = cudaGetLastError();
- if(err != cudaSuccess)
- {
- std::cerr << "file3_kernel [SYNC] failed: "
- << cudaGetErrorString(err) << std::endl;
+ if (err != cudaSuccess) {
+ std::cerr << "file3_kernel [SYNC] failed: " << cudaGetErrorString(err)
+ << std::endl;
return x;
- }
+ }
err = cudaDeviceSynchronize();
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "file3_kernel [ASYNC] failed: "
<< cudaGetErrorString(cudaGetLastError()) << std::endl;
return x;
- }
+ }
int result = r->sum;
err = cudaFree(r);
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "file3_launch_kernel: cudaFree failed: "
<< cudaGetErrorString(err) << std::endl;
return x;
- }
+ }
return result;
}
diff --git a/Tests/Cuda/Complex/mixed.cu b/Tests/Cuda/Complex/mixed.cu
index d96cc7c..a81ccb7 100644
--- a/Tests/Cuda/Complex/mixed.cu
+++ b/Tests/Cuda/Complex/mixed.cu
@@ -17,9 +17,7 @@ result_type_dynamic __device__ file2_func(int x);
IMPORT void __host__ cuda_dynamic_lib_func();
-static
-__global__
-void mixed_kernel(result_type* r, int x)
+static __global__ void mixed_kernel(result_type* r, int x)
{
*r = file1_func(x);
result_type_dynamic rd = file2_func(x);
@@ -31,37 +29,33 @@ EXPORT int mixed_launch_kernel(int x)
result_type* r;
cudaError_t err = cudaMallocManaged(&r, sizeof(result_type));
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "mixed_launch_kernel: cudaMallocManaged failed: "
<< cudaGetErrorString(err) << std::endl;
return x;
- }
+ }
- mixed_kernel <<<1,1>>> (r,x);
+ mixed_kernel<<<1, 1>>>(r, x);
err = cudaGetLastError();
- if(err != cudaSuccess)
- {
- std::cerr << "mixed_kernel [SYNC] failed: "
- << cudaGetErrorString(err) << std::endl;
+ if (err != cudaSuccess) {
+ std::cerr << "mixed_kernel [SYNC] failed: " << cudaGetErrorString(err)
+ << std::endl;
return x;
- }
+ }
err = cudaDeviceSynchronize();
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "mixed_kernel [ASYNC] failed: "
<< cudaGetErrorString(cudaGetLastError()) << std::endl;
return x;
- }
+ }
int result = r->sum;
err = cudaFree(r);
- if(err != cudaSuccess)
- {
+ if (err != cudaSuccess) {
std::cerr << "mixed_launch_kernel: cudaFree failed: "
<< cudaGetErrorString(err) << std::endl;
return x;
- }
+ }
return result;
}