summaryrefslogtreecommitdiff
path: root/modules/remote-sycl/c++/device.hpp
blob: 6d133aec476000d94d1a604b40e5aa4776748ec2 (plain)
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
#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() = default;

	SAW_FORBID_COPY(device);
	SAW_FORBID_MOVE(device);

	/**
	 * Copy data to device
	 */
	template<typename Schema, typename Encoding, typename Storage>
	error_or<data<Schema, Encoding, rmt::Sycl>> copy_to_device(const data<Schema, Encoding, Storage>& host_data){
		return data<Schema, Encoding, rmt::Sycl>::copy_to_device(host_data, *this);
	}
	
	/**
	 * Copy data to host
	 */
	template<typename Schema, typename Encoding, typename Storage>
	error_or<data<Schema, Encoding, Storage>> copy_to_host(const data<Schema, Encoding, rmt::Sycl>& dev_data){
		return dev_data.copy_to_host();
	}
	
	/**
	 * Get a reference to the handle
	 */
	cl::sycl::queue& get_handle(){
		return cmd_queue_;
	}
};

}