|
38 | 38 |
|
39 | 39 | #include <syclcompat/device.hpp> |
40 | 40 | #include <syclcompat/group_utils.hpp> |
| 41 | +#include <syclcompat/memory.hpp> |
41 | 42 |
|
42 | 43 | void StripedToBlockedKernel(int *d_data, const sycl::nd_item<3> &item_ct1, |
43 | 44 | uint8_t *load_temp_storage, |
@@ -138,10 +139,11 @@ bool test_striped_to_blocked() { |
138 | 139 | std::ostream_iterator<int> Iter(std::cout, ", "); |
139 | 140 | std::copy(d_data, d_data + 512, Iter); |
140 | 141 | std::cout << std::endl; |
| 142 | + syclcompat::wait_and_free(d_data, q_ct1); |
141 | 143 | return false; |
142 | 144 | } |
143 | 145 | } |
144 | | - |
| 146 | + syclcompat::wait_and_free(d_data, q_ct1); |
145 | 147 | std::cout << "test_striped_to_blocked pass\n"; |
146 | 148 | return true; |
147 | 149 | } |
@@ -181,9 +183,11 @@ bool test_blocked_to_striped() { |
181 | 183 | std::ostream_iterator<int> Iter(std::cout, ", "); |
182 | 184 | std::copy(d_data, d_data + 512, Iter); |
183 | 185 | std::cout << std::endl; |
| 186 | + syclcompat::wait_and_free(d_data, q_ct1); |
184 | 187 | return false; |
185 | 188 | } |
186 | 189 | } |
| 190 | + syclcompat::wait_and_free(d_data, q_ct1); |
187 | 191 | std::cout << "test_blocked_to_striped pass\n"; |
188 | 192 | return true; |
189 | 193 | } |
@@ -226,10 +230,13 @@ bool test_scatter_to_blocked() { |
226 | 230 | std::ostream_iterator<int> Iter(std::cout, ", "); |
227 | 231 | std::copy(d_data, d_data + 512, Iter); |
228 | 232 | std::cout << std::endl; |
| 233 | + syclcompat::wait_and_free(d_data, q_ct1); |
| 234 | + syclcompat::wait_and_free(d_rank, q_ct1); |
229 | 235 | return false; |
230 | 236 | } |
231 | 237 | } |
232 | | - |
| 238 | + syclcompat::wait_and_free(d_data, q_ct1); |
| 239 | + syclcompat::wait_and_free(d_rank, q_ct1); |
233 | 240 | std::cout << "test_scatter_to_blocked pass\n"; |
234 | 241 | return true; |
235 | 242 | } |
@@ -282,9 +289,13 @@ bool test_scatter_to_striped() { |
282 | 289 | std::ostream_iterator<int> Iter(std::cout, ", "); |
283 | 290 | std::copy(d_data, d_data + 512, Iter); |
284 | 291 | std::cout << std::endl; |
| 292 | + syclcompat::wait_and_free(d_data, q_ct1); |
| 293 | + syclcompat::wait_and_free(d_rank, q_ct1); |
285 | 294 | return false; |
286 | 295 | } |
287 | 296 | } |
| 297 | + syclcompat::wait_and_free(d_data, q_ct1); |
| 298 | + syclcompat::wait_and_free(d_rank, q_ct1); |
288 | 299 | std::cout << "test_blocked_to_striped pass\n"; |
289 | 300 | return true; |
290 | 301 | } |
|
0 commit comments