Launch API to support the triple-chevron syntax#
Functions | |
hipError_t | hipConfigureCall (dim3 gridDim, dim3 blockDim, size_t sharedMem, hipStream_t stream) |
Configure a kernel launch. | |
hipError_t | hipSetupArgument (const void *arg, size_t size, size_t offset) |
Set a kernel argument. | |
hipError_t | hipLaunchByPtr (const void *func) |
Launch a kernel. | |
hipError_t | __hipPushCallConfiguration (dim3 gridDim, dim3 blockDim, size_t sharedMem, hipStream_t stream) |
Push configuration of a kernel launch. | |
hipError_t | __hipPopCallConfiguration (dim3 *gridDim, dim3 *blockDim, size_t *sharedMem, hipStream_t *stream) |
Pop configuration of a kernel launch. | |
hipError_t | hipLaunchKernel (const void *function_address, dim3 numBlocks, dim3 dimBlocks, void **args, size_t sharedMemBytes, hipStream_t stream) |
C compliant kernel launch API. | |
hipError_t | hipLaunchHostFunc (hipStream_t stream, hipHostFn_t fn, void *userData) |
Enqueues a host function call in a stream. | |
hipError_t | hipDrvMemcpy2DUnaligned (const hip_Memcpy2D *pCopy) |
hipError_t | hipExtLaunchKernel (const void *function_address, dim3 numBlocks, dim3 dimBlocks, void **args, size_t sharedMemBytes, hipStream_t stream, hipEvent_t startEvent, hipEvent_t stopEvent, int flags) |
Launches kernel from the pointer address, with arguments and shared memory on stream. | |
Detailed Description
This section describes the API to support the triple-chevron syntax.
Function Documentation
◆ __hipPopCallConfiguration()
hipError_t __hipPopCallConfiguration | ( | dim3 * | gridDim, |
dim3 * | blockDim, | ||
size_t * | sharedMem, | ||
hipStream_t * | stream | ||
) |
Pop configuration of a kernel launch.
- Parameters
-
[out] gridDim grid dimension specified as multiple of blockDim. [out] blockDim block dimensions specified in work-items [out] sharedMem Amount of dynamic shared memory to allocate for this kernel. The HIP-Clang compiler provides support for extern shared declarations. [out] stream Stream where the kernel should be dispatched. May be 0, in which case the default stream is used with associated synchronization rules.
Please note, HIP does not support kernel launch with total work items defined in dimension with size gridDim x blockDim >= 2^32.
Please note, HIP does not support kernel launch with total work items defined in dimension with size gridDim x blockDim >= 2^32.
◆ __hipPushCallConfiguration()
hipError_t __hipPushCallConfiguration | ( | dim3 | gridDim, |
dim3 | blockDim, | ||
size_t | sharedMem, | ||
hipStream_t | stream | ||
) |
Push configuration of a kernel launch.
- Parameters
-
[in] gridDim grid dimension specified as multiple of blockDim. [in] blockDim block dimensions specified in work-items [in] sharedMem Amount of dynamic shared memory to allocate for this kernel. The HIP-Clang compiler provides support for extern shared declarations. [in] stream Stream where the kernel should be dispatched. May be 0, in which case the default stream is used with associated synchronization rules.
Please note, HIP does not support kernel launch with total work items defined in dimension with size gridDim x blockDim >= 2^32.
◆ hipConfigureCall()
hipError_t hipConfigureCall | ( | dim3 | gridDim, |
dim3 | blockDim, | ||
size_t | sharedMem, | ||
hipStream_t | stream | ||
) |
Configure a kernel launch.
- Parameters
-
[in] gridDim grid dimension specified as multiple of blockDim. [in] blockDim block dimensions specified in work-items [in] sharedMem Amount of dynamic shared memory to allocate for this kernel. The HIP-Clang compiler provides support for extern shared declarations. [in] stream Stream where the kernel should be dispatched. May be 0, in which case the default stream is used with associated synchronization rules.
Please note, HIP does not support kernel launch with total work items defined in dimension with size gridDim x blockDim >= 2^32.
◆ hipDrvMemcpy2DUnaligned()
hipError_t hipDrvMemcpy2DUnaligned | ( | const hip_Memcpy2D * | pCopy | ) |
Copies memory for 2D arrays.
- Parameters
-
pCopy - Parameters for the memory copy
- Returns
- hipSuccess, hipErrorInvalidValue
◆ hipExtLaunchKernel()
hipError_t hipExtLaunchKernel | ( | const void * | function_address, |
dim3 | numBlocks, | ||
dim3 | dimBlocks, | ||
void ** | args, | ||
size_t | sharedMemBytes, | ||
hipStream_t | stream, | ||
hipEvent_t | startEvent, | ||
hipEvent_t | stopEvent, | ||
int | flags | ||
) |
Launches kernel from the pointer address, with arguments and shared memory on stream.
- Parameters
-
[in] function_address pointer to the Kernel to launch. [in] numBlocks number of blocks. [in] dimBlocks dimension of a block. [in] args pointer to kernel arguments. [in] sharedMemBytes Amount of dynamic shared memory to allocate for this kernel. HIP-Clang compiler provides support for extern shared declarations. [in] stream Stream where the kernel should be dispatched. May be 0, in which case the default stream is used with associated synchronization rules. [in] startEvent If non-null, specified event will be updated to track the start time of the kernel launch. The event must be created before calling this API. [in] stopEvent If non-null, specified event will be updated to track the stop time of the kernel launch. The event must be created before calling this API. [in] flags The value of hipExtAnyOrderLaunch, signifies if kernel can be launched in any order.
◆ hipLaunchByPtr()
hipError_t hipLaunchByPtr | ( | const void * | func | ) |
Launch a kernel.
- Parameters
-
[in] func Kernel to launch.
◆ hipLaunchHostFunc()
hipError_t hipLaunchHostFunc | ( | hipStream_t | stream, |
hipHostFn_t | fn, | ||
void * | userData | ||
) |
Enqueues a host function call in a stream.
- Parameters
-
[in] stream - stream to enqueue work to. [in] fn - function to call once operations enqueued preceeding are complete. [in] userData - User-specified data to be passed to the function.
- Warning
- : This API is marked as beta, meaning, while this is feature complete, it is still open to changes and may have outstanding issues.
◆ hipLaunchKernel()
hipError_t hipLaunchKernel | ( | const void * | function_address, |
dim3 | numBlocks, | ||
dim3 | dimBlocks, | ||
void ** | args, | ||
size_t | sharedMemBytes, | ||
hipStream_t | stream | ||
) |
C compliant kernel launch API.
- Parameters
-
[in] function_address - kernel stub function pointer. [in] numBlocks - number of blocks [in] dimBlocks - dimension of a block [in] args - kernel arguments [in] sharedMemBytes - Amount of dynamic shared memory to allocate for this kernel. The HIP-Clang compiler provides support for extern shared declarations. [in] stream - Stream where the kernel should be dispatched. May be 0, in which case th default stream is used with associated synchronization rules.
- Returns
- hipSuccess, hipErrorInvalidValue
◆ hipSetupArgument()
hipError_t hipSetupArgument | ( | const void * | arg, |
size_t | size, | ||
size_t | offset | ||
) |
Set a kernel argument.
- Parameters
-
[in] arg Pointer the argument in host memory. [in] size Size of the argument. [in] offset Offset of the argument on the argument stack.