|
9 | 9 |
|
10 | 10 | #include <gtest/gtest.h> |
11 | 11 |
|
12 | | -TEST(RangesRefUsage, RangesRefUsage) { |
13 | | - sycl::detail::ranges_ref_view r0; |
14 | | - ASSERT_EQ(r0.Dims, size_t{0}); |
15 | | - |
| 12 | +template <int dims> |
| 13 | +void TestNDRangesRefView(sycl::range<dims> global, sycl::range<dims> local, |
| 14 | + sycl::id<dims> offset) { |
16 | 15 | { |
17 | | - sycl::range<1> global_range{1024}; |
18 | | - sycl::range<1> local_range{64}; |
19 | | - sycl::id<1> offset{10}; |
20 | | - sycl::nd_range<1> nd_range{global_range, local_range, offset}; |
21 | | - |
22 | | - { |
23 | | - sycl::detail::ranges_ref_view r{nd_range}; |
24 | | - ASSERT_EQ(r.Dims, size_t{1}); |
25 | | - ASSERT_EQ(*r.GlobalSize, global_range[0]); |
26 | | - ASSERT_EQ(*r.LocalSize, local_range[0]); |
27 | | - ASSERT_EQ(*r.GlobalOffset, offset[0]); |
28 | | - } |
29 | | - { |
30 | | - sycl::detail::ranges_ref_view r{global_range, local_range}; |
31 | | - ASSERT_EQ(r.Dims, size_t{1}); |
32 | | - ASSERT_EQ(*r.GlobalSize, global_range[0]); |
33 | | - ASSERT_EQ(*r.LocalSize, local_range[0]); |
34 | | - } |
35 | | - { |
36 | | - sycl::detail::ranges_ref_view r{global_range}; |
37 | | - ASSERT_EQ(r.Dims, size_t{1}); |
38 | | - ASSERT_EQ(*r.GlobalSize, global_range[0]); |
39 | | - ASSERT_EQ(r.LocalSize, nullptr); |
| 16 | + sycl::nd_range<dims> nd_range{global, local, offset}; |
| 17 | + sycl::detail::ranges_ref_view r{nd_range}; |
| 18 | + ASSERT_EQ(r.Dims, size_t{dims}); |
| 19 | + for (int d = 0; d < dims; d++) { |
| 20 | + ASSERT_EQ(r.GlobalSize[d], global[d]); |
| 21 | + ASSERT_EQ(r.LocalSize[d], local[d]); |
| 22 | + ASSERT_EQ(r.GlobalOffset[d], offset[d]); |
40 | 23 | } |
41 | 24 | } |
42 | 25 | { |
43 | | - sycl::range<2> global_range{1024, 512}; |
44 | | - sycl::range<2> local_range{64, 32}; |
45 | | - sycl::id<2> offset{10, 20}; |
46 | | - sycl::nd_range<2> nd_range{global_range, local_range, offset}; |
47 | | - |
48 | | - { |
49 | | - sycl::detail::ranges_ref_view r{nd_range}; |
50 | | - ASSERT_EQ(r.Dims, size_t{2}); |
51 | | - ASSERT_EQ(r.GlobalSize[0], global_range[0]); |
52 | | - ASSERT_EQ(r.GlobalSize[1], global_range[1]); |
53 | | - ASSERT_EQ(r.LocalSize[0], local_range[0]); |
54 | | - ASSERT_EQ(r.LocalSize[1], local_range[1]); |
55 | | - ASSERT_EQ(r.GlobalOffset[0], offset[0]); |
56 | | - ASSERT_EQ(r.GlobalOffset[1], offset[1]); |
57 | | - } |
58 | | - { |
59 | | - sycl::detail::ranges_ref_view r{global_range, local_range}; |
60 | | - ASSERT_EQ(r.Dims, size_t{2}); |
61 | | - ASSERT_EQ(r.GlobalSize[0], global_range[0]); |
62 | | - ASSERT_EQ(r.GlobalSize[1], global_range[1]); |
63 | | - ASSERT_EQ(r.LocalSize[0], local_range[0]); |
64 | | - ASSERT_EQ(r.LocalSize[1], local_range[1]); |
65 | | - } |
66 | | - { |
67 | | - sycl::detail::ranges_ref_view r{global_range}; |
68 | | - ASSERT_EQ(r.Dims, size_t{2}); |
69 | | - ASSERT_EQ(r.GlobalSize[0], global_range[0]); |
70 | | - ASSERT_EQ(r.GlobalSize[1], global_range[1]); |
71 | | - ASSERT_EQ(r.LocalSize, nullptr); |
| 26 | + sycl::detail::ranges_ref_view r{global, local}; |
| 27 | + ASSERT_EQ(r.Dims, size_t{dims}); |
| 28 | + for (int d = 0; d < dims; d++) { |
| 29 | + ASSERT_EQ(r.GlobalSize[d], global[d]); |
| 30 | + ASSERT_EQ(r.LocalSize[d], local[d]); |
72 | 31 | } |
| 32 | + ASSERT_EQ(r.GlobalOffset, nullptr); |
73 | 33 | } |
74 | 34 | { |
75 | | - sycl::range<3> global_range{1024, 512, 256}; |
76 | | - sycl::range<3> local_range{64, 32, 16}; |
77 | | - sycl::id<3> offset{10, 20, 30}; |
78 | | - sycl::nd_range<3> nd_range{global_range, local_range, offset}; |
79 | | - |
80 | | - { |
81 | | - sycl::detail::ranges_ref_view r{nd_range}; |
82 | | - ASSERT_EQ(r.Dims, size_t{3}); |
83 | | - ASSERT_EQ(r.GlobalSize[0], global_range[0]); |
84 | | - ASSERT_EQ(r.GlobalSize[1], global_range[1]); |
85 | | - ASSERT_EQ(r.GlobalSize[2], global_range[2]); |
86 | | - ASSERT_EQ(r.LocalSize[0], local_range[0]); |
87 | | - ASSERT_EQ(r.LocalSize[1], local_range[1]); |
88 | | - ASSERT_EQ(r.LocalSize[2], local_range[2]); |
89 | | - ASSERT_EQ(r.GlobalOffset[0], offset[0]); |
90 | | - ASSERT_EQ(r.GlobalOffset[1], offset[1]); |
91 | | - ASSERT_EQ(r.GlobalOffset[2], offset[2]); |
92 | | - } |
93 | | - { |
94 | | - sycl::detail::ranges_ref_view r{global_range, local_range}; |
95 | | - ASSERT_EQ(r.Dims, size_t{3}); |
96 | | - ASSERT_EQ(r.GlobalSize[0], global_range[0]); |
97 | | - ASSERT_EQ(r.GlobalSize[1], global_range[1]); |
98 | | - ASSERT_EQ(r.GlobalSize[2], global_range[2]); |
99 | | - ASSERT_EQ(r.LocalSize[0], local_range[0]); |
100 | | - ASSERT_EQ(r.LocalSize[1], local_range[1]); |
101 | | - ASSERT_EQ(r.LocalSize[2], local_range[2]); |
102 | | - } |
103 | | - { |
104 | | - sycl::detail::ranges_ref_view r{global_range}; |
105 | | - ASSERT_EQ(r.Dims, size_t{3}); |
106 | | - ASSERT_EQ(r.GlobalSize[0], global_range[0]); |
107 | | - ASSERT_EQ(r.GlobalSize[1], global_range[1]); |
108 | | - ASSERT_EQ(r.GlobalSize[2], global_range[2]); |
109 | | - ASSERT_EQ(r.LocalSize, nullptr); |
| 35 | + sycl::detail::ranges_ref_view r{global}; |
| 36 | + ASSERT_EQ(r.Dims, size_t{dims}); |
| 37 | + for (int d = 0; d < dims; d++) { |
| 38 | + ASSERT_EQ(r.GlobalSize[d], global[d]); |
110 | 39 | } |
| 40 | + ASSERT_EQ(r.LocalSize, nullptr); |
| 41 | + ASSERT_EQ(r.GlobalOffset, nullptr); |
111 | 42 | } |
112 | 43 | } |
| 44 | + |
| 45 | + |
| 46 | +TEST(RangesRefUsage, RangesRefUsage) { |
| 47 | + TestNDRangesRefView(sycl::range<1>{1024}, sycl::range<1>{64}, |
| 48 | + sycl::id<1>{10}); |
| 49 | + TestNDRangesRefView( |
| 50 | + sycl::range<2>{1024, 512}, sycl::range<2>{64, 32}, sycl::id<2>{10, 5}); |
| 51 | + TestNDRangesRefView( |
| 52 | + sycl::range<3>{1024, 512, 256}, sycl::range<3>{64, 32, 16}, |
| 53 | + sycl::id<3>{10, 5, 2}); |
| 54 | +} |
0 commit comments