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
|
namespace saw {
namespace impl {
template<typename Schema, typename Encoding>
struct hip_copy_to_device {
static error_or<void> apply(data<Schema, Encoding>& from, data<Schema, Encoding>** to){
static_assert(always_false<Schema,Encoding>, "Unsupported case.");
return make_void();
}
};
template<typename T, uint64_t N, typename Encoding>
struct hip_copy_to_device<schema::Primitive<T,N>, Encoding> {
using Schema = schema::Primitive<T,N>;
static error_or<void> apply(data<Schema, Encoding>& from, data<Schema,Encoding>** to){
hipError_t malloc_err = hipMalloc(to, sizeof(data<Schema,Encoding>));
// HIP_CHECK(malloc_err);
hipError_t copy_err = hipMemcpy(*to, &from, sizeof(data<Schema,Encoding>), hipMemcpyHostToDevice);
// HIP_CHECK(copy_err);
return make_void();
}
};
}
}
|