case LX: \
{ \
STR(ax_helm_kernel_lx##LX), &err); \
CL_CHECK(clSetKernelArg(kernel, 0,
sizeof(cl_mem), (
void *) &
w)); \
CL_CHECK(clSetKernelArg(kernel, 1,
sizeof(cl_mem), (
void *) &
u)); \
CL_CHECK(clSetKernelArg(kernel, 2,
sizeof(cl_mem), (
void *) &
dx)); \
CL_CHECK(clSetKernelArg(kernel, 3,
sizeof(cl_mem), (
void *) &
dy)); \
CL_CHECK(clSetKernelArg(kernel, 4,
sizeof(cl_mem), (
void *) &
dz)); \
CL_CHECK(clSetKernelArg(kernel, 5,
sizeof(cl_mem), (
void *) &
dxt)); \
CL_CHECK(clSetKernelArg(kernel, 6,
sizeof(cl_mem), (
void *) &
dyt)); \
CL_CHECK(clSetKernelArg(kernel, 7,
sizeof(cl_mem), (
void *) &
dzt)); \
CL_CHECK(clSetKernelArg(kernel, 8,
sizeof(cl_mem), (
void *) &
h1)); \
CL_CHECK(clSetKernelArg(kernel, 9,
sizeof(cl_mem), (
void *) &
g11)); \
CL_CHECK(clSetKernelArg(kernel, 10,
sizeof(cl_mem), (
void *) &
g22)); \
CL_CHECK(clSetKernelArg(kernel, 11,
sizeof(cl_mem), (
void *) &
g33)); \
CL_CHECK(clSetKernelArg(kernel, 12,
sizeof(cl_mem), (
void *) &
g12)); \
CL_CHECK(clSetKernelArg(kernel, 13,
sizeof(cl_mem), (
void *) &
g13)); \
CL_CHECK(clSetKernelArg(kernel, 14,
sizeof(cl_mem), (
void *) &
g23));
\
kernel, 1, NULL, &global_item_size, \
&local_item_size, 0, NULL, NULL)); \
\
} \
break
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ w
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ u
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dx
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dz
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ h1
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dy
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dzt
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dyt
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dxt
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ g23
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ g22
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ g13
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ g12
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ g33
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ g11