denshooter/genode
1
0
Fork 0
mirror of https://github.com/mmueller41/genode.git synced 2026-01-21 20:42:56 +01:00
Code Issues Packages Projects Releases Wiki Activity

fixed opencl kernel bugs

Browse Source
This commit is contained in:
Marcel Lütke Dreimann
2022-08-30 10:39:21 +02:00
parent b5f2d3fad9
commit 90df5b3756
1 changed files with 8 additions and 6 deletions
Download Patch File Download Diff File Expand all files Collapse all files

14
repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc
View File

@@ -319,6 +319,7 @@ clReleaseCommandQueue(cl_command_queue command_queue)
while(cmd != NULL)
{
cl_command_queue next = cmd->next;
g_cl_genode->free(cmd->kc);
g_cl_genode->free(cmd);
cmd = next;
}
@@ -1423,6 +1424,10 @@ clEnqueueNDRangeKernel(cl_command_queue command_queue,
}
}
// create shallow copy (TODO: do we need a deep copy?)
kernel_config* kcopy = new(g_cl_genode->getAlloc()) kernel_config();
*kcopy = *kc;
// skip to end of queue
cl_command_queue cmd = command_queue;
for(;cmd->next != NULL; cmd = cmd->next);
@@ -1430,21 +1435,18 @@ clEnqueueNDRangeKernel(cl_command_queue command_queue,
// enqueue
if(cmd->kc == NULL)
{
cmd->kc = kc;
cmd->kc = kcopy;
}
else // or extend queue
{
cl_command_queue n = (cl_command_queue)g_cl_genode->alloc(sizeof(struct _cl_command_queue));
n->next = NULL;
n->kc = kcopy;
cmd->next = n;
n->kc = kc;
}
// reset finished flag in case the user enqueue the same kernel object multiple times
kc->finished = false;
g_cl_genode->enqueue_task(kc);
g_cl_genode->enqueue_task(kcopy);
return CL_SUCCESS;
}