From 039dd61d291060010a11a3f7bb1addfa7eb77bfd Mon Sep 17 00:00:00 2001 From: "Claudius \"keldu\" Holeksa" Date: Fri, 31 May 2024 14:19:32 +0200 Subject: Working on getting sycl to work --- modules/remote-sycl/examples/sycl_basic_kernel.cpp | 16 +++++++++++++--- 1 file changed, 13 insertions(+), 3 deletions(-) (limited to 'modules/remote-sycl/examples/sycl_basic_kernel.cpp') diff --git a/modules/remote-sycl/examples/sycl_basic_kernel.cpp b/modules/remote-sycl/examples/sycl_basic_kernel.cpp index eb79bb8..18fe9b7 100644 --- a/modules/remote-sycl/examples/sycl_basic_kernel.cpp +++ b/modules/remote-sycl/examples/sycl_basic_kernel.cpp @@ -1,12 +1,22 @@ #include "sycl_basic.hpp" -rpc_server, rmt::Sycl> listen_basic_sycl(remote& ctx, remote_address& addr){ +saw::rpc_server, saw::rmt::Sycl> listen_basic_sycl(saw::remote& ctx, saw::remote_address& addr){ saw::interface, cl::sycl::queue*> iface{ [](saw::data in, cl::sycl::queue* q) -> saw::data { - return {in.get() + 1u}; + uint64_t inr = in.get(); + cl::sycl::buffer d_inc{ &inr, 1u }; + q->submit([&](cl::sycl::handler& h){ + auto a_inc = d_inc.get_access(h); + + h.parallel_for(cl::sycl::range<1>(1u), [=] (cl::sycl::id<1> it){ + a_inc[0] += 1u; + }); + }); + q->wait(); + return {inr}; } }; - auto rpc_server = remote_ctx.template listen>(*rmt_addr, std::move(iface)); + auto rpc_server = ctx.template listen>(addr, std::move(iface)); return rpc_server; } -- cgit v1.2.3