From 426618dbd6ca4c4e2ee99597d7d5814669c67ba2 Mon Sep 17 00:00:00 2001
From: =?UTF-8?q?Marcel=20L=C3=BCtke=20Dreimann?=
 <marcel.luetkedreimann@uos.de>
Date: Fri, 18 Nov 2022 10:07:05 +0100
Subject: [PATCH] improve gpu task latency

---
 repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc | 4 +++-
 1 file changed, 3 insertions(+), 1 deletion(-)

diff --git a/repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc b/repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc
index ae88ee6b59..32018357dd 100644
--- a/repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc
+++ b/repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc
@@ -1438,6 +1438,9 @@ clEnqueueNDRangeKernel(cl_command_queue command_queue,
         kcopy->buffConfigs[i] = kc->buffConfigs[i];
     }
 
+    // start task
+    g_cl_genode->enqueue_task(kcopy);
+
     // skip to end of queue
     cl_command_queue cmd = command_queue;
     for(;cmd->next != NULL; cmd = cmd->next);
@@ -1456,7 +1459,6 @@ clEnqueueNDRangeKernel(cl_command_queue command_queue,
         cmd->next = n;
     }
 
-    g_cl_genode->enqueue_task(kcopy);
     return CL_SUCCESS;
 }