标签:tca 事件 线程安全 type dock offset 失败 ram range
本节介绍OpenCL的事件的相关知识。 事件是与命令的状态相关联的对象。命令队列中的命令会产生事件,其他命令在执行之前需要等待某个事件。如我们下面条之前需要查看水开了没有,那么水开了
就是一个事件。
根据场景的不同,可以分为内核端事件和宿主机端事件:
个人自扫门前雪
的意味,因为人民内部矛盾内部解决嘛
)。 同时事件还可以划分为命令事件
和用户自定义事件
。
事件在命令之间传递状态信息。命令的状态即事件的值可以取以下:
创建事件的方法有很多,最常见的还是命令在状态发生变化时。如下面的命令是将内核加入队列的API,那么就会产生一个CL_QUEUED
命令。
cl_int clEnqueueNDRangeKernel(
cl_command_queue command_queue,
cl_kernel kernel,
cl_unit work_dim,
const size_t* global_work_offset,
const size_t* global_work_size,
const size_t* local_work_size,
cl_uint num_events_in_wait_list,
const cl_event* event_wait_list,
cl_event* event
)
我们着重关注一下后面三个参数:
CL_QUEUED
,之后在执行的时候会赋值为CL_RUNNING
等等。再看一下多个事件之间的联系的一个示例:
cl_event k_events[2]; //定义两个事件
clEnqueueNDRangeKernel(command1, .... , 0, NULL, &k_events[0]); //将第一个命令加入队列,会对k_events[0]赋值,指向之前不需要等待任何事件
clEnqueueNDRangeKernel(command2, ...., 0, NULL, &k_events[0]); //同上
clEnqueueNDRangeKernel(command3, ...., 2,&k_events, NULL) //执行这条命令时会等待前面的两个命令
命令事件主要在命令队列中产生,影响同一个上下文的设备。如果我们需要与其他上下文进行同步,就需要使用到用户自定义事件:
cl_event clCreateUserEvent(
cl_context context, //指定上下文
cl_uint* errcode_ret //该函数所关联的错误值
)
如果创建成功,errcode_ret会被赋值为CL_SUCCESS
或者错误时,赋值为一下的值:
之后我们就可以在各个处理函数中设置返回的事件的值:
cl_int clSetUserEventStatus(
cl_event event, //具体事件值
cl_int execution_status //指向状态
)
上面已经说过了用户自定义事件的设置,那么命令事件的管理又是通过那些API的呢?
clGetEventStatus
clRetainEvent //增加引用计数,即得到事件
cl_ReleaseEvent //减少引用计数
当然如果需要获取事件的更详细的信息,需要用到:
cl_int clGetEventInfo(
cl_event event, //具体事件
cl_event_info param_name, //查询的信息,如命令队列,或者上下文
size_t param_value_size, //参数大小,
void* param_value, //指向的结果的指针
size_t param_value_size_ret //返回结果的大小
)
事件是OpenCL中为命令指定明确顺序约束的机制。不过事件不能跨上下文,跨上下文边界时,只有一种选择,就是让宿主机帮忙等待一个事件,然后使用用户事件触发另一个上下文命令的执行。总而言之,由于事件不能跨上下文,所以宿主机必须代表两个命令队列在两个上下文之间管理事件。
同时,事件还可以使用OpenCL定义的回调机制与宿主机上的函数进行交互。回调就是应用程序异步调用的函数。
我们可以使用下面这个函数设置回调:
cl_int clSetEventCallback(
cl_event event,
cl_int command_exec_callback_type,
void(CL_CALLBACK *pfn_event_notify)(
cl_event event,
cl_int event_command_exec_status,
void *user_data),
void *user_data
)
注意事项:
上面的命令、事件都是要与命令队列相关联。可以同步命令,有助于命令与宿主机之间的交互提供细粒度的控制。
那么内核中是否有相同的机制呢?其实事件还可以出现在内核内部,内核中的事件主要用来支持在全局与局部内存之间的异步数据复制。下面这些函数用以支持这些功能。
event_t async_work_group_copy()
event_t async_work_group_strided_copy
event_t wait_group_events
会在后面的章节有所介绍。
版权声明:本文为博主原创文章,转载需声明为转载内容并添加原文地址。
原文地址:http://coderdock.com
标签:tca 事件 线程安全 type dock offset 失败 ram range
原文地址:http://blog.51cto.com/9598289/2060009