From 5329652f839b99b95d63cd471ff73d251f74d911 Mon Sep 17 00:00:00 2001
From: "Claudius \"keldu\" Holeksa" <mail@keldu.de>
Date: Fri, 14 Jun 2024 14:33:22 +0200
Subject: Fixed calc of sycl vals

---
 modules/remote-sycl/c++/remote.hpp | 47 ++++++++++++++++++++++++++++++++------
 1 file changed, 40 insertions(+), 7 deletions(-)

(limited to 'modules/remote-sycl/c++')

diff --git a/modules/remote-sycl/c++/remote.hpp b/modules/remote-sycl/c++/remote.hpp
index bcc8a3c..4510237 100644
--- a/modules/remote-sycl/c++/remote.hpp
+++ b/modules/remote-sycl/c++/remote.hpp
@@ -22,22 +22,34 @@ class remote_data<T, Encoding, Storage, rmt::Sycl> {
 private:
 	id<T> id_;
 	id_map<T,Encoding,rmt::Sycl>* map_;
-	cl::sycl::queue* queue_;
 public:
 	/**
 	 * Main constructor
 	 */
 	remote_data(const id<T>& id, id_map<T, Encoding, rmt::Sycl>& map, cl::sycl::queue& queue__):
 		id_{id},
-		map_{&map},
-		queue_{&queue__}
+		map_{&map}
 	{}
 
 	/**
 	 * Wait for the data
 	 */
 	error_or<data<T,Encoding,Storage>> wait(){
+		auto eov = map_->find(id_);
+		if(eov.is_error()){
+			auto& err = eov.get_error();
+			return std::move(err);
+		}
+		auto& val = eov.get_value();
+		std::cout<<"Values Sycl in Map: "<<val->size()<<std::endl;
 
+		{
+			auto eocop = val->template copy_to_host<storage::Default>();
+			if(eocop.is_error()){
+				return eocop;
+			}
+			return eocop.get_value();
+		}
 	}
 
 	/**
@@ -87,7 +99,9 @@ public:
 	{
 		if(!device_data_){
 			total_length_ = 0u;
+			return;
 		}
+		queue_->wait();
 	}
 
 	template<typename Encoding, typename Storage>
@@ -102,6 +116,7 @@ public:
 			return;
 		}
 		queue_->template copy<data<T,encode::Native,storage::Default>>(&from.at(0), device_data_, total_length_);
+		queue_->wait();
 	}
 	
 	data(const data<Schema, encode::Native, rmt::Sycl>& from):
@@ -116,7 +131,10 @@ public:
 		// device_data_ = cl::sycl::malloc_device<typename native_data_type<T>::type>(from.size(), *queue_);
 		if(!device_data_){
 			total_length_ = 0u;
+			return;
 		}
+
+		queue_->template copy<data<T,encode::Native,storage::Default>>(from.device_data_, device_data_, total_length_);
 	}
 	
 	data<Schema, encode::Native, rmt::Sycl>& operator=(const data<Schema, encode::Native, rmt::Sycl>& rhs) {
@@ -158,7 +176,20 @@ public:
 		}
 	}
 
-	data<T, encode::Native, saw::storage::Default>& at(uint64_t i){
+	/**
+	 * Allocate appropriate meta data and then copy to host
+	 */
+	template<typename Storage>
+	error_or<data<Schema, encode::Native, Storage>> copy_to_host() const {
+		data<Schema,encode::Native, Storage> data_{total_length_};
+
+		/// TODO Check success
+		queue_->template copy<data<T,encode::Native,storage::Default>>(device_data_, &data_.at(0), total_length_);
+		queue_->wait();
+		return data_;
+	}
+
+	data<T, encode::Native, storage::Default>& at(uint64_t i){
 	//typename native_data_type<T>::type& at(uint64_t i){
 		return device_data_[i];
 	}
@@ -247,6 +278,9 @@ public:
 		return std::get<id_map<T,Encoding,rmt::Sycl>>(storage_.maps).next_free_id();
 	}
 
+	/**
+	 * Main constructor
+	 */
 	rpc_server(interface<Iface, Encoding, rmt::Sycl, InterfaceCtxT> cl_iface):
 		cmd_queue_{},
 		cl_interface_{std::move(cl_iface)},
@@ -255,12 +289,11 @@ public:
 
 	template<typename IdT, typename Storage>
 	remote_data<IdT, Encoding, Storage, rmt::Sycl> request_data(id<IdT> dat_id){
-		/// @TODO Fix so I can receive data
-		return {dat_id, std::get<id_map<IdT, Encoding,rmt::Sycl>>(storage_.maps)};
+		return {dat_id, std::get<id_map<IdT,Encoding,rmt::Sycl>>(storage_.maps), cmd_queue_};
 	}
 
 	/**
-	 * Rpc call
+	 * Rpc call based on the name
 	 */
 	template<string_literal Name, typename ClientAllocation>
 	error_or<
-- 
cgit v1.2.3