refs #27: Add unit test stubs for CUDA

 * I've found alignment issues in complex/nested structs in CUDA;
   we need some thorough tests for them!

include/nba/engines/cuda/test.hh

@@ -0,0 +1,5 @@
+namespace nba {
+extern void* get_test_kernel_noop();
+}
+
+// vim: ts=8 sts=4 sw=4 et

include/nba/framework/datablock_shared.hh

@@ -8,7 +8,6 @@
 
 #include <cstdint>
 #include <nba/core/shiftedint.hh>
-#include <nba/framework/config.hh>
 
 struct datablock_batch_info {
     void *buffer_bases_in;

src/engines/cuda/test.cu

@@ -0,0 +1,16 @@
+#include <nba/engines/cuda/test.hh>
+
+using namespace std;
+using namespace nba;
+
+__global__ void noop()
+{
+    __syncthreads();
+}
+
+void *nba::get_test_kernel_noop()
+{
+    return reinterpret_cast<void *> (noop);
+}
+
+// vim: ts=8 sts=4 sw=4 et

tests/test_cuda.cc

@@ -0,0 +1,37 @@
+#include <cstdint>
+#include <cuda_runtime.h>
+#include <nba/core/shiftedint.hh>
+#include <nba/framework/datablock_shared.hh>
+#include <gtest/gtest.h>
+#include <nba/engines/cuda/test.hh>
+#if 0
+#require <engines/cuda/test.o>
+#endif
+
+using namespace std;
+using namespace nba;
+
+#ifdef USE_CUDA
+
+TEST(CUDADeviceTest, Initialization) {
+    EXPECT_EQ(cudaSuccess, cudaSetDevice(0));
+    EXPECT_EQ(cudaSuccess, cudaDeviceReset());
+}
+
+TEST(CUDADeviceTest, NoopKernel) {
+    EXPECT_EQ(cudaSuccess, cudaSetDevice(0));
+    void *k = get_test_kernel_noop();
+    EXPECT_EQ(cudaSuccess, cudaLaunchKernel(k, dim3(1), dim3(1), nullptr, 0, 0));
+    EXPECT_EQ(cudaSuccess, cudaDeviceSynchronize());
+    EXPECT_EQ(cudaSuccess, cudaDeviceReset());
+}
+
+#else
+
+TEST(CUDATest, Noop) {
+    EXPECT_TRUE(1);
+}
+
+#endif
+
+// vim: ts=8 sts=4 sw=4 et