Working on getting sycl to work

5 files changed, 35 insertions, 9 deletions

diff --git a/modules/remote-sycl/.nix/derivation.nix b/modules/remote-sycl/.nix/derivation.nix
index 2b00ada..65c408c 100644
--- a/modules/remote-sycl/.nix/derivation.nix
+++ b/modules/remote-sycl/.nix/derivation.nix
@@ -6,6 +6,7 @@
 , forstio
 , openmp
 , opensycl
+, python3
 , ocl-icd
 
 , build_examples ? "false"
@@ -22,7 +23,8 @@ in stdenv.mkDerivation {
 
   nativeBuildInputs = [
     scons
-    clang-tools
+		clang-tools
+		python3
   ];
 
   buildInputs = [
diff --git a/modules/remote-sycl/c++/remote.hpp b/modules/remote-sycl/c++/remote.hpp
index 003dd0e..dbbefcb 100644
--- a/modules/remote-sycl/c++/remote.hpp
+++ b/modules/remote-sycl/c++/remote.hpp
@@ -116,7 +116,7 @@ public:
 					return std::move(eov.get_error());
 				}
 				return eov.get_value();
-			}else {
+			} else {
 				return &input.get_data();
 			}
 		}();
diff --git a/modules/remote-sycl/examples/sycl_basic.cpp b/modules/remote-sycl/examples/sycl_basic.cpp
index abea738..64ec1fe 100644
--- a/modules/remote-sycl/examples/sycl_basic.cpp
+++ b/modules/remote-sycl/examples/sycl_basic.cpp
@@ -1,4 +1,5 @@
 #include "./sycl_basic.hpp"
+#include <forstio/codec/schema.hpp>
 
 int main(){
 	saw::remote<saw::rmt::Sycl> remote_ctx;
@@ -20,15 +21,26 @@ int main(){
 
 	auto rpc_server = listen_basic_sycl(remote_ctx, *rmt_addr);
 
+	saw::id<schema::UInt64> next_id{0u};
 	{
-		auto eov = rpc_server.template call<"increment">(saw::id<schema::UInt64>{1u});
+		auto eov = rpc_server.template call<"increment">(saw::data<schema::UInt64>{1u});
 		if(eov.is_error()){
+			auto& err = eov.get_error();
+			std::cerr<<"Error: "<<err.get_category()<<" : "<<err.get_message()<<std::endl;
+			return -2;
+		}
+		next_id = eov.get_value();
+	}
+	{
+		auto eov = rpc_server.template call<"increment">(next_id);
+		if(eov.is_error()){
+			auto& err = eov.get_error();
+			std::cerr<<"Error: "<<err.get_category()<<" : "<<err.get_message()<<std::endl;
 			return -2;
 		}
 		auto& val = eov.get_value();
-		// std::cout<<"Value: "<<val<<std::endl;
+		std::cout<<"Value: "<<val.get_value()<<std::endl;
 	}
 
-
 	return 0;
 }
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<schema::BasicInterface, encode::Native<storage::Default>, rmt::Sycl> listen_basic_sycl(remote<rmt::Sycl>& ctx, remote_address<rmt::Sycl>& addr){
+saw::rpc_server<schema::BasicInterface, saw::encode::Native<saw::storage::Default>, saw::rmt::Sycl> listen_basic_sycl(saw::remote<saw::rmt::Sycl>& ctx, saw::remote_address<saw::rmt::Sycl>& addr){
 	saw::interface<schema::BasicInterface, saw::encode::Native<saw::storage::Default>, cl::sycl::queue*> iface{
 		[](saw::data<saw::schema::UInt64> in, cl::sycl::queue* q) -> saw::data<saw::schema::UInt64> {
-			return {in.get() + 1u};
+			uint64_t inr = in.get();
+			cl::sycl::buffer<uint64_t,1>  d_inc{ &inr, 1u };
+			q->submit([&](cl::sycl::handler& h){
+				auto a_inc = d_inc.get_access<cl::sycl::access::mode::read_write>(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<schema::BasicInterface, saw::encode::Native<saw::storage::Default>>(*rmt_addr, std::move(iface));
+	auto rpc_server = ctx.template listen<schema::BasicInterface, saw::encode::Native<saw::storage::Default>>(addr, std::move(iface));
 	
 	return rpc_server;
 }
diff --git a/modules/remote-sycl/tests/SConscript b/modules/remote-sycl/tests/SConscript
index f8ffc92..3a9a2cf 100644
--- a/modules/remote-sycl/tests/SConscript
+++ b/modules/remote-sycl/tests/SConscript
@@ -12,6 +12,8 @@ dir_path = Dir('.').abspath
 # Environment for base library
 test_cases_env = env.Clone();
 
+test_cases_env['CXX'] = 'syclcc';
+
 test_cases_env.Append(LIBS=['forstio-test']);
 
 test_cases_env.sources = sorted(glob.glob(dir_path + "/*.cpp"))
@@ -28,4 +30,4 @@ test_cases_env.program = test_cases_env.Program('#bin/tests', [objects_static, e
 env.Alias('test', test_cases_env.program);
 env.Alias('check', test_cases_env.program);
 
-env.targets += ['test','check'];
+# env.targets += ['test','check'];