Neko  0.9.0
A portable framework for high-order spectral element flow simulations
Macros | Functions
opr_dudxyz.c File Reference
#include <CL/cl.h>
#include <stdio.h>
#include <device/device_config.h>
#include <device/opencl/jit.h>
#include <device/opencl/prgm_lib.h>
#include <device/opencl/check.h>
#include "dudxyz_kernel.cl.h"
Include dependency graph for opr_dudxyz.c:

Go to the source code of this file.

Macros

#define STR(X)   #X
 
#define CASE(LX)
 

Functions

void opencl_dudxyz (void *du, void *u, void *dr, void *ds, void *dt, void *dx, void *dy, void *dz, void *jacinv, int *nel, int *lx)
 

Macro Definition Documentation

◆ CASE

#define CASE (   LX)
Value:
case LX: \
{ \
cl_kernel kernel = clCreateKernel(dudxyz_program, \
STR(dudxyz_kernel_lx##LX), &err); \
CL_CHECK(err); \
\
CL_CHECK(clSetKernelArg(kernel, 0, sizeof(cl_mem), (void *) &du)); \
CL_CHECK(clSetKernelArg(kernel, 1, sizeof(cl_mem), (void *) &u)); \
CL_CHECK(clSetKernelArg(kernel, 2, sizeof(cl_mem), (void *) &dr)); \
CL_CHECK(clSetKernelArg(kernel, 3, sizeof(cl_mem), (void *) &ds)); \
CL_CHECK(clSetKernelArg(kernel, 4, sizeof(cl_mem), (void *) &dt)); \
CL_CHECK(clSetKernelArg(kernel, 5, sizeof(cl_mem), (void *) &dx)); \
CL_CHECK(clSetKernelArg(kernel, 6, sizeof(cl_mem), (void *) &dy)); \
CL_CHECK(clSetKernelArg(kernel, 7, sizeof(cl_mem), (void *) &dz)); \
CL_CHECK(clSetKernelArg(kernel, 8, sizeof(cl_mem), (void *) &jacinv)); \
\
CL_CHECK(clEnqueueNDRangeKernel((cl_command_queue) glb_cmd_queue, \
kernel, 1, NULL, &global_item_size, \
&local_item_size, 0, NULL, NULL)); \
} \
break
u
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ u
Definition: ax_helm_full_kernel.h:46
dx
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dx
Definition: ax_helm_full_kernel.h:49
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__ dz
Definition: ax_helm_full_kernel.h:51
dy
__global__ void T *__restrict__ T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dy
Definition: ax_helm_full_kernel.h:50
jacinv
__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__ 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__ jacinv
Definition: ax_helm_full_kernel.h:62
dr
__global__ void const T *__restrict__ const T *__restrict__ dr
Definition: cdtp_kernel.h:107
ds
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ ds
Definition: cdtp_kernel.h:108
dt
__global__ void const T *__restrict__ const T *__restrict__ const T *__restrict__ const T *__restrict__ dt
Definition: cdtp_kernel.h:109
glb_cmd_queue
void * glb_cmd_queue
CL_CHECK
#define CL_CHECK(err)
Definition: check.h:12
STR
#define STR(X)
dudxyz_program
void * dudxyz_program

◆ STR

#define STR (   X)    #X

Function Documentation

◆ opencl_dudxyz()

void opencl_dudxyz ( void *  du,
void *  u,
void *  dr,
void *  ds,
void *  dt,
void *  dx,
void *  dy,
void *  dz,
void *  jacinv,
int *  nel,
int *  lx 
)

Fortran wrapper for device OpenCL derivative kernels

Definition at line 52 of file opr_dudxyz.c.

Here is the call graph for this function:
Here is the caller graph for this function: