将变量传递到内核

Question

我是 OpenCL 新手，正在阅读 OpenCL in Action 一书。有一个我不明白的简单问题：如何将值传递给内核并从内核返回它们。

首先，我们应该总是按地址将参数传递给内核吗？

然后，我在下面有两个简单的内核示例。在第一个中，虽然输出是作为函数参数的指针，但在内核主体中我们从未使用过 *output。而在另一个内核中，*s1 和 *s2 用作函数参数，我们实际上将值分配给 *s1 和 *s2 而不是 s1 和 s2。谁能告诉我为什么在第一个内核中将值分配给输出（而不是 *output），而在第二个内核中我们将值分配给 *s1 和 *s2（而不是 s1 和 s2）。

我查看了许多资源以找到一种在内核之间传递和返回值的通用方法，但我找不到任何通用规则。

这是内核：

1：

__kernel void id_check(__global float *output) { 

   /* Access work-item/work-group information */
   size_t global_id_0 = get_global_id(0);
   size_t global_id_1 = get_global_id(1);
   size_t global_size_0 = get_global_size(0);
   size_t offset_0 = get_global_offset(0);
   size_t offset_1 = get_global_offset(1);
   size_t local_id_0 = get_local_id(0);
   size_t local_id_1 = get_local_id(1);

   /* Determine array index */
   int index_0 = global_id_0 - offset_0;
   int index_1 = global_id_1 - offset_1;
   int index = index_1 * global_size_0 + index_0;

   /* Set float data */
   float f = global_id_0 * 10.0f + global_id_1 * 1.0f;
   f += local_id_0 * 0.1f + local_id_1 * 0.01f;

   output[index] = f;
}

2：

__kernel void select_test(__global float4 *s1, 
                          __global uchar2 *s2) {

   /* Execute select */
   int4 mask1 = (int4)(-1, 0, -1, 0);
   float4 input1 = (float4)(0.25f, 0.5f, 0.75f, 1.0f);
   float4 input2 = (float4)(1.25f, 1.5f, 1.75f, 2.0f);
   *s1 = select(input1, input2, mask1); 

   /* Execute bitselect */
   uchar2 mask2 = (uchar2)(0xAA, 0x55);
   uchar2 input3 = (uchar2)(0x0F, 0x0F);
   uchar2 input4 = (uchar2)(0x33, 0x33);
   *s2 = bitselect(input3, input4, mask2); 
}

Answer 1

您的问题不在于 OpenCL，而在于 C 语言本身。请阅读有关 C 语言如何工作的书。这是一个非常基本的问题。

当你有一个指针时，(output, s1, s2) 你可以通过多种方式访问​​它。 output 指的是指针（地址），*output 指的是第一个元素（或指针指向的单个元素）处的值，output[i] 指的是ith 元素的值。

*output 和 output[0] 相同，*(output+1) 和 output[1] 相同。