Spaces:
Runtime error
Runtime error
File size: 2,689 Bytes
be11144 |
1 2 3 4 5 6 7 8 9 10 11 12 13 14 15 16 17 18 19 20 21 22 23 24 25 26 27 28 29 30 31 32 33 34 35 36 37 38 39 40 41 42 43 44 45 46 47 48 49 50 51 52 53 54 55 56 57 58 59 60 61 62 63 64 65 66 67 68 69 70 71 72 73 74 75 76 77 78 79 80 81 82 83 84 85 86 87 88 89 90 91 92 93 94 95 96 97 98 99 100 101 102 103 104 105 106 107 108 109 110 111 112 113 114 115 |
#include <unittest/unittest.h>
#include <thrust/tabulate.h>
#include <thrust/functional.h>
#include <thrust/execution_policy.h>
template<typename ExecutionPolicy, typename Iterator, typename Function>
__global__
void tabulate_kernel(ExecutionPolicy exec, Iterator first, Iterator last, Function f)
{
thrust::tabulate(exec, first, last, f);
}
template<typename ExecutionPolicy>
void TestTabulateDevice(ExecutionPolicy exec)
{
typedef thrust::device_vector<int> Vector;
using namespace thrust::placeholders;
typedef typename Vector::value_type T;
Vector v(5);
tabulate_kernel<<<1,1>>>(exec, v.begin(), v.end(), thrust::identity<T>());
{
cudaError_t const err = cudaDeviceSynchronize();
ASSERT_EQUAL(cudaSuccess, err);
}
ASSERT_EQUAL(v[0], 0);
ASSERT_EQUAL(v[1], 1);
ASSERT_EQUAL(v[2], 2);
ASSERT_EQUAL(v[3], 3);
ASSERT_EQUAL(v[4], 4);
tabulate_kernel<<<1,1>>>(exec, v.begin(), v.end(), -_1);
{
cudaError_t const err = cudaDeviceSynchronize();
ASSERT_EQUAL(cudaSuccess, err);
}
ASSERT_EQUAL(v[0], 0);
ASSERT_EQUAL(v[1], -1);
ASSERT_EQUAL(v[2], -2);
ASSERT_EQUAL(v[3], -3);
ASSERT_EQUAL(v[4], -4);
tabulate_kernel<<<1,1>>>(exec, v.begin(), v.end(), _1 * _1 * _1);
{
cudaError_t const err = cudaDeviceSynchronize();
ASSERT_EQUAL(cudaSuccess, err);
}
ASSERT_EQUAL(v[0], 0);
ASSERT_EQUAL(v[1], 1);
ASSERT_EQUAL(v[2], 8);
ASSERT_EQUAL(v[3], 27);
ASSERT_EQUAL(v[4], 64);
}
void TestTabulateDeviceSeq()
{
TestTabulateDevice(thrust::seq);
}
DECLARE_UNITTEST(TestTabulateDeviceSeq);
void TestTabulateDeviceDevice()
{
TestTabulateDevice(thrust::device);
}
DECLARE_UNITTEST(TestTabulateDeviceDevice);
void TestTabulateCudaStreams()
{
using namespace thrust::placeholders;
typedef thrust::device_vector<int> Vector;
typedef Vector::value_type T;
Vector v(5);
cudaStream_t s;
cudaStreamCreate(&s);
thrust::tabulate(thrust::cuda::par.on(s), v.begin(), v.end(), thrust::identity<T>());
cudaStreamSynchronize(s);
ASSERT_EQUAL(v[0], 0);
ASSERT_EQUAL(v[1], 1);
ASSERT_EQUAL(v[2], 2);
ASSERT_EQUAL(v[3], 3);
ASSERT_EQUAL(v[4], 4);
thrust::tabulate(thrust::cuda::par.on(s), v.begin(), v.end(), -_1);
cudaStreamSynchronize(s);
ASSERT_EQUAL(v[0], 0);
ASSERT_EQUAL(v[1], -1);
ASSERT_EQUAL(v[2], -2);
ASSERT_EQUAL(v[3], -3);
ASSERT_EQUAL(v[4], -4);
thrust::tabulate(thrust::cuda::par.on(s), v.begin(), v.end(), _1 * _1 * _1);
cudaStreamSynchronize(s);
ASSERT_EQUAL(v[0], 0);
ASSERT_EQUAL(v[1], 1);
ASSERT_EQUAL(v[2], 8);
ASSERT_EQUAL(v[3], 27);
ASSERT_EQUAL(v[4], 64);
cudaStreamSynchronize(s);
}
DECLARE_UNITTEST(TestTabulateCudaStreams);
|