|
6 | 6 |
|
7 | 7 | #include <CL/sycl.hpp>
|
8 | 8 |
|
9 |
| -#include <array> |
10 | 9 | #include <cassert>
|
11 | 10 |
|
12 |
| -using namespace cl::sycl; |
| 11 | +namespace s = cl::sycl; |
13 | 12 |
|
14 | 13 | int main() {
|
15 | 14 | // dot
|
16 | 15 | {
|
17 |
| - cl::sycl::cl_float r{0}; |
| 16 | + s::cl_float r{ 0 }; |
18 | 17 | {
|
19 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
20 |
| - queue myQueue; |
21 |
| - myQueue.submit([&](handler &cgh) { |
22 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
| 18 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 19 | + s::queue myQueue; |
| 20 | + myQueue.submit([&](s::handler &cgh) { |
| 21 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
23 | 22 | cgh.single_task<class dotF1F1>([=]() {
|
24 |
| - AccR[0] = |
25 |
| - cl::sycl::dot(cl::sycl::cl_float{0.5}, cl::sycl::cl_float{1.6}); |
| 23 | + AccR[0] = s::dot(s::cl_float{ 0.5 }, s::cl_float{ 1.6 }); |
26 | 24 | });
|
27 | 25 | });
|
28 | 26 | }
|
29 |
| - std::cout << "r " << r << std::endl; |
30 | 27 | assert(r == 0.8f);
|
31 | 28 | }
|
32 | 29 |
|
33 | 30 | // distance
|
34 | 31 | {
|
35 |
| - cl::sycl::cl_float r{0}; |
| 32 | + s::cl_float r{ 0 }; |
36 | 33 | {
|
37 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
38 |
| - queue myQueue; |
39 |
| - myQueue.submit([&](handler &cgh) { |
40 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
| 34 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 35 | + s::queue myQueue; |
| 36 | + myQueue.submit([&](s::handler &cgh) { |
| 37 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
41 | 38 | cgh.single_task<class distanceF1>([=]() {
|
42 |
| - AccR[0] = cl::sycl::distance(cl::sycl::cl_float{1.f}, |
43 |
| - cl::sycl::cl_float{3.f}); |
| 39 | + AccR[0] = s::distance(s::cl_float{ 1.f }, s::cl_float{ 3.f }); |
44 | 40 | });
|
45 | 41 | });
|
46 | 42 | }
|
47 |
| - std::cout << "r " << r << std::endl; |
48 | 43 | assert(r == 2.f);
|
49 | 44 | }
|
50 | 45 |
|
51 | 46 | // length
|
52 | 47 | {
|
53 |
| - cl::sycl::cl_float r{0}; |
| 48 | + s::cl_float r{ 0 }; |
54 | 49 | {
|
55 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
56 |
| - queue myQueue; |
57 |
| - myQueue.submit([&](handler &cgh) { |
58 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
59 |
| - cgh.single_task<class lengthF1>( |
60 |
| - [=]() { AccR[0] = cl::sycl::length(cl::sycl::cl_float{1.f}); }); |
| 50 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 51 | + s::queue myQueue; |
| 52 | + myQueue.submit([&](s::handler &cgh) { |
| 53 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
| 54 | + cgh.single_task<class lengthF1>([=]() { |
| 55 | + AccR[0] = s::length(s::cl_float{ 1.f }); |
| 56 | + }); |
61 | 57 | });
|
62 | 58 | }
|
63 |
| - std::cout << "r " << r << std::endl; |
64 | 59 | assert(r == 1.f);
|
65 | 60 | }
|
| 61 | + |
66 | 62 | // normalize
|
67 | 63 | {
|
68 |
| - cl::sycl::cl_float r{0}; |
| 64 | + s::cl_float r{ 0 }; |
69 | 65 | {
|
70 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
71 |
| - queue myQueue; |
72 |
| - myQueue.submit([&](handler &cgh) { |
73 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
74 |
| - cgh.single_task<class normalizeF1>( |
75 |
| - [=]() { AccR[0] = cl::sycl::normalize(cl::sycl::cl_float{2.f}); }); |
| 66 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 67 | + s::queue myQueue; |
| 68 | + myQueue.submit([&](s::handler &cgh) { |
| 69 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
| 70 | + cgh.single_task<class normalizeF1>([=]() { |
| 71 | + AccR[0] = s::normalize(s::cl_float{ 2.f }); |
| 72 | + }); |
76 | 73 | });
|
77 | 74 | }
|
78 |
| - |
79 |
| - std::cout << "r " << r << std::endl; |
80 | 75 | assert(r == 1.f);
|
81 | 76 | }
|
82 | 77 |
|
83 | 78 | // fast_distance
|
84 | 79 | {
|
85 |
| - cl::sycl::cl_float r{0}; |
| 80 | + s::cl_float r{ 0 }; |
86 | 81 | {
|
87 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
88 |
| - queue myQueue; |
89 |
| - myQueue.submit([&](handler &cgh) { |
90 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
| 82 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 83 | + s::queue myQueue; |
| 84 | + myQueue.submit([&](s::handler &cgh) { |
| 85 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
91 | 86 | cgh.single_task<class fast_distanceF1>([=]() {
|
92 |
| - AccR[0] = cl::sycl::fast_distance(cl::sycl::cl_float{1.f}, |
93 |
| - cl::sycl::cl_float{3.f}); |
| 87 | + AccR[0] = s::fast_distance(s::cl_float{ 1.f }, s::cl_float{ 3.f }); |
94 | 88 | });
|
95 | 89 | });
|
96 | 90 | }
|
97 |
| - std::cout << "r " << r << std::endl; |
98 | 91 | assert(r == 2.f);
|
99 | 92 | }
|
| 93 | + |
100 | 94 | // fast_length
|
101 | 95 | {
|
102 |
| - cl::sycl::cl_float r{0}; |
| 96 | + s::cl_float r{ 0 }; |
103 | 97 | {
|
104 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
105 |
| - queue myQueue; |
106 |
| - myQueue.submit([&](handler &cgh) { |
107 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
| 98 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 99 | + s::queue myQueue; |
| 100 | + myQueue.submit([&](s::handler &cgh) { |
| 101 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
108 | 102 | cgh.single_task<class fast_lengthF1>([=]() {
|
109 |
| - AccR[0] = cl::sycl::fast_length(cl::sycl::cl_float{2.f}); |
| 103 | + AccR[0] = s::fast_length(s::cl_float{ 2.f }); |
110 | 104 | });
|
111 | 105 | });
|
112 | 106 | }
|
113 |
| - std::cout << "r " << r << std::endl; |
114 | 107 | assert(r == 2.f);
|
115 | 108 | }
|
| 109 | + |
116 | 110 | // fast_normalize
|
117 | 111 | {
|
118 |
| - cl::sycl::cl_float r{0}; |
| 112 | + s::cl_float r{ 0 }; |
119 | 113 | {
|
120 |
| - buffer<cl::sycl::cl_float, 1> BufR(&r, range<1>(1)); |
121 |
| - queue myQueue; |
122 |
| - myQueue.submit([&](handler &cgh) { |
123 |
| - auto AccR = BufR.get_access<access::mode::write>(cgh); |
| 114 | + s::buffer<s::cl_float, 1> BufR(&r, s::range<1>(1)); |
| 115 | + s::queue myQueue; |
| 116 | + myQueue.submit([&](s::handler &cgh) { |
| 117 | + auto AccR = BufR.get_access<s::access::mode::write>(cgh); |
124 | 118 | cgh.single_task<class fast_normalizeF1>([=]() {
|
125 |
| - AccR[0] = cl::sycl::fast_normalize(cl::sycl::cl_float{2.f}); |
| 119 | + AccR[0] = s::fast_normalize(s::cl_float{ 2.f }); |
126 | 120 | });
|
127 | 121 | });
|
128 | 122 | }
|
129 | 123 |
|
130 |
| - std::cout << "r " << r << std::endl; |
131 | 124 | assert(r == 1.f);
|
132 | 125 | }
|
133 | 126 |
|
|
0 commit comments