OpenCL 内核仅利用诊断

我目前正在 OSX 上开发 OpenCL 内核，我正在尝试将输入图像设置为所有 255。我使用CL_MEM_WRITE_ONLY | CL_MEM_ALLOC_HOST_PTR和创建了一个 1 通道图像，CL_UNSIGNED_INT8我的内核和主机代码如下：

const sampler_t linear_sampler = CLK_NORMALIZED_COORDS_FALSE | CLK_FILTER_LINEAR | CLK_ADDRESS_CLAMP_TO_EDGE;
__kernel void test(__write_only image2d_t dst)
{
    const int2 src_pos = int2(get_global_id(0), get_global_id(1));
    write_imagei(dst, src_pos, 255);
}

void clTest(cl_image2d dst)
{        
    cl_int retval;

    cl_kernel kTest = clCreateKernel(m_oclEnv.program, "test", &retval);
    CHECK_OCL(clSetKernelArg(kTest, 0, sizeof(cl_mem), (void*)&dst.mem));

    size_t grid_item_size[2] = {static_cast<size_t>(m_nFrameWidth), static_cast<size_t>(m_nFrameHeight)};
    size_t block_item_size[2] = {8, 8};
    cl_uint nDim = 2;        

    CHECK_OCL(clEnqueueNDRangeKernel(m_oclEnv.queue, kTest, nDim, NULL, grid_item_size, block_item_size, 0, NULL, NULL));

    clReleaseKernel(kTest);

}

结果输出图像是这样的：

显然内核只在y=x的位置绘制，那么问题出在哪里？谢谢。

ps：我已经尝试将图像写入GPU并立即读出并且效果很好，因此opencl上下文或环境应该没有任何问题。