Commit 096c1130 authored by Paul's avatar Paul
Browse files

Hipmemcpy to copy from gpu

parent f934f7a9
...@@ -45,11 +45,11 @@ hip_ptr write(const T& x) ...@@ -45,11 +45,11 @@ hip_ptr write(const T& x)
} }
template <class T> template <class T>
std::vector<T> read(const hip_ptr& x, std::size_t sz) std::vector<T> read(const void* x, std::size_t sz)
{ {
std::vector<T> result(sz); std::vector<T> result(sz);
// TODO: Check status // TODO: Check status
hipMemcpy(result.data(), x.get(), sz * sizeof(T), hipMemcpyDeviceToHost); hipMemcpy(result.data(), x, sz * sizeof(T), hipMemcpyDeviceToHost);
return result; return result;
} }
...@@ -108,7 +108,7 @@ std::vector<float> gpu() ...@@ -108,7 +108,7 @@ std::vector<float> gpu()
auto handle = make_obj<miopen_handle>(&miopenCreate); auto handle = make_obj<miopen_handle>(&miopenCreate);
auto r = p.eval( auto r = p.eval(
{{"x", x}, {"w", w}, {"output", y}, {"handle", {rtg::shape::any_type, handle.get()}}}); {{"x", x}, {"w", w}, {"output", y}, {"handle", {rtg::shape::any_type, handle.get()}}});
r.visit([&](auto output) { result.assign(output.begin(), output.end()); }); result = read<float>(r.data(), r.get_shape().elements());
return result; return result;
} }
......
Markdown is supported
0% or .
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment