macOS CPU已设全内核参数clEnqueueNDRangeKernel报CL_INVALID_KERNEL_ARGS

问题定位与排查方案 #

这个错误是苹果平台CPU端OpenCL实现的严格参数校验逻辑触发的，其他平台驱动普遍存在容错机制，不会在参数大小/对齐存在微小偏差时报错，可按以下优先级排查：

• 第一优先级：校验内核实际参数计数，排除宏展开不一致问题
  不要靠源码逻辑判断参数个数，内核构建完成后直接调用clGetKernelInfo传入CL_KERNEL_NUM_ARGS标记，获取编译后内核的实际入参总数，确认是否存在macOS平台编译时意外触发调试宏、导致内核实际入参数量和主机端设置的参数数量不匹配的情况。
  对每一次clSetKernelArg调用增加返回值日志校验，不要默认所有参数设置都返回CL_SUCCESS——苹果OpenCL实现存在部分场景下clSetKernelArg阶段不返回错误、直到clEnqueueNDRangeKernel调用时统一抛出CL_INVALID_KERNEL_ARGS的已知问题。

• 第二优先级：校验自定义大整数类型的参数大小与对齐
  这是该类跨平台问题最高发的诱因：

  1. 苹果CPU端OpenCL基于LLVM实现，对__private地址空间按值传递的非标量类型，强制要求参数大小、偏移量满足2的幂次对齐规则：12字节的96位自定义整型会被对齐到16字节，24字节的192位自定义整型会被对齐到32字节；如果主机端定义的对应结构体没有添加填充字节、clSetKernelArg传入的arg_size为12/24，会直接触发参数校验失败。
  2. 若自定义类型是通过OpenCL内置向量拼接实现，注意3元素向量（如uint3）在设备端的实际大小与4元素向量一致，为16字节而非12字节，主机端如果按3个uint共12字节构造传参结构体，会出现大小不匹配。
  3. 15位内核无该问题，核心原因是其没有传入超过128位的按值私有参数，不会触发对齐校验逻辑。
     可逐参数调用clGetKernelArgInfo获取每个入参的实际类型名、地址空间修饰符、期望大小，和主机端传入的参数属性逐一比对，重点核对两个自定义大整数类型的参数属性。

• 第三优先级：快速验证测试
  可临时将内核中所有按值传递的96位、192位自定义类型私有参数，改为通过全局内存buffer或__constant地址空间传入，若修改后内核可正常调度执行，可100%确认问题根因为按值传参的大小/对齐不匹配。

注：工作组大小限制与该错误无关，CL_INVALID_KERNEL_ARGS仅在参数设置存在问题时抛出，工作组大小不合法会返回CL_INVALID_WORK_GROUP_SIZE错误码，无需在该方向继续排查。

内容的提问来源于stack exchange，提问作者Danny