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
|
#pragma once
#include "common.hpp"
namespace saw {
/**
* Represents a remote Sycl device.
*/
template<>
class device<rmt::Sycl> final {
private:
cl::sycl::queue cmd_queue_;
public:
device():
cmd_queue_{cl::sycl::default_selector_v, cl::sycl::property_list{cl::sycl::property::queue::enable_profiling()}}
{}
SAW_FORBID_COPY(device);
SAW_FORBID_MOVE(device);
/**
* Copy data to device
*/
template<typename Schema, typename Encoding>
error_or<data<Schema, encode::Sycl<Encoding>>> copy_to_device(const data<Schema, Encoding>& host_data){
return data<Schema, encode::Sycl<Encoding>>{host_data};
}
template<typename Schema, typename Encoding>
error_or<data<Schema, encode::Sycl<Encoding>>> allocate_on_device(const data<typename meta_schema<Schema>::MetaSchema, Encoding>& host_meta){
return copy_to_device(data<Schema, Encoding>{host_meta});
}
/**
* Copy data to host
*/
template<typename Schema, typename Encoding>
error_or<data<Schema, Encoding>> copy_to_host(data<Schema, encode::Sycl<Encoding>>& dev_data){
/**
data<Schema,Encoding, Storage> host_data;
cmd_queue_.submit([&](cl::sycl::handler& h){
auto acc_buff = dev_data.template access<cl::sycl::access::mode::read>(h);
h.copy(acc_buff, &host_data);
});
cmd_queue_.wait();
*/
cl::sycl::host_accessor result{dev_data.get_handle()};
return result[0];
}
/**
* Get a reference to the handle
*/
cl::sycl::queue& get_handle(){
return cmd_queue_;
}
};
}
|
