diff --git a/docs/RuntimeAPI/html/Synchonization.html b/docs/RuntimeAPI/html/Synchonization.html new file mode 100644 index 0000000000..fa615f44d1 --- /dev/null +++ b/docs/RuntimeAPI/html/Synchonization.html @@ -0,0 +1,117 @@ + + +
+ + + +|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
The following commands are "host-asynchronous" - meaning they do not wait for any preceding commands to complete, and may return control to the host thread before the requested operation completes:
+"Host-synchronous" commands have the following properties:
+The following commands are "host-synchronous".
+The term "blocking" has two meanings in HIP.
+The first refers to synchronization commands (ie hipStreamSynchronize, hipEventSynchronize) that cause the host CPU to wait for GPU activity to complete. These can either use an active where the host CPU spin-waits on the synchronization variable, or can use an interrupt-based scheme where the core is interrupted when the wait completes. The second technique is referred to as "blocking" (ie hipDeviceBlockingSync, hipEventBlockingSync) while the first is referred to as "active". Active can be appropriate for short tasks where latency is critical, but comes at the expense of a CPU core dedicated to monitoring the event.
+Note CUDA_LAUNCH_BLOCKING does add any pre-serialization to the commands and does not affect the concurrent stream behavior. For example, even when CUDA_LAUNCH_BLOCKING is set, kernels or data copy commands launched to separate streams can execute concurrently. Use the NULL stream if additional stream synchronization is desired.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/annotated.html b/docs/RuntimeAPI/html/annotated.html
new file mode 100644
index 0000000000..eeeaa5f91f
--- /dev/null
+++ b/docs/RuntimeAPI/html/annotated.html
@@ -0,0 +1,145 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/bc_s.png b/docs/RuntimeAPI/html/bc_s.png
new file mode 100644
index 0000000000..224b29aa98
Binary files /dev/null and b/docs/RuntimeAPI/html/bc_s.png differ
diff --git a/docs/RuntimeAPI/html/bdwn.png b/docs/RuntimeAPI/html/bdwn.png
new file mode 100644
index 0000000000..940a0b9504
Binary files /dev/null and b/docs/RuntimeAPI/html/bdwn.png differ
diff --git a/docs/RuntimeAPI/html/bug.html b/docs/RuntimeAPI/html/bug.html
new file mode 100644
index 0000000000..a79e8f7948
--- /dev/null
+++ b/docs/RuntimeAPI/html/bug.html
@@ -0,0 +1,97 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
HCC always returns 0 for maxThreadsPerMultiProcessor
+HCC always returns 0 for regsPerBlock
+HCC always returns 0 for l2CacheSize
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classFakeMutex-members.html b/docs/RuntimeAPI/html/classFakeMutex-members.html
new file mode 100644
index 0000000000..37207bf255
--- /dev/null
+++ b/docs/RuntimeAPI/html/classFakeMutex-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for FakeMutex, including all inherited members.
+| lock() (defined in FakeMutex) | FakeMutex | inline |
| try_lock() (defined in FakeMutex) | FakeMutex | inline |
| unlock() (defined in FakeMutex) | FakeMutex | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classFakeMutex.html b/docs/RuntimeAPI/html/classFakeMutex.html
new file mode 100644
index 0000000000..dd73a2063c
--- /dev/null
+++ b/docs/RuntimeAPI/html/classFakeMutex.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| +void | lock () |
| +bool | try_lock () |
| +void | unlock () |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classLockedAccessor-members.html b/docs/RuntimeAPI/html/classLockedAccessor-members.html
new file mode 100644
index 0000000000..97ee053446
--- /dev/null
+++ b/docs/RuntimeAPI/html/classLockedAccessor-members.html
@@ -0,0 +1,105 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for LockedAccessor< T >, including all inherited members.
+| LockedAccessor(T &criticalData, bool autoUnlock=true) (defined in LockedAccessor< T >) | LockedAccessor< T > | inline |
| operator->() (defined in LockedAccessor< T >) | LockedAccessor< T > | inline |
| unlock() (defined in LockedAccessor< T >) | LockedAccessor< T > | inline |
| ~LockedAccessor() (defined in LockedAccessor< T >) | LockedAccessor< T > | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classLockedAccessor.html b/docs/RuntimeAPI/html/classLockedAccessor.html
new file mode 100644
index 0000000000..1ca2f522a5
--- /dev/null
+++ b/docs/RuntimeAPI/html/classLockedAccessor.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| + | LockedAccessor (T &criticalData, bool autoUnlock=true) |
| +void | unlock () |
| +T * | operator-> () |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classShortTid-members.html b/docs/RuntimeAPI/html/classShortTid-members.html
new file mode 100644
index 0000000000..65b4c7a8ab
--- /dev/null
+++ b/docs/RuntimeAPI/html/classShortTid-members.html
@@ -0,0 +1,105 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ShortTid, including all inherited members.
+| apiSeqNum() const (defined in ShortTid) | ShortTid | inline |
| incApiSeqNum() (defined in ShortTid) | ShortTid | inline |
| ShortTid() (defined in ShortTid) | ShortTid | |
| tid() const (defined in ShortTid) | ShortTid | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classShortTid.html b/docs/RuntimeAPI/html/classShortTid.html
new file mode 100644
index 0000000000..8a98c9d95f
--- /dev/null
+++ b/docs/RuntimeAPI/html/classShortTid.html
@@ -0,0 +1,118 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| +int | tid () const |
| +uint64_t | incApiSeqNum () |
| +uint64_t | apiSeqNum () const |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classes.html b/docs/RuntimeAPI/html/classes.html
new file mode 100644
index 0000000000..fbbc40e7a7
--- /dev/null
+++ b/docs/RuntimeAPI/html/classes.html
@@ -0,0 +1,130 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
|
| double1 | hipFloatComplex | ihipStreamCriticalBase_t | ||||
| double3 | hipPointerAttribute_t | int3 | ||||||
| DbName | ShortTid |
|
|
| ||||
|
| |||||||
| float1 | ihipCtx_t | long3 | ||||||
| FakeMutex | __half | float3 | ihipCtxCriticalBase_t | longlong3 | ||||
|
|
| ihipDevice_t |
| ||||
| ihipEvent_t | ||||||||
| LockedAccessor | char3 | hipArray | ihipException | short3 | ||||
| LockedBase | char4 | hipChannelFormatDesc | ihipFunction_t | struct_float | ||||
|
| hipDeviceArch_t | ihipIpcMemHandle_t |
| ||||
| hipDeviceProp_t | ihipModule_t | |||||||
| ProfTrigger | dim3 | hipDoubleComplex | ihipStream_t | textureReference | ||||
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipCtxCriticalBase__t-members.html b/docs/RuntimeAPI/html/classihipCtxCriticalBase__t-members.html
new file mode 100644
index 0000000000..574362a0ec
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipCtxCriticalBase__t-members.html
@@ -0,0 +1,118 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipCtxCriticalBase_t< MUTEX_TYPE >, including all inherited members.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipCtxCriticalBase__t.html b/docs/RuntimeAPI/html/classihipCtxCriticalBase__t.html
new file mode 100644
index 0000000000..e18eee4e66
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipCtxCriticalBase__t.html
@@ -0,0 +1,164 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+
+ +Public Member Functions | |
| + | ihipCtxCriticalBase_t (unsigned deviceCnt) |
| +void | addStream (ihipStream_t *stream) |
| +std::list< ihipStream_t * > & | streams () |
| +const std::list< ihipStream_t * > & | const_streams () const |
| +bool | isPeerWatcher (const ihipCtx_t *peer) |
| +bool | addPeerWatcher (const ihipCtx_t *thisCtx, ihipCtx_t *peer) |
| +bool | removePeerWatcher (const ihipCtx_t *thisCtx, ihipCtx_t *peer) |
| +void | resetPeerWatchers (ihipCtx_t *thisDevice) |
| +void | printPeerWatchers (FILE *f) const |
| +uint32_t | peerCnt () const |
| +hsa_agent_t * | peerAgents () const |
+Public Attributes | |
| +std::list< ihipCtx_t * > | _peers |
+Friends | |
| +class | LockedAccessor< ihipCtxCriticalBase_t > |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipCtxCriticalBase__t.png b/docs/RuntimeAPI/html/classihipCtxCriticalBase__t.png
new file mode 100644
index 0000000000..7fe1e9a2dd
Binary files /dev/null and b/docs/RuntimeAPI/html/classihipCtxCriticalBase__t.png differ
diff --git a/docs/RuntimeAPI/html/classihipCtx__t-members.html b/docs/RuntimeAPI/html/classihipCtx__t-members.html
new file mode 100644
index 0000000000..200a5d4faa
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipCtx__t-members.html
@@ -0,0 +1,115 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipCtx_t, including all inherited members.
+| _ctxFlags (defined in ihipCtx_t) | ihipCtx_t | |
| _defaultStream (defined in ihipCtx_t) | ihipCtx_t | |
| criticalData() (defined in ihipCtx_t) | ihipCtx_t | inline |
| getDevice() const (defined in ihipCtx_t) | ihipCtx_t | inline |
| getDeviceNum() const (defined in ihipCtx_t) | ihipCtx_t | inline |
| getWriteableDevice() const (defined in ihipCtx_t) | ihipCtx_t | inline |
| ihipCtx_t(ihipDevice_t *device, unsigned deviceCnt, unsigned flags) (defined in ihipCtx_t) | ihipCtx_t | |
| locked_addStream(ihipStream_t *s) (defined in ihipCtx_t) | ihipCtx_t | |
| locked_removeStream(ihipStream_t *s) (defined in ihipCtx_t) | ihipCtx_t | |
| locked_reset() (defined in ihipCtx_t) | ihipCtx_t | |
| locked_syncDefaultStream(bool waitOnSelf) (defined in ihipCtx_t) | ihipCtx_t | |
| locked_waitAllStreams() (defined in ihipCtx_t) | ihipCtx_t | |
| toString() const (defined in ihipCtx_t) | ihipCtx_t | |
| ~ihipCtx_t() (defined in ihipCtx_t) | ihipCtx_t |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipCtx__t.html b/docs/RuntimeAPI/html/classihipCtx__t.html
new file mode 100644
index 0000000000..42115ba7d7
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipCtx__t.html
@@ -0,0 +1,152 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| + | ihipCtx_t (ihipDevice_t *device, unsigned deviceCnt, unsigned flags) |
| +void | locked_addStream (ihipStream_t *s) |
| +void | locked_removeStream (ihipStream_t *s) |
| +void | locked_reset () |
| +void | locked_waitAllStreams () |
| +void | locked_syncDefaultStream (bool waitOnSelf) |
| +ihipCtxCritical_t & | criticalData () |
| +const ihipDevice_t * | getDevice () const |
| +int | getDeviceNum () const |
| +ihipDevice_t * | getWriteableDevice () const |
| +std::string | toString () const |
+Public Attributes | |
| +ihipStream_t * | _defaultStream |
| +unsigned | _ctxFlags |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipDevice__t-members.html b/docs/RuntimeAPI/html/classihipDevice__t-members.html
new file mode 100644
index 0000000000..bcff2ac95d
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipDevice__t-members.html
@@ -0,0 +1,111 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipDevice_t, including all inherited members.
+| _acc (defined in ihipDevice_t) | ihipDevice_t | |
| _computeUnits | ihipDevice_t | |
| _deviceId (defined in ihipDevice_t) | ihipDevice_t | |
| _hsaAgent (defined in ihipDevice_t) | ihipDevice_t | |
| _isLargeBar (defined in ihipDevice_t) | ihipDevice_t | |
| _primaryCtx (defined in ihipDevice_t) | ihipDevice_t | |
| _props (defined in ihipDevice_t) | ihipDevice_t | |
| getPrimaryCtx() const (defined in ihipDevice_t) | ihipDevice_t | inline |
| ihipDevice_t(unsigned deviceId, unsigned deviceCnt, hc::accelerator &acc) (defined in ihipDevice_t) | ihipDevice_t | |
| ~ihipDevice_t() (defined in ihipDevice_t) | ihipDevice_t |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipDevice__t.html b/docs/RuntimeAPI/html/classihipDevice__t.html
new file mode 100644
index 0000000000..53dbfb48ce
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipDevice__t.html
@@ -0,0 +1,141 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| + | ihipDevice_t (unsigned deviceId, unsigned deviceCnt, hc::accelerator &acc) |
| +ihipCtx_t * | getPrimaryCtx () const |
+Public Attributes | |
| +unsigned | _deviceId |
| +hc::accelerator | _acc |
| +hsa_agent_t | _hsaAgent |
| +unsigned | _computeUnits |
| Number of compute units supported by the device: | |
| +hipDeviceProp_t | _props |
| +int | _isLargeBar |
| +ihipCtx_t * | _primaryCtx |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipException-members.html b/docs/RuntimeAPI/html/classihipException-members.html
new file mode 100644
index 0000000000..a95b0cec3d
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipException-members.html
@@ -0,0 +1,103 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipException, including all inherited members.
+| _code (defined in ihipException) | ihipException | |
| ihipException(hipError_t e) (defined in ihipException) | ihipException | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipException.html b/docs/RuntimeAPI/html/classihipException.html
new file mode 100644
index 0000000000..09965dc766
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipException.html
@@ -0,0 +1,126 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+
+ +Public Member Functions | |
| + | ihipException (hipError_t e) |
+Public Attributes | |
| +hipError_t | _code |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipException.png b/docs/RuntimeAPI/html/classihipException.png
new file mode 100644
index 0000000000..36add951e6
Binary files /dev/null and b/docs/RuntimeAPI/html/classihipException.png differ
diff --git a/docs/RuntimeAPI/html/classihipFunction__t-members.html b/docs/RuntimeAPI/html/classihipFunction__t-members.html
new file mode 100644
index 0000000000..b2146dd003
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipFunction__t-members.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipFunction_t, including all inherited members.
+| _kernel (defined in ihipFunction_t) | ihipFunction_t | |
| _kernelName (defined in ihipFunction_t) | ihipFunction_t | |
| _kernelSymbol (defined in ihipFunction_t) | ihipFunction_t | |
| ihipFunction_t(const char *name) (defined in ihipFunction_t) | ihipFunction_t | inline |
| ~ihipFunction_t() (defined in ihipFunction_t) | ihipFunction_t | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipFunction__t.html b/docs/RuntimeAPI/html/classihipFunction__t.html
new file mode 100644
index 0000000000..2b852c1910
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipFunction__t.html
@@ -0,0 +1,124 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| + | ihipFunction_t (const char *name) |
+Public Attributes | |
| +const char * | _kernelName |
| +hsa_executable_symbol_t | _kernelSymbol |
| +uint64_t | _kernel |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipIpcMemHandle__t-members.html b/docs/RuntimeAPI/html/classihipIpcMemHandle__t-members.html
new file mode 100644
index 0000000000..87eee6dc9a
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipIpcMemHandle__t-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipIpcMemHandle_t, including all inherited members.
+| ipc_handle | ihipIpcMemHandle_t | |
| psize (defined in ihipIpcMemHandle_t) | ihipIpcMemHandle_t | |
| reserved (defined in ihipIpcMemHandle_t) | ihipIpcMemHandle_t |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipIpcMemHandle__t.html b/docs/RuntimeAPI/html/classihipIpcMemHandle__t.html
new file mode 100644
index 0000000000..b057cf392b
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipIpcMemHandle__t.html
@@ -0,0 +1,118 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +hsa_amd_ipc_memory_t | ipc_handle |
| ipc memory handle on ROCr | |
| +char | reserved [HIP_IPC_HANDLE_SIZE] |
| +size_t | psize |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipModule__t-members.html b/docs/RuntimeAPI/html/classihipModule__t-members.html
new file mode 100644
index 0000000000..0ee668b4a5
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipModule__t-members.html
@@ -0,0 +1,109 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipModule_t, including all inherited members.
+| executable (defined in ihipModule_t) | ihipModule_t | |
| fileName (defined in ihipModule_t) | ihipModule_t | |
| ihipModule_t() (defined in ihipModule_t) | ihipModule_t | inline |
| object (defined in ihipModule_t) | ihipModule_t | |
| ptr (defined in ihipModule_t) | ihipModule_t | |
| registerFunction(ihipFunction_t *func) (defined in ihipModule_t) | ihipModule_t | inline |
| size (defined in ihipModule_t) | ihipModule_t | |
| ~ihipModule_t() (defined in ihipModule_t) | ihipModule_t | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipModule__t.html b/docs/RuntimeAPI/html/classihipModule__t.html
new file mode 100644
index 0000000000..0726617630
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipModule__t.html
@@ -0,0 +1,130 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| +void | registerFunction (ihipFunction_t *func) |
+Public Attributes | |
| +hsa_executable_t | executable |
| +hsa_code_object_t | object |
| +std::string | fileName |
| +void * | ptr |
| +size_t | size |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipStreamCriticalBase__t-members.html b/docs/RuntimeAPI/html/classihipStreamCriticalBase__t-members.html
new file mode 100644
index 0000000000..6cd21dc31f
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipStreamCriticalBase__t-members.html
@@ -0,0 +1,109 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipStreamCriticalBase_t< MUTEX_TYPE >, including all inherited members.
+| _av (defined in ihipStreamCriticalBase_t< MUTEX_TYPE >) | ihipStreamCriticalBase_t< MUTEX_TYPE > | |
| _kernelCnt (defined in ihipStreamCriticalBase_t< MUTEX_TYPE >) | ihipStreamCriticalBase_t< MUTEX_TYPE > | |
| _mutex (defined in LockedBase< MUTEX_TYPE >) | LockedBase< MUTEX_TYPE > | |
| ihipStreamCriticalBase_t(hc::accelerator_view av) (defined in ihipStreamCriticalBase_t< MUTEX_TYPE >) | ihipStreamCriticalBase_t< MUTEX_TYPE > | inline |
| lock() (defined in LockedBase< MUTEX_TYPE >) | LockedBase< MUTEX_TYPE > | inline |
| mlock() (defined in ihipStreamCriticalBase_t< MUTEX_TYPE >) | ihipStreamCriticalBase_t< MUTEX_TYPE > | inline |
| unlock() (defined in LockedBase< MUTEX_TYPE >) | LockedBase< MUTEX_TYPE > | inline |
| ~ihipStreamCriticalBase_t() (defined in ihipStreamCriticalBase_t< MUTEX_TYPE >) | ihipStreamCriticalBase_t< MUTEX_TYPE > | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipStreamCriticalBase__t.html b/docs/RuntimeAPI/html/classihipStreamCriticalBase__t.html
new file mode 100644
index 0000000000..c06d346cc3
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipStreamCriticalBase__t.html
@@ -0,0 +1,145 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+
+ +Public Member Functions | |
| + | ihipStreamCriticalBase_t (hc::accelerator_view av) |
|
+ihipStreamCriticalBase_t +< StreamMutex > * | mlock () |
Public Member Functions inherited from LockedBase< MUTEX_TYPE > | |
| +void | lock () |
| +void | unlock () |
+Public Attributes | |
| +uint32_t | _kernelCnt |
| +hc::accelerator_view | _av |
Public Attributes inherited from LockedBase< MUTEX_TYPE > | |
| +MUTEX_TYPE | _mutex |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipStreamCriticalBase__t.png b/docs/RuntimeAPI/html/classihipStreamCriticalBase__t.png
new file mode 100644
index 0000000000..4d8990f4ca
Binary files /dev/null and b/docs/RuntimeAPI/html/classihipStreamCriticalBase__t.png differ
diff --git a/docs/RuntimeAPI/html/classihipStream__t-members.html b/docs/RuntimeAPI/html/classihipStream__t-members.html
new file mode 100644
index 0000000000..2b1739efbf
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipStream__t-members.html
@@ -0,0 +1,124 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipStream_t, including all inherited members.
+| _flags (defined in ihipStream_t) | ihipStream_t | |
| _id (defined in ihipStream_t) | ihipStream_t | |
| Auto enum value (defined in ihipStream_t) | ihipStream_t | |
| getCtx() const (defined in ihipStream_t) | ihipStream_t | |
| getDevice() const (defined in ihipStream_t) | ihipStream_t | |
| hipStreamQuery(hipStream_t) | ihipStream_t | friend |
| ihipStream_t(ihipCtx_t *ctx, hc::accelerator_view av, unsigned int flags) (defined in ihipStream_t) | ihipStream_t | |
| launchModuleKernel(hc::accelerator_view av, hsa_signal_t signal, uint32_t blockDimX, uint32_t blockDimY, uint32_t blockDimZ, uint32_t gridDimX, uint32_t gridDimY, uint32_t gridDimZ, uint32_t groupSegmentSize, uint32_t sharedMemBytes, void *kernarg, size_t kernSize, uint64_t kernel) (defined in ihipStream_t) | ihipStream_t | |
| lockclose_postKernelCommand(const char *kernelName, hc::accelerator_view *av) (defined in ihipStream_t) | ihipStream_t | |
| locked_copyAsync(void *dst, const void *src, size_t sizeBytes, unsigned kind) (defined in ihipStream_t) | ihipStream_t | |
| locked_copySync(void *dst, const void *src, size_t sizeBytes, unsigned kind, bool resolveOn=true) (defined in ihipStream_t) | ihipStream_t | |
| locked_getAv() (defined in ihipStream_t) | ihipStream_t | inline |
| locked_recordEvent(hipEvent_t event) (defined in ihipStream_t) | ihipStream_t | |
| locked_wait(bool assertQueueEmpty=false) (defined in ihipStream_t) | ihipStream_t | |
| locked_waitEvent(hipEvent_t event) (defined in ihipStream_t) | ihipStream_t | |
| lockopen_preKernelCommand() (defined in ihipStream_t) | ihipStream_t | |
| operator<< (defined in ihipStream_t) | ihipStream_t | friend |
| ScheduleMode enum name (defined in ihipStream_t) | ihipStream_t | |
| SeqNum_t typedef (defined in ihipStream_t) | ihipStream_t | |
| Spin enum value (defined in ihipStream_t) | ihipStream_t | |
| wait(LockedAccessor_StreamCrit_t &crit, bool assertQueueEmpty=false) (defined in ihipStream_t) | ihipStream_t | |
| Yield enum value (defined in ihipStream_t) | ihipStream_t | |
| ~ihipStream_t() (defined in ihipStream_t) | ihipStream_t |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/classihipStream__t.html b/docs/RuntimeAPI/html/classihipStream__t.html
new file mode 100644
index 0000000000..9b06ac3bc4
--- /dev/null
+++ b/docs/RuntimeAPI/html/classihipStream__t.html
@@ -0,0 +1,216 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Types | |
| enum | ScheduleMode { Auto, +Spin, +Yield + } |
| +typedef uint64_t | SeqNum_t |
+Public Member Functions | |
| + | ihipStream_t (ihipCtx_t *ctx, hc::accelerator_view av, unsigned int flags) |
| +void | locked_copySync (void *dst, const void *src, size_t sizeBytes, unsigned kind, bool resolveOn=true) |
| +void | locked_copyAsync (void *dst, const void *src, size_t sizeBytes, unsigned kind) |
| +LockedAccessor_StreamCrit_t | lockopen_preKernelCommand () |
| +void | lockclose_postKernelCommand (const char *kernelName, hc::accelerator_view *av) |
| +void | locked_wait (bool assertQueueEmpty=false) |
| +hc::accelerator_view * | locked_getAv () |
| +void | locked_waitEvent (hipEvent_t event) |
| +void | locked_recordEvent (hipEvent_t event) |
| +void | wait (LockedAccessor_StreamCrit_t &crit, bool assertQueueEmpty=false) |
| +void | launchModuleKernel (hc::accelerator_view av, hsa_signal_t signal, uint32_t blockDimX, uint32_t blockDimY, uint32_t blockDimZ, uint32_t gridDimX, uint32_t gridDimY, uint32_t gridDimZ, uint32_t groupSegmentSize, uint32_t sharedMemBytes, void *kernarg, size_t kernSize, uint64_t kernel) |
| +const ihipDevice_t * | getDevice () const |
| +ihipCtx_t * | getCtx () const |
+Public Attributes | |
| +SeqNum_t | _id |
| +unsigned | _flags |
+Friends | |
| +std::ostream & | operator<< (std::ostream &os, const ihipStream_t &s) |
| hipError_t | hipStreamQuery (hipStream_t) |
Return hipSuccess if all of the operations in the specified stream have completed, or hipErrorNotReady if not. More... | |
+
|
+ +friend | +
Return hipSuccess if all of the operations in the specified stream have completed, or hipErrorNotReady if not.
| [in] | stream | stream to query |
This is thread-safe and returns a snapshot of the current state of the queue. However, if other host threads are sending work to the stream, the status may change immediately after the function is called. It is typically used for debug.
+ + +
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/closed.png b/docs/RuntimeAPI/html/closed.png
new file mode 100644
index 0000000000..98cc2c909d
Binary files /dev/null and b/docs/RuntimeAPI/html/closed.png differ
diff --git a/docs/RuntimeAPI/html/deprecated.html b/docs/RuntimeAPI/html/deprecated.html
new file mode 100644
index 0000000000..3511316256
--- /dev/null
+++ b/docs/RuntimeAPI/html/deprecated.html
@@ -0,0 +1,98 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/device__util_8h_source.html b/docs/RuntimeAPI/html/device__util_8h_source.html
new file mode 100644
index 0000000000..7b1dbfd91e
--- /dev/null
+++ b/docs/RuntimeAPI/html/device__util_8h_source.html
@@ -0,0 +1,138 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/dir_68267d1309a1af8e8297ef4c3efbcdba.html b/docs/RuntimeAPI/html/dir_68267d1309a1af8e8297ef4c3efbcdba.html
new file mode 100644
index 0000000000..96d309a573
--- /dev/null
+++ b/docs/RuntimeAPI/html/dir_68267d1309a1af8e8297ef4c3efbcdba.html
@@ -0,0 +1,130 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Files | |
| file | device_util.cpp |
| file | device_util.h [code] |
| file | hip_context.cpp |
| file | hip_device.cpp |
| file | hip_error.cpp |
| file | hip_event.cpp |
| file | hip_fp16.cpp |
| file | hip_hcc.cpp |
| file | hip_hcc.h [code] |
| file | hip_ldg.cpp |
| file | hip_memory.cpp |
| file | hip_module.cpp |
| file | hip_peer.cpp |
| file | hip_stream.cpp |
| file | hip_util.h [code] |
| file | trace_helper.h [code] |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/dir_82c4e5e99cd964a390bd8b007f79d8a6.html b/docs/RuntimeAPI/html/dir_82c4e5e99cd964a390bd8b007f79d8a6.html
new file mode 100644
index 0000000000..15a657aa89
--- /dev/null
+++ b/docs/RuntimeAPI/html/dir_82c4e5e99cd964a390bd8b007f79d8a6.html
@@ -0,0 +1,121 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Directories | |
| directory | hcc_detail |
+Files | |
| file | hcc.h [code] |
| file | hip_common.h [code] |
| file | hip_complex.h [code] |
| file | hip_fp16.h [code] |
| file | hip_profile.h [code] |
| file | hip_runtime.h [code] |
| file | hip_runtime_api.h [code] |
| file | hip_texture.h [code] |
| file | hip_vector_types.h [code] |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/dir_ce4f9d092cd8b82b7c46cef8ba457558.html b/docs/RuntimeAPI/html/dir_ce4f9d092cd8b82b7c46cef8ba457558.html
new file mode 100644
index 0000000000..64041d944b
--- /dev/null
+++ b/docs/RuntimeAPI/html/dir_ce4f9d092cd8b82b7c46cef8ba457558.html
@@ -0,0 +1,121 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Files | |
| file | hcc_acc.h [code] |
| file | hip_complex.h [code] |
| file | hip_fp16.h [code] |
| file | hip_ldg.h [code] |
| file | hip_runtime.h [code] |
| Contains definitions of APIs for HIP runtime. | |
| file | hip_runtime_api.h [code] |
| Contains C function APIs for HIP runtime. This file does not use any HCC builtin or special language extensions (-hc mode) ; those functions in hip_runtime.h. | |
| file | hip_texture.h [code] |
| HIP C++ Texture API for hcc compiler. | |
| file | hip_vector_types.h [code] |
| Defines the different newt vector types for HIP runtime. | |
| file | host_defines.h [code] |
| TODO-doc. | |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/dir_d44c64559bbebec7f509842c48db8b23.html b/docs/RuntimeAPI/html/dir_d44c64559bbebec7f509842c48db8b23.html
new file mode 100644
index 0000000000..719a287cc7
--- /dev/null
+++ b/docs/RuntimeAPI/html/dir_d44c64559bbebec7f509842c48db8b23.html
@@ -0,0 +1,100 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Directories | |
| directory | hip |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/doxygen.css b/docs/RuntimeAPI/html/doxygen.css
new file mode 100644
index 0000000000..f0f36f89f5
--- /dev/null
+++ b/docs/RuntimeAPI/html/doxygen.css
@@ -0,0 +1,1366 @@
+/* The standard CSS for doxygen 1.8.6 */
+
+body, table, div, p, dl {
+ font: 400 14px/22px Roboto,sans-serif;
+}
+
+/* @group Heading Levels */
+
+h1.groupheader {
+ font-size: 150%;
+}
+
+.title {
+ font: 400 14px/28px Roboto,sans-serif;
+ font-size: 150%;
+ font-weight: bold;
+ margin: 10px 2px;
+}
+
+h2.groupheader {
+ border-bottom: 1px solid #879ECB;
+ color: #354C7B;
+ font-size: 150%;
+ font-weight: normal;
+ margin-top: 1.75em;
+ padding-top: 8px;
+ padding-bottom: 4px;
+ width: 100%;
+}
+
+h3.groupheader {
+ font-size: 100%;
+}
+
+h1, h2, h3, h4, h5, h6 {
+ -webkit-transition: text-shadow 0.5s linear;
+ -moz-transition: text-shadow 0.5s linear;
+ -ms-transition: text-shadow 0.5s linear;
+ -o-transition: text-shadow 0.5s linear;
+ transition: text-shadow 0.5s linear;
+ margin-right: 15px;
+}
+
+h1.glow, h2.glow, h3.glow, h4.glow, h5.glow, h6.glow {
+ text-shadow: 0 0 15px cyan;
+}
+
+dt {
+ font-weight: bold;
+}
+
+div.multicol {
+ -moz-column-gap: 1em;
+ -webkit-column-gap: 1em;
+ -moz-column-count: 3;
+ -webkit-column-count: 3;
+}
+
+p.startli, p.startdd {
+ margin-top: 2px;
+}
+
+p.starttd {
+ margin-top: 0px;
+}
+
+p.endli {
+ margin-bottom: 0px;
+}
+
+p.enddd {
+ margin-bottom: 4px;
+}
+
+p.endtd {
+ margin-bottom: 2px;
+}
+
+/* @end */
+
+caption {
+ font-weight: bold;
+}
+
+span.legend {
+ font-size: 70%;
+ text-align: center;
+}
+
+h3.version {
+ font-size: 90%;
+ text-align: center;
+}
+
+div.qindex, div.navtab{
+ background-color: #EBEFF6;
+ border: 1px solid #A3B4D7;
+ text-align: center;
+}
+
+div.qindex, div.navpath {
+ width: 100%;
+ line-height: 140%;
+}
+
+div.navtab {
+ margin-right: 15px;
+}
+
+/* @group Link Styling */
+
+a {
+ color: #3D578C;
+ font-weight: normal;
+ text-decoration: none;
+}
+
+.contents a:visited {
+ color: #4665A2;
+}
+
+a:hover {
+ text-decoration: underline;
+}
+
+a.qindex {
+ font-weight: bold;
+}
+
+a.qindexHL {
+ font-weight: bold;
+ background-color: #9CAFD4;
+ color: #ffffff;
+ border: 1px double #869DCA;
+}
+
+.contents a.qindexHL:visited {
+ color: #ffffff;
+}
+
+a.el {
+ font-weight: bold;
+}
+
+a.elRef {
+}
+
+a.code, a.code:visited, a.line, a.line:visited {
+ color: #4665A2;
+}
+
+a.codeRef, a.codeRef:visited, a.lineRef, a.lineRef:visited {
+ color: #4665A2;
+}
+
+/* @end */
+
+dl.el {
+ margin-left: -1cm;
+}
+
+pre.fragment {
+ border: 1px solid #C4CFE5;
+ background-color: #FBFCFD;
+ padding: 4px 6px;
+ margin: 4px 8px 4px 2px;
+ overflow: auto;
+ word-wrap: break-word;
+ font-size: 9pt;
+ line-height: 125%;
+ font-family: monospace, fixed;
+ font-size: 105%;
+}
+
+div.fragment {
+ padding: 4px 6px;
+ margin: 4px 8px 4px 2px;
+ background-color: #FBFCFD;
+ border: 1px solid #C4CFE5;
+}
+
+div.line {
+ font-family: monospace, fixed;
+ font-size: 13px;
+ min-height: 13px;
+ line-height: 1.0;
+ text-wrap: unrestricted;
+ white-space: -moz-pre-wrap; /* Moz */
+ white-space: -pre-wrap; /* Opera 4-6 */
+ white-space: -o-pre-wrap; /* Opera 7 */
+ white-space: pre-wrap; /* CSS3 */
+ word-wrap: break-word; /* IE 5.5+ */
+ text-indent: -53px;
+ padding-left: 53px;
+ padding-bottom: 0px;
+ margin: 0px;
+ -webkit-transition-property: background-color, box-shadow;
+ -webkit-transition-duration: 0.5s;
+ -moz-transition-property: background-color, box-shadow;
+ -moz-transition-duration: 0.5s;
+ -ms-transition-property: background-color, box-shadow;
+ -ms-transition-duration: 0.5s;
+ -o-transition-property: background-color, box-shadow;
+ -o-transition-duration: 0.5s;
+ transition-property: background-color, box-shadow;
+ transition-duration: 0.5s;
+}
+
+div.line.glow {
+ background-color: cyan;
+ box-shadow: 0 0 10px cyan;
+}
+
+
+span.lineno {
+ padding-right: 4px;
+ text-align: right;
+ border-right: 2px solid #0F0;
+ background-color: #E8E8E8;
+ white-space: pre;
+}
+span.lineno a {
+ background-color: #D8D8D8;
+}
+
+span.lineno a:hover {
+ background-color: #C8C8C8;
+}
+
+div.ah {
+ background-color: black;
+ font-weight: bold;
+ color: #ffffff;
+ margin-bottom: 3px;
+ margin-top: 3px;
+ padding: 0.2em;
+ border: solid thin #333;
+ border-radius: 0.5em;
+ -webkit-border-radius: .5em;
+ -moz-border-radius: .5em;
+ box-shadow: 2px 2px 3px #999;
+ -webkit-box-shadow: 2px 2px 3px #999;
+ -moz-box-shadow: rgba(0, 0, 0, 0.15) 2px 2px 2px;
+ background-image: -webkit-gradient(linear, left top, left bottom, from(#eee), to(#000),color-stop(0.3, #444));
+ background-image: -moz-linear-gradient(center top, #eee 0%, #444 40%, #000);
+}
+
+div.groupHeader {
+ margin-left: 16px;
+ margin-top: 12px;
+ font-weight: bold;
+}
+
+div.groupText {
+ margin-left: 16px;
+ font-style: italic;
+}
+
+body {
+ background-color: white;
+ color: black;
+ margin: 0;
+}
+
+div.contents {
+ margin-top: 10px;
+ margin-left: 12px;
+ margin-right: 8px;
+}
+
+td.indexkey {
+ background-color: #EBEFF6;
+ font-weight: bold;
+ border: 1px solid #C4CFE5;
+ margin: 2px 0px 2px 0;
+ padding: 2px 10px;
+ white-space: nowrap;
+ vertical-align: top;
+}
+
+td.indexvalue {
+ background-color: #EBEFF6;
+ border: 1px solid #C4CFE5;
+ padding: 2px 10px;
+ margin: 2px 0px;
+}
+
+tr.memlist {
+ background-color: #EEF1F7;
+}
+
+p.formulaDsp {
+ text-align: center;
+}
+
+img.formulaDsp {
+
+}
+
+img.formulaInl {
+ vertical-align: middle;
+}
+
+div.center {
+ text-align: center;
+ margin-top: 0px;
+ margin-bottom: 0px;
+ padding: 0px;
+}
+
+div.center img {
+ border: 0px;
+}
+
+address.footer {
+ text-align: right;
+ padding-right: 12px;
+}
+
+img.footer {
+ border: 0px;
+ vertical-align: middle;
+}
+
+/* @group Code Colorization */
+
+span.keyword {
+ color: #008000
+}
+
+span.keywordtype {
+ color: #604020
+}
+
+span.keywordflow {
+ color: #e08000
+}
+
+span.comment {
+ color: #800000
+}
+
+span.preprocessor {
+ color: #806020
+}
+
+span.stringliteral {
+ color: #002080
+}
+
+span.charliteral {
+ color: #008080
+}
+
+span.vhdldigit {
+ color: #ff00ff
+}
+
+span.vhdlchar {
+ color: #000000
+}
+
+span.vhdlkeyword {
+ color: #700070
+}
+
+span.vhdllogic {
+ color: #ff0000
+}
+
+blockquote {
+ background-color: #F7F8FB;
+ border-left: 2px solid #9CAFD4;
+ margin: 0 24px 0 4px;
+ padding: 0 12px 0 16px;
+}
+
+/* @end */
+
+/*
+.search {
+ color: #003399;
+ font-weight: bold;
+}
+
+form.search {
+ margin-bottom: 0px;
+ margin-top: 0px;
+}
+
+input.search {
+ font-size: 75%;
+ color: #000080;
+ font-weight: normal;
+ background-color: #e8eef2;
+}
+*/
+
+td.tiny {
+ font-size: 75%;
+}
+
+.dirtab {
+ padding: 4px;
+ border-collapse: collapse;
+ border: 1px solid #A3B4D7;
+}
+
+th.dirtab {
+ background: #EBEFF6;
+ font-weight: bold;
+}
+
+hr {
+ height: 0px;
+ border: none;
+ border-top: 1px solid #4A6AAA;
+}
+
+hr.footer {
+ height: 1px;
+}
+
+/* @group Member Descriptions */
+
+table.memberdecls {
+ border-spacing: 0px;
+ padding: 0px;
+}
+
+.memberdecls td, .fieldtable tr {
+ -webkit-transition-property: background-color, box-shadow;
+ -webkit-transition-duration: 0.5s;
+ -moz-transition-property: background-color, box-shadow;
+ -moz-transition-duration: 0.5s;
+ -ms-transition-property: background-color, box-shadow;
+ -ms-transition-duration: 0.5s;
+ -o-transition-property: background-color, box-shadow;
+ -o-transition-duration: 0.5s;
+ transition-property: background-color, box-shadow;
+ transition-duration: 0.5s;
+}
+
+.memberdecls td.glow, .fieldtable tr.glow {
+ background-color: cyan;
+ box-shadow: 0 0 15px cyan;
+}
+
+.mdescLeft, .mdescRight,
+.memItemLeft, .memItemRight,
+.memTemplItemLeft, .memTemplItemRight, .memTemplParams {
+ background-color: #F9FAFC;
+ border: none;
+ margin: 4px;
+ padding: 1px 0 0 8px;
+}
+
+.mdescLeft, .mdescRight {
+ padding: 0px 8px 4px 8px;
+ color: #555;
+}
+
+.memSeparator {
+ border-bottom: 1px solid #DEE4F0;
+ line-height: 1px;
+ margin: 0px;
+ padding: 0px;
+}
+
+.memItemLeft, .memTemplItemLeft {
+ white-space: nowrap;
+}
+
+.memItemRight {
+ width: 100%;
+}
+
+.memTemplParams {
+ color: #4665A2;
+ white-space: nowrap;
+ font-size: 80%;
+}
+
+/* @end */
+
+/* @group Member Details */
+
+/* Styles for detailed member documentation */
+
+.memtemplate {
+ font-size: 80%;
+ color: #4665A2;
+ font-weight: normal;
+ margin-left: 9px;
+}
+
+.memnav {
+ background-color: #EBEFF6;
+ border: 1px solid #A3B4D7;
+ text-align: center;
+ margin: 2px;
+ margin-right: 15px;
+ padding: 2px;
+}
+
+.mempage {
+ width: 100%;
+}
+
+.memitem {
+ padding: 0;
+ margin-bottom: 10px;
+ margin-right: 5px;
+ -webkit-transition: box-shadow 0.5s linear;
+ -moz-transition: box-shadow 0.5s linear;
+ -ms-transition: box-shadow 0.5s linear;
+ -o-transition: box-shadow 0.5s linear;
+ transition: box-shadow 0.5s linear;
+ display: table !important;
+ width: 100%;
+}
+
+.memitem.glow {
+ box-shadow: 0 0 15px cyan;
+}
+
+.memname {
+ font-weight: bold;
+ margin-left: 6px;
+}
+
+.memname td {
+ vertical-align: bottom;
+}
+
+.memproto, dl.reflist dt {
+ border-top: 1px solid #A8B8D9;
+ border-left: 1px solid #A8B8D9;
+ border-right: 1px solid #A8B8D9;
+ padding: 6px 0px 6px 0px;
+ color: #253555;
+ font-weight: bold;
+ text-shadow: 0px 1px 1px rgba(255, 255, 255, 0.9);
+ background-image:url('nav_f.png');
+ background-repeat:repeat-x;
+ background-color: #E2E8F2;
+ /* opera specific markup */
+ box-shadow: 5px 5px 5px rgba(0, 0, 0, 0.15);
+ border-top-right-radius: 4px;
+ border-top-left-radius: 4px;
+ /* firefox specific markup */
+ -moz-box-shadow: rgba(0, 0, 0, 0.15) 5px 5px 5px;
+ -moz-border-radius-topright: 4px;
+ -moz-border-radius-topleft: 4px;
+ /* webkit specific markup */
+ -webkit-box-shadow: 5px 5px 5px rgba(0, 0, 0, 0.15);
+ -webkit-border-top-right-radius: 4px;
+ -webkit-border-top-left-radius: 4px;
+
+}
+
+.memdoc, dl.reflist dd {
+ border-bottom: 1px solid #A8B8D9;
+ border-left: 1px solid #A8B8D9;
+ border-right: 1px solid #A8B8D9;
+ padding: 6px 10px 2px 10px;
+ background-color: #FBFCFD;
+ border-top-width: 0;
+ background-image:url('nav_g.png');
+ background-repeat:repeat-x;
+ background-color: #FFFFFF;
+ /* opera specific markup */
+ border-bottom-left-radius: 4px;
+ border-bottom-right-radius: 4px;
+ box-shadow: 5px 5px 5px rgba(0, 0, 0, 0.15);
+ /* firefox specific markup */
+ -moz-border-radius-bottomleft: 4px;
+ -moz-border-radius-bottomright: 4px;
+ -moz-box-shadow: rgba(0, 0, 0, 0.15) 5px 5px 5px;
+ /* webkit specific markup */
+ -webkit-border-bottom-left-radius: 4px;
+ -webkit-border-bottom-right-radius: 4px;
+ -webkit-box-shadow: 5px 5px 5px rgba(0, 0, 0, 0.15);
+}
+
+dl.reflist dt {
+ padding: 5px;
+}
+
+dl.reflist dd {
+ margin: 0px 0px 10px 0px;
+ padding: 5px;
+}
+
+.paramkey {
+ text-align: right;
+}
+
+.paramtype {
+ white-space: nowrap;
+}
+
+.paramname {
+ color: #602020;
+ white-space: nowrap;
+}
+.paramname em {
+ font-style: normal;
+}
+.paramname code {
+ line-height: 14px;
+}
+
+.params, .retval, .exception, .tparams {
+ margin-left: 0px;
+ padding-left: 0px;
+}
+
+.params .paramname, .retval .paramname {
+ font-weight: bold;
+ vertical-align: top;
+}
+
+.params .paramtype {
+ font-style: italic;
+ vertical-align: top;
+}
+
+.params .paramdir {
+ font-family: "courier new",courier,monospace;
+ vertical-align: top;
+}
+
+table.mlabels {
+ border-spacing: 0px;
+}
+
+td.mlabels-left {
+ width: 100%;
+ padding: 0px;
+}
+
+td.mlabels-right {
+ vertical-align: bottom;
+ padding: 0px;
+ white-space: nowrap;
+}
+
+span.mlabels {
+ margin-left: 8px;
+}
+
+span.mlabel {
+ background-color: #728DC1;
+ border-top:1px solid #5373B4;
+ border-left:1px solid #5373B4;
+ border-right:1px solid #C4CFE5;
+ border-bottom:1px solid #C4CFE5;
+ text-shadow: none;
+ color: white;
+ margin-right: 4px;
+ padding: 2px 3px;
+ border-radius: 3px;
+ font-size: 7pt;
+ white-space: nowrap;
+ vertical-align: middle;
+}
+
+
+
+/* @end */
+
+/* these are for tree view when not used as main index */
+
+div.directory {
+ margin: 10px 0px;
+ border-top: 1px solid #A8B8D9;
+ border-bottom: 1px solid #A8B8D9;
+ width: 100%;
+}
+
+.directory table {
+ border-collapse:collapse;
+}
+
+.directory td {
+ margin: 0px;
+ padding: 0px;
+ vertical-align: top;
+}
+
+.directory td.entry {
+ white-space: nowrap;
+ padding-right: 6px;
+ padding-top: 3px;
+}
+
+.directory td.entry a {
+ outline:none;
+}
+
+.directory td.entry a img {
+ border: none;
+}
+
+.directory td.desc {
+ width: 100%;
+ padding-left: 6px;
+ padding-right: 6px;
+ padding-top: 3px;
+ border-left: 1px solid rgba(0,0,0,0.05);
+}
+
+.directory tr.even {
+ padding-left: 6px;
+ background-color: #F7F8FB;
+}
+
+.directory img {
+ vertical-align: -30%;
+}
+
+.directory .levels {
+ white-space: nowrap;
+ width: 100%;
+ text-align: right;
+ font-size: 9pt;
+}
+
+.directory .levels span {
+ cursor: pointer;
+ padding-left: 2px;
+ padding-right: 2px;
+ color: #3D578C;
+}
+
+div.dynheader {
+ margin-top: 8px;
+ -webkit-touch-callout: none;
+ -webkit-user-select: none;
+ -khtml-user-select: none;
+ -moz-user-select: none;
+ -ms-user-select: none;
+ user-select: none;
+}
+
+address {
+ font-style: normal;
+ color: #2A3D61;
+}
+
+table.doxtable {
+ border-collapse:collapse;
+ margin-top: 4px;
+ margin-bottom: 4px;
+}
+
+table.doxtable td, table.doxtable th {
+ border: 1px solid #2D4068;
+ padding: 3px 7px 2px;
+}
+
+table.doxtable th {
+ background-color: #374F7F;
+ color: #FFFFFF;
+ font-size: 110%;
+ padding-bottom: 4px;
+ padding-top: 5px;
+}
+
+table.fieldtable {
+ /*width: 100%;*/
+ margin-bottom: 10px;
+ border: 1px solid #A8B8D9;
+ border-spacing: 0px;
+ -moz-border-radius: 4px;
+ -webkit-border-radius: 4px;
+ border-radius: 4px;
+ -moz-box-shadow: rgba(0, 0, 0, 0.15) 2px 2px 2px;
+ -webkit-box-shadow: 2px 2px 2px rgba(0, 0, 0, 0.15);
+ box-shadow: 2px 2px 2px rgba(0, 0, 0, 0.15);
+}
+
+.fieldtable td, .fieldtable th {
+ padding: 3px 7px 2px;
+}
+
+.fieldtable td.fieldtype, .fieldtable td.fieldname {
+ white-space: nowrap;
+ border-right: 1px solid #A8B8D9;
+ border-bottom: 1px solid #A8B8D9;
+ vertical-align: top;
+}
+
+.fieldtable td.fieldname {
+ padding-top: 3px;
+}
+
+.fieldtable td.fielddoc {
+ border-bottom: 1px solid #A8B8D9;
+ /*width: 100%;*/
+}
+
+.fieldtable td.fielddoc p:first-child {
+ margin-top: 0px;
+}
+
+.fieldtable td.fielddoc p:last-child {
+ margin-bottom: 2px;
+}
+
+.fieldtable tr:last-child td {
+ border-bottom: none;
+}
+
+.fieldtable th {
+ background-image:url('nav_f.png');
+ background-repeat:repeat-x;
+ background-color: #E2E8F2;
+ font-size: 90%;
+ color: #253555;
+ padding-bottom: 4px;
+ padding-top: 5px;
+ text-align:left;
+ -moz-border-radius-topleft: 4px;
+ -moz-border-radius-topright: 4px;
+ -webkit-border-top-left-radius: 4px;
+ -webkit-border-top-right-radius: 4px;
+ border-top-left-radius: 4px;
+ border-top-right-radius: 4px;
+ border-bottom: 1px solid #A8B8D9;
+}
+
+
+.tabsearch {
+ top: 0px;
+ left: 10px;
+ height: 36px;
+ background-image: url('tab_b.png');
+ z-index: 101;
+ overflow: hidden;
+ font-size: 13px;
+}
+
+.navpath ul
+{
+ font-size: 11px;
+ background-image:url('tab_b.png');
+ background-repeat:repeat-x;
+ background-position: 0 -5px;
+ height:30px;
+ line-height:30px;
+ color:#8AA0CC;
+ border:solid 1px #C2CDE4;
+ overflow:hidden;
+ margin:0px;
+ padding:0px;
+}
+
+.navpath li
+{
+ list-style-type:none;
+ float:left;
+ padding-left:10px;
+ padding-right:15px;
+ background-image:url('bc_s.png');
+ background-repeat:no-repeat;
+ background-position:right;
+ color:#364D7C;
+}
+
+.navpath li.navelem a
+{
+ height:32px;
+ display:block;
+ text-decoration: none;
+ outline: none;
+ color: #283A5D;
+ font-family: 'Lucida Grande',Geneva,Helvetica,Arial,sans-serif;
+ text-shadow: 0px 1px 1px rgba(255, 255, 255, 0.9);
+ text-decoration: none;
+}
+
+.navpath li.navelem a:hover
+{
+ color:#6884BD;
+}
+
+.navpath li.footer
+{
+ list-style-type:none;
+ float:right;
+ padding-left:10px;
+ padding-right:15px;
+ background-image:none;
+ background-repeat:no-repeat;
+ background-position:right;
+ color:#364D7C;
+ font-size: 8pt;
+}
+
+
+div.summary
+{
+ float: right;
+ font-size: 8pt;
+ padding-right: 5px;
+ width: 50%;
+ text-align: right;
+}
+
+div.summary a
+{
+ white-space: nowrap;
+}
+
+div.ingroups
+{
+ font-size: 8pt;
+ width: 50%;
+ text-align: left;
+}
+
+div.ingroups a
+{
+ white-space: nowrap;
+}
+
+div.header
+{
+ background-image:url('nav_h.png');
+ background-repeat:repeat-x;
+ background-color: #F9FAFC;
+ margin: 0px;
+ border-bottom: 1px solid #C4CFE5;
+}
+
+div.headertitle
+{
+ padding: 5px 5px 5px 10px;
+}
+
+dl
+{
+ padding: 0 0 0 10px;
+}
+
+/* dl.note, dl.warning, dl.attention, dl.pre, dl.post, dl.invariant, dl.deprecated, dl.todo, dl.test, dl.bug */
+dl.section
+{
+ margin-left: 0px;
+ padding-left: 0px;
+}
+
+dl.note
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #D0C000;
+}
+
+dl.warning, dl.attention
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #FF0000;
+}
+
+dl.pre, dl.post, dl.invariant
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #00D000;
+}
+
+dl.deprecated
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #505050;
+}
+
+dl.todo
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #00C0E0;
+}
+
+dl.test
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #3030E0;
+}
+
+dl.bug
+{
+ margin-left:-7px;
+ padding-left: 3px;
+ border-left:4px solid;
+ border-color: #C08050;
+}
+
+dl.section dd {
+ margin-bottom: 6px;
+}
+
+
+#projectlogo
+{
+ text-align: center;
+ vertical-align: bottom;
+ border-collapse: separate;
+}
+
+#projectlogo img
+{
+ border: 0px none;
+}
+
+#projectname
+{
+ font: 300% Tahoma, Arial,sans-serif;
+ margin: 0px;
+ padding: 2px 0px;
+}
+
+#projectbrief
+{
+ font: 120% Tahoma, Arial,sans-serif;
+ margin: 0px;
+ padding: 0px;
+}
+
+#projectnumber
+{
+ font: 50% Tahoma, Arial,sans-serif;
+ margin: 0px;
+ padding: 0px;
+}
+
+#titlearea
+{
+ padding: 0px;
+ margin: 0px;
+ width: 100%;
+ border-bottom: 1px solid #5373B4;
+}
+
+.image
+{
+ text-align: center;
+}
+
+.dotgraph
+{
+ text-align: center;
+}
+
+.mscgraph
+{
+ text-align: center;
+}
+
+.diagraph
+{
+ text-align: center;
+}
+
+.caption
+{
+ font-weight: bold;
+}
+
+div.zoom
+{
+ border: 1px solid #90A5CE;
+}
+
+dl.citelist {
+ margin-bottom:50px;
+}
+
+dl.citelist dt {
+ color:#334975;
+ float:left;
+ font-weight:bold;
+ margin-right:10px;
+ padding:5px;
+}
+
+dl.citelist dd {
+ margin:2px 0;
+ padding:5px 0;
+}
+
+div.toc {
+ padding: 14px 25px;
+ background-color: #F4F6FA;
+ border: 1px solid #D8DFEE;
+ border-radius: 7px 7px 7px 7px;
+ float: right;
+ height: auto;
+ margin: 0 20px 10px 10px;
+ width: 200px;
+}
+
+div.toc li {
+ background: url("bdwn.png") no-repeat scroll 0 5px transparent;
+ font: 10px/1.2 Verdana,DejaVu Sans,Geneva,sans-serif;
+ margin-top: 5px;
+ padding-left: 10px;
+ padding-top: 2px;
+}
+
+div.toc h3 {
+ font: bold 12px/1.2 Arial,FreeSans,sans-serif;
+ color: #4665A2;
+ border-bottom: 0 none;
+ margin: 0;
+}
+
+div.toc ul {
+ list-style: none outside none;
+ border: medium none;
+ padding: 0px;
+}
+
+div.toc li.level1 {
+ margin-left: 0px;
+}
+
+div.toc li.level2 {
+ margin-left: 15px;
+}
+
+div.toc li.level3 {
+ margin-left: 30px;
+}
+
+div.toc li.level4 {
+ margin-left: 45px;
+}
+
+.inherit_header {
+ font-weight: bold;
+ color: gray;
+ cursor: pointer;
+ -webkit-touch-callout: none;
+ -webkit-user-select: none;
+ -khtml-user-select: none;
+ -moz-user-select: none;
+ -ms-user-select: none;
+ user-select: none;
+}
+
+.inherit_header td {
+ padding: 6px 0px 2px 5px;
+}
+
+.inherit {
+ display: none;
+}
+
+tr.heading h2 {
+ margin-top: 12px;
+ margin-bottom: 4px;
+}
+
+/* tooltip related style info */
+
+.ttc {
+ position: absolute;
+ display: none;
+}
+
+#powerTip {
+ cursor: default;
+ white-space: nowrap;
+ background-color: white;
+ border: 1px solid gray;
+ border-radius: 4px 4px 4px 4px;
+ box-shadow: 1px 1px 7px gray;
+ display: none;
+ font-size: smaller;
+ max-width: 80%;
+ opacity: 0.9;
+ padding: 1ex 1em 1em;
+ position: absolute;
+ z-index: 2147483647;
+}
+
+#powerTip div.ttdoc {
+ color: grey;
+ font-style: italic;
+}
+
+#powerTip div.ttname a {
+ font-weight: bold;
+}
+
+#powerTip div.ttname {
+ font-weight: bold;
+}
+
+#powerTip div.ttdeci {
+ color: #006318;
+}
+
+#powerTip div {
+ margin: 0px;
+ padding: 0px;
+ font: 12px/16px Roboto,sans-serif;
+}
+
+#powerTip:before, #powerTip:after {
+ content: "";
+ position: absolute;
+ margin: 0px;
+}
+
+#powerTip.n:after, #powerTip.n:before,
+#powerTip.s:after, #powerTip.s:before,
+#powerTip.w:after, #powerTip.w:before,
+#powerTip.e:after, #powerTip.e:before,
+#powerTip.ne:after, #powerTip.ne:before,
+#powerTip.se:after, #powerTip.se:before,
+#powerTip.nw:after, #powerTip.nw:before,
+#powerTip.sw:after, #powerTip.sw:before {
+ border: solid transparent;
+ content: " ";
+ height: 0;
+ width: 0;
+ position: absolute;
+}
+
+#powerTip.n:after, #powerTip.s:after,
+#powerTip.w:after, #powerTip.e:after,
+#powerTip.nw:after, #powerTip.ne:after,
+#powerTip.sw:after, #powerTip.se:after {
+ border-color: rgba(255, 255, 255, 0);
+}
+
+#powerTip.n:before, #powerTip.s:before,
+#powerTip.w:before, #powerTip.e:before,
+#powerTip.nw:before, #powerTip.ne:before,
+#powerTip.sw:before, #powerTip.se:before {
+ border-color: rgba(128, 128, 128, 0);
+}
+
+#powerTip.n:after, #powerTip.n:before,
+#powerTip.ne:after, #powerTip.ne:before,
+#powerTip.nw:after, #powerTip.nw:before {
+ top: 100%;
+}
+
+#powerTip.n:after, #powerTip.ne:after, #powerTip.nw:after {
+ border-top-color: #ffffff;
+ border-width: 10px;
+ margin: 0px -10px;
+}
+#powerTip.n:before {
+ border-top-color: #808080;
+ border-width: 11px;
+ margin: 0px -11px;
+}
+#powerTip.n:after, #powerTip.n:before {
+ left: 50%;
+}
+
+#powerTip.nw:after, #powerTip.nw:before {
+ right: 14px;
+}
+
+#powerTip.ne:after, #powerTip.ne:before {
+ left: 14px;
+}
+
+#powerTip.s:after, #powerTip.s:before,
+#powerTip.se:after, #powerTip.se:before,
+#powerTip.sw:after, #powerTip.sw:before {
+ bottom: 100%;
+}
+
+#powerTip.s:after, #powerTip.se:after, #powerTip.sw:after {
+ border-bottom-color: #ffffff;
+ border-width: 10px;
+ margin: 0px -10px;
+}
+
+#powerTip.s:before, #powerTip.se:before, #powerTip.sw:before {
+ border-bottom-color: #808080;
+ border-width: 11px;
+ margin: 0px -11px;
+}
+
+#powerTip.s:after, #powerTip.s:before {
+ left: 50%;
+}
+
+#powerTip.sw:after, #powerTip.sw:before {
+ right: 14px;
+}
+
+#powerTip.se:after, #powerTip.se:before {
+ left: 14px;
+}
+
+#powerTip.e:after, #powerTip.e:before {
+ left: 100%;
+}
+#powerTip.e:after {
+ border-left-color: #ffffff;
+ border-width: 10px;
+ top: 50%;
+ margin-top: -10px;
+}
+#powerTip.e:before {
+ border-left-color: #808080;
+ border-width: 11px;
+ top: 50%;
+ margin-top: -11px;
+}
+
+#powerTip.w:after, #powerTip.w:before {
+ right: 100%;
+}
+#powerTip.w:after {
+ border-right-color: #ffffff;
+ border-width: 10px;
+ top: 50%;
+ margin-top: -10px;
+}
+#powerTip.w:before {
+ border-right-color: #808080;
+ border-width: 11px;
+ top: 50%;
+ margin-top: -11px;
+}
+
+@media print
+{
+ #top { display: none; }
+ #side-nav { display: none; }
+ #nav-path { display: none; }
+ body { overflow:visible; }
+ h1, h2, h3, h4, h5, h6 { page-break-after: avoid; }
+ .summary { display: none; }
+ .memitem { page-break-inside: avoid; }
+ #doc-content
+ {
+ margin-left:0 !important;
+ height:auto !important;
+ width:auto !important;
+ overflow:inherit;
+ display:inline;
+ }
+}
+
diff --git a/docs/RuntimeAPI/html/doxygen.png b/docs/RuntimeAPI/html/doxygen.png
new file mode 100644
index 0000000000..3ff17d807f
Binary files /dev/null and b/docs/RuntimeAPI/html/doxygen.png differ
diff --git a/docs/RuntimeAPI/html/dynsections.js b/docs/RuntimeAPI/html/dynsections.js
new file mode 100644
index 0000000000..ed092c7f63
--- /dev/null
+++ b/docs/RuntimeAPI/html/dynsections.js
@@ -0,0 +1,97 @@
+function toggleVisibility(linkObj)
+{
+ var base = $(linkObj).attr('id');
+ var summary = $('#'+base+'-summary');
+ var content = $('#'+base+'-content');
+ var trigger = $('#'+base+'-trigger');
+ var src=$(trigger).attr('src');
+ if (content.is(':visible')===true) {
+ content.hide();
+ summary.show();
+ $(linkObj).addClass('closed').removeClass('opened');
+ $(trigger).attr('src',src.substring(0,src.length-8)+'closed.png');
+ } else {
+ content.show();
+ summary.hide();
+ $(linkObj).removeClass('closed').addClass('opened');
+ $(trigger).attr('src',src.substring(0,src.length-10)+'open.png');
+ }
+ return false;
+}
+
+function updateStripes()
+{
+ $('table.directory tr').
+ removeClass('even').filter(':visible:even').addClass('even');
+}
+function toggleLevel(level)
+{
+ $('table.directory tr').each(function(){
+ var l = this.id.split('_').length-1;
+ var i = $('#img'+this.id.substring(3));
+ var a = $('#arr'+this.id.substring(3));
+ if (l|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
| Contains definitions of APIs for HIP runtime | |
| Contains C function APIs for HIP runtime. This file does not use any HCC builtin or special language extensions (-hc mode) ; those functions in hip_runtime.h | |
| HIP C++ Texture API for hcc compiler | |
| Defines the different newt vector types for HIP runtime | |
| TODO-doc | |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/ftv2blank.png b/docs/RuntimeAPI/html/ftv2blank.png
new file mode 100644
index 0000000000..63c605bb4c
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2blank.png differ
diff --git a/docs/RuntimeAPI/html/ftv2cl.png b/docs/RuntimeAPI/html/ftv2cl.png
new file mode 100644
index 0000000000..132f6577bf
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2cl.png differ
diff --git a/docs/RuntimeAPI/html/ftv2doc.png b/docs/RuntimeAPI/html/ftv2doc.png
new file mode 100644
index 0000000000..17edabff95
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2doc.png differ
diff --git a/docs/RuntimeAPI/html/ftv2folderclosed.png b/docs/RuntimeAPI/html/ftv2folderclosed.png
new file mode 100644
index 0000000000..bb8ab35edc
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2folderclosed.png differ
diff --git a/docs/RuntimeAPI/html/ftv2folderopen.png b/docs/RuntimeAPI/html/ftv2folderopen.png
new file mode 100644
index 0000000000..d6c7f676a3
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2folderopen.png differ
diff --git a/docs/RuntimeAPI/html/ftv2lastnode.png b/docs/RuntimeAPI/html/ftv2lastnode.png
new file mode 100644
index 0000000000..63c605bb4c
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2lastnode.png differ
diff --git a/docs/RuntimeAPI/html/ftv2link.png b/docs/RuntimeAPI/html/ftv2link.png
new file mode 100644
index 0000000000..17edabff95
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2link.png differ
diff --git a/docs/RuntimeAPI/html/ftv2mlastnode.png b/docs/RuntimeAPI/html/ftv2mlastnode.png
new file mode 100644
index 0000000000..0b63f6d38c
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2mlastnode.png differ
diff --git a/docs/RuntimeAPI/html/ftv2mnode.png b/docs/RuntimeAPI/html/ftv2mnode.png
new file mode 100644
index 0000000000..0b63f6d38c
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2mnode.png differ
diff --git a/docs/RuntimeAPI/html/ftv2mo.png b/docs/RuntimeAPI/html/ftv2mo.png
new file mode 100644
index 0000000000..4bfb80f76e
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2mo.png differ
diff --git a/docs/RuntimeAPI/html/ftv2node.png b/docs/RuntimeAPI/html/ftv2node.png
new file mode 100644
index 0000000000..63c605bb4c
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2node.png differ
diff --git a/docs/RuntimeAPI/html/ftv2ns.png b/docs/RuntimeAPI/html/ftv2ns.png
new file mode 100644
index 0000000000..72e3d71c28
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2ns.png differ
diff --git a/docs/RuntimeAPI/html/ftv2plastnode.png b/docs/RuntimeAPI/html/ftv2plastnode.png
new file mode 100644
index 0000000000..c6ee22f937
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2plastnode.png differ
diff --git a/docs/RuntimeAPI/html/ftv2pnode.png b/docs/RuntimeAPI/html/ftv2pnode.png
new file mode 100644
index 0000000000..c6ee22f937
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2pnode.png differ
diff --git a/docs/RuntimeAPI/html/ftv2splitbar.png b/docs/RuntimeAPI/html/ftv2splitbar.png
new file mode 100644
index 0000000000..fe895f2c58
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2splitbar.png differ
diff --git a/docs/RuntimeAPI/html/ftv2vertline.png b/docs/RuntimeAPI/html/ftv2vertline.png
new file mode 100644
index 0000000000..63c605bb4c
Binary files /dev/null and b/docs/RuntimeAPI/html/ftv2vertline.png differ
diff --git a/docs/RuntimeAPI/html/functions.html b/docs/RuntimeAPI/html/functions.html
new file mode 100644
index 0000000000..ca8882856d
--- /dev/null
+++ b/docs/RuntimeAPI/html/functions.html
@@ -0,0 +1,332 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/functions_rela.html b/docs/RuntimeAPI/html/functions_rela.html
new file mode 100644
index 0000000000..9ddcfb49b4
--- /dev/null
+++ b/docs/RuntimeAPI/html/functions_rela.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/functions_vars.html b/docs/RuntimeAPI/html/functions_vars.html
new file mode 100644
index 0000000000..4569adf399
--- /dev/null
+++ b/docs/RuntimeAPI/html/functions_vars.html
@@ -0,0 +1,329 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/globals.html b/docs/RuntimeAPI/html/globals.html
new file mode 100644
index 0000000000..1bdcacb7ee
--- /dev/null
+++ b/docs/RuntimeAPI/html/globals.html
@@ -0,0 +1,567 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/globals_defs.html b/docs/RuntimeAPI/html/globals_defs.html
new file mode 100644
index 0000000000..6f7178061f
--- /dev/null
+++ b/docs/RuntimeAPI/html/globals_defs.html
@@ -0,0 +1,152 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/globals_enum.html b/docs/RuntimeAPI/html/globals_enum.html
new file mode 100644
index 0000000000..f11ce794d3
--- /dev/null
+++ b/docs/RuntimeAPI/html/globals_enum.html
@@ -0,0 +1,119 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/globals_eval.html b/docs/RuntimeAPI/html/globals_eval.html
new file mode 100644
index 0000000000..c2ff74f32f
--- /dev/null
+++ b/docs/RuntimeAPI/html/globals_eval.html
@@ -0,0 +1,146 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/globals_func.html b/docs/RuntimeAPI/html/globals_func.html
new file mode 100644
index 0000000000..f21de520bb
--- /dev/null
+++ b/docs/RuntimeAPI/html/globals_func.html
@@ -0,0 +1,451 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/globals_type.html b/docs/RuntimeAPI/html/globals_type.html
new file mode 100644
index 0000000000..99b173c22b
--- /dev/null
+++ b/docs/RuntimeAPI/html/globals_type.html
@@ -0,0 +1,119 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__API.html b/docs/RuntimeAPI/html/group__API.html
new file mode 100644
index 0000000000..8a7c5d7c71
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__API.html
@@ -0,0 +1,245 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Modules | |
| Device Management | |
| Error Handling | |
| Stream Management | |
| Event Management | |
| Memory Management | |
| Device Memory Access | |
| Initialization and Version | |
| Control | |
| HCC-Specific Accessors | |
| Texture Reference Management | |
+Functions | |
| hipError_t | hipIpcGetMemHandle (hipIpcMemHandle_t *handle, void *devPtr) |
| Gets an interprocess memory handle for an existing device memory allocation. More... | |
| hipError_t | hipIpcOpenMemHandle (void **devPtr, hipIpcMemHandle_t handle, unsigned int flags) |
| Opens an interprocess memory handle exported from another process and returns a device pointer usable in the local process. More... | |
| hipError_t | hipIpcCloseMemHandle (void *devPtr) |
| Close memory mapped with hipIpcOpenMemHandle. More... | |
Defines the HIP API. See the individual sections for more information.
+| hipError_t hipIpcCloseMemHandle | +( | +void * | +devPtr | ) | ++ |
Close memory mapped with hipIpcOpenMemHandle.
+Unmaps memory returnd by hipIpcOpenMemHandle. The original allocation in the exporting process as well as imported mappings in other processes will be unaffected.
+Any resources used to enable peer access will be freed if this is the last mapping using them.
+| devPtr | - Device pointer returned by hipIpcOpenMemHandle |
| hipError_t hipIpcGetMemHandle | +( | +hipIpcMemHandle_t * | +handle, | +
| + | + | void * | +devPtr | +
| + | ) | ++ |
Gets an interprocess memory handle for an existing device memory allocation.
+Takes a pointer to the base of an existing device memory allocation created with hipMalloc and exports it for use in another process. This is a lightweight operation and may be called multiple times on an allocation without adverse effects.
+If a region of memory is freed with hipFree and a subsequent call to hipMalloc returns memory with the same device address, hipIpcGetMemHandle will return a unique handle for the new memory.
+| handle | - Pointer to user allocated hipIpcMemHandle to return the handle in. |
| devPtr | - Base pointer to previously allocated device memory |
| hipError_t hipIpcOpenMemHandle | +( | +void ** | +devPtr, | +
| + | + | hipIpcMemHandle_t | +handle, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Opens an interprocess memory handle exported from another process and returns a device pointer usable in the local process.
+Maps memory exported from another process with hipIpcGetMemHandle into the current device address space. For contexts on different devices hipIpcOpenMemHandle can attempt to enable peer access between the devices as if the user called hipDeviceEnablePeerAccess. This behavior is controlled by the hipIpcMemLazyEnablePeerAccess flag. hipDeviceCanAccessPeer can determine if a mapping is possible.
+Contexts that may open hipIpcMemHandles are restricted in the following way. hipIpcMemHandles from each device in a given process may only be opened by one context per device per other process.
+Memory returned from hipIpcOpenMemHandle must be freed with hipIpcCloseMemHandle.
+Calling hipFree on an exported memory region before calling hipIpcCloseMemHandle in the importing context will result in undefined behavior.
+| devPtr | - Returned device pointer |
| handle | - hipIpcMemHandle to open |
| flags | - Flags for this operation. Must be specified as hipIpcMemLazyEnablePeerAccess |
*devPtr. In particular, multiple processes may not receive the same address for the same handle.
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Context.html b/docs/RuntimeAPI/html/group__Context.html
new file mode 100644
index 0000000000..7699238778
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Context.html
@@ -0,0 +1,607 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipError_t | hipCtxCreate (hipCtx_t *ctx, unsigned int flags, hipDevice_t device) |
| Create a context and set it as current/ default context. More... | |
| hipError_t | hipCtxDestroy (hipCtx_t ctx) |
| Destroy a HIP context. More... | |
| hipError_t | hipCtxPopCurrent (hipCtx_t *ctx) |
| Pop the current/default context and return the popped context. More... | |
| hipError_t | hipCtxPushCurrent (hipCtx_t ctx) |
| Push the context to be set as current/ default context. More... | |
| hipError_t | hipCtxSetCurrent (hipCtx_t ctx) |
| Set the passed context as current/default. More... | |
| hipError_t | hipCtxGetCurrent (hipCtx_t *ctx) |
| Get the handle of the current/ default context. More... | |
| hipError_t | hipCtxGetDevice (hipDevice_t *device) |
| Get the handle of the device associated with current/default context. More... | |
| hipError_t | hipCtxGetApiVersion (hipCtx_t ctx, int *apiVersion) |
| Returns the approximate HIP api version. More... | |
| hipError_t | hipCtxGetCacheConfig (hipFuncCache_t *cacheConfig) |
| Set Cache configuration for a specific function. More... | |
| hipError_t | hipCtxSetCacheConfig (hipFuncCache_t cacheConfig) |
| Set L1/Shared cache partition. More... | |
| hipError_t | hipCtxSetSharedMemConfig (hipSharedMemConfig config) |
| Set Shared memory bank configuration. More... | |
| hipError_t | hipCtxGetSharedMemConfig (hipSharedMemConfig *pConfig) |
| Get Shared memory bank configuration. More... | |
| hipError_t | hipCtxSynchronize (void) |
| Blocks until the default context has completed all preceding requested tasks. More... | |
| hipError_t | hipCtxGetFlags (unsigned int *flags) |
| Return flags used for creating default context. More... | |
| hipError_t | hipCtxEnablePeerAccess (hipCtx_t peerCtx, unsigned int flags) |
| Enables direct access to memory allocations in a peer context. More... | |
| hipError_t | hipCtxDisablePeerAccess (hipCtx_t peerCtx) |
| Disable direct access from current context's virtual address space to memory allocations physically located on a peer context.Disables direct access to memory allocations in a peer context and unregisters any registered allocations. More... | |
| hipError_t hipCtxCreate | +( | +hipCtx_t * | +ctx, | +
| + | + | unsigned int | +flags, | +
| + | + | hipDevice_t | +device | +
| + | ) | ++ |
Create a context and set it as current/ default context.
+| [out] | ctx | |
| [in] | flags | |
| [in] | associated | device handle |
| hipError_t hipCtxDestroy | +( | +hipCtx_t | +ctx | ) | ++ |
Destroy a HIP context.
+| [in] | ctx | Context to destroy |
| hipError_t hipCtxDisablePeerAccess | +( | +hipCtx_t | +peerCtx | ) | ++ |
Disable direct access from current context's virtual address space to memory allocations physically located on a peer context.Disables direct access to memory allocations in a peer context and unregisters any registered allocations.
+Returns hipErrorPeerAccessNotEnabled if direct access to memory on peerDevice has not yet been enabled from the current device.
+| [in] | peerCtx |
| hipError_t hipCtxEnablePeerAccess | +( | +hipCtx_t | +peerCtx, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Enables direct access to memory allocations in a peer context.
+Memory which already allocated on peer device will be mapped into the address space of the current device. In addition, all future memory allocations on peerDeviceId will be mapped into the address space of the current device when the memory is allocated. The peer memory remains accessible from the current device until a call to hipDeviceDisablePeerAccess or hipDeviceReset.
+| [in] | peerCtx | |
| [in] | flags |
| hipError_t hipCtxGetApiVersion | +( | +hipCtx_t | +ctx, | +
| + | + | int * | +apiVersion | +
| + | ) | ++ |
Returns the approximate HIP api version.
+| [in] | ctx | Context to check |
| [out] | apiVersion |
| hipError_t hipCtxGetCacheConfig | +( | +hipFuncCache_t * | +cacheConfig | ) | ++ |
Set Cache configuration for a specific function.
+| [out] | cacheConfiguration |
| hipError_t hipCtxGetCurrent | +( | +hipCtx_t * | +ctx | ) | ++ |
Get the handle of the current/ default context.
+| [out] | ctx |
| hipError_t hipCtxGetDevice | +( | +hipDevice_t * | +device | ) | ++ |
Get the handle of the device associated with current/default context.
+| [out] | device |
| hipError_t hipCtxGetFlags | +( | +unsigned int * | +flags | ) | ++ |
Return flags used for creating default context.
+| [out] | flags |
| hipError_t hipCtxGetSharedMemConfig | +( | +hipSharedMemConfig * | +pConfig | ) | ++ |
Get Shared memory bank configuration.
+| [out] | sharedMemoryConfiguration |
| hipError_t hipCtxPopCurrent | +( | +hipCtx_t * | +ctx | ) | ++ |
Pop the current/default context and return the popped context.
+| [out] | ctx |
| hipError_t hipCtxPushCurrent | +( | +hipCtx_t | +ctx | ) | ++ |
Push the context to be set as current/ default context.
+| [in] | ctx |
| hipError_t hipCtxSetCacheConfig | +( | +hipFuncCache_t | +cacheConfig | ) | ++ |
Set L1/Shared cache partition.
+| [in] | cacheConfiguration |
| hipError_t hipCtxSetCurrent | +( | +hipCtx_t | +ctx | ) | ++ |
Set the passed context as current/default.
+| [in] | ctx |
| hipError_t hipCtxSetSharedMemConfig | +( | +hipSharedMemConfig | +config | ) | ++ |
Set Shared memory bank configuration.
+| [in] | sharedMemoryConfiguration |
| hipError_t hipCtxSynchronize | +( | +void | +) | ++ |
Blocks until the default context has completed all preceding requested tasks.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Device.html b/docs/RuntimeAPI/html/group__Device.html
new file mode 100644
index 0000000000..e1dddbbed7
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Device.html
@@ -0,0 +1,584 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipError_t | hipDeviceSynchronize (void) |
| Waits on all active streams on current device. More... | |
| hipError_t | hipDeviceReset (void) |
| The state of current device is discarded and updated to a fresh state. More... | |
| hipError_t | hipSetDevice (int deviceId) |
| Set default device to be used for subsequent hip API calls from this thread. More... | |
| hipError_t | hipGetDevice (int *deviceId) |
| Return the default device id for the calling host thread. More... | |
| hipError_t | hipGetDeviceCount (int *count) |
| Return number of compute-capable devices. More... | |
| hipError_t | hipDeviceGetAttribute (int *pi, hipDeviceAttribute_t attr, int deviceId) |
| Query for a specific device attribute. More... | |
| hipError_t | hipGetDeviceProperties (hipDeviceProp_t *prop, int deviceId) |
| Returns device properties. More... | |
| hipError_t | hipDeviceSetCacheConfig (hipFuncCache_t cacheConfig) |
| Set L1/Shared cache partition. More... | |
| hipError_t | hipDeviceGetCacheConfig (hipFuncCache_t *cacheConfig) |
| Set Cache configuration for a specific function. More... | |
| hipError_t | hipDeviceGetLimit (size_t *pValue, hipLimit_t limit) |
| Get Resource limits of current device. More... | |
| hipError_t | hipFuncSetCacheConfig (hipFuncCache_t config) |
| Set Cache configuration for a specific function. More... | |
| hipError_t | hipDeviceGetSharedMemConfig (hipSharedMemConfig *pConfig) |
| Returns bank width of shared memory for current device. More... | |
| hipError_t | hipDeviceSetSharedMemConfig (hipSharedMemConfig config) |
| The bank width of shared memory on current device is set. More... | |
| hipError_t | hipSetDeviceFlags (unsigned flags) |
| The current device behavior is changed according the flags passed. More... | |
| hipError_t | hipChooseDevice (int *device, const hipDeviceProp_t *prop) |
| Device which matches hipDeviceProp_t is returned. More... | |
| hipError_t hipChooseDevice | +( | +int * | +device, | +
| + | + | const hipDeviceProp_t * | +prop | +
| + | ) | ++ |
Device which matches hipDeviceProp_t is returned.
+| [out] | device | ID |
| [in] | device | properties pointer |
| hipError_t hipDeviceGetAttribute | +( | +int * | +pi, | +
| + | + | hipDeviceAttribute_t | +attr, | +
| + | + | int | +deviceId | +
| + | ) | ++ |
Query for a specific device attribute.
+| [out] | pi | pointer to value to return |
| [in] | attr | attribute to query |
| [in] | deviceId | which device to query for information |
| hipError_t hipDeviceGetCacheConfig | +( | +hipFuncCache_t * | +cacheConfig | ) | ++ |
Set Cache configuration for a specific function.
+| [in] | cacheConfig |
| hipError_t hipDeviceGetLimit | +( | +size_t * | +pValue, | +
| + | + | hipLimit_t | +limit | +
| + | ) | ++ |
Get Resource limits of current device.
+| [out] | pValue | |
| [in] | limit |
| hipError_t hipDeviceGetSharedMemConfig | +( | +hipSharedMemConfig * | +pConfig | ) | ++ |
Returns bank width of shared memory for current device.
+| [out] | pConfig |
Note: AMD devices and recent Nvidia GPUS do not support shared cache banking, and the hint is ignored on those architectures.
+ +| hipError_t hipDeviceReset | +( | +void | +) | ++ |
The state of current device is discarded and updated to a fresh state.
+Calling this function deletes all streams created, memory allocated, kernels running, events created. Make sure that no other thread is using the device or streams, memory, kernels, events associated with the current device.
+| hipError_t hipDeviceSetCacheConfig | +( | +hipFuncCache_t | +cacheConfig | ) | ++ |
Set L1/Shared cache partition.
+| [in] | cacheConfig |
| hipError_t hipDeviceSetSharedMemConfig | +( | +hipSharedMemConfig | +config | ) | ++ |
The bank width of shared memory on current device is set.
+| [in] | config |
Note: AMD devices and recent Nvidia GPUS do not support shared cache banking, and the hint is ignored on those architectures.
+ +| hipError_t hipDeviceSynchronize | +( | +void | +) | ++ |
Waits on all active streams on current device.
+When this command is invoked, the host thread gets blocked until all the commands associated with streams associated with the device. HIP does not support multiple blocking modes (yet!).
+| hipError_t hipFuncSetCacheConfig | +( | +hipFuncCache_t | +config | ) | ++ |
Set Cache configuration for a specific function.
+| [in] | config; |
| hipError_t hipGetDevice | +( | +int * | +deviceId | ) | ++ |
Return the default device id for the calling host thread.
+| [out] | device | *device is written with the default device |
HIP maintains an default device for each thread using thread-local-storage. This device is used implicitly for HIP runtime APIs called by this thread. hipGetDevice returns in * device the default device for the calling host thread.
| hipError_t hipGetDeviceCount | +( | +int * | +count | ) | ++ |
Return number of compute-capable devices.
+| [output] | count Returns number of compute-capable devices. |
Returns in *count the number of devices that have ability to run compute commands. If there are no such devices, then hipGetDeviceCount will return hipErrorNoDevice. If 1 or more devices can be found, then hipGetDeviceCount returns hipSuccess.
| hipError_t hipGetDeviceProperties | +( | +hipDeviceProp_t * | +prop, | +
| + | + | int | +deviceId | +
| + | ) | ++ |
Returns device properties.
+| [out] | prop | written with device properties |
| [in] | deviceId | which device to query for information |
HCC always returns 0 for maxThreadsPerMultiProcessor
+HCC always returns 0 for regsPerBlock
+HCC always returns 0 for l2CacheSize
+Populates hipGetDeviceProperties with information for the specified device.
+ +| hipError_t hipSetDevice | +( | +int | +deviceId | ) | ++ |
Set default device to be used for subsequent hip API calls from this thread.
+| [in] | deviceId | Valid device in range 0...hipGetDeviceCount(). |
Sets device as the default device for the calling host thread. Valid device id's are 0... (hipGetDeviceCount()-1).
Many HIP APIs implicitly use the "default device" :
+This function may be called from any host thread. Multiple host threads may use the same device. This function does no synchronization with the previous or new device, and has very little runtime overhead. Applications can use hipSetDevice to quickly switch the default device before making a HIP runtime call which uses the default device.
+The default device is stored in thread-local-storage for each thread. Thread-pool implementations may inherit the default device of the previous thread. A good practice is to always call hipSetDevice at the start of HIP coding sequency to establish a known standard device.
+| hipError_t hipSetDeviceFlags | +( | +unsigned | +flags | ) | ++ |
The current device behavior is changed according the flags passed.
+| [in] | flags | The schedule flags impact how HIP waits for the completion of a command running on a device. hipDeviceScheduleSpin : HIP runtime will actively spin in the thread which submitted the work until the command completes. This offers the lowest latency, but will consume a CPU core and may increase power. hipDeviceScheduleYield : The HIP runtime will yield the CPU to system so that other tasks can use it. This may increase latency to detect the completion but will consume less power and is friendlier to other tasks in the system. hipDeviceScheduleBlockingSync : On ROCm platform, this is a synonym for hipDeviceScheduleYield. hipDeviceScheduleAuto : Use a hueristic to select between Spin and Yield modes. If the number of HIP contexts is greater than the number of logical processors in the system, use Spin scheduling. Else use Yield scheduling. |
hipDeviceMapHost : Allow mapping host memory. On ROCM, this is always allowed and the flag is ignored. hipDeviceLmemResizeToMax :
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Driver.html b/docs/RuntimeAPI/html/group__Driver.html
new file mode 100644
index 0000000000..c045006c7e
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Driver.html
@@ -0,0 +1,750 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Modules | |
| Management | |
+Functions | |
| hipError_t | hipInit (unsigned int flags) |
| Explicitly initializes the HIP runtime. More... | |
| hipError_t | hipDeviceGet (hipDevice_t *device, int ordinal) |
| Returns a handle to a compute device. More... | |
| hipError_t | hipDeviceComputeCapability (int *major, int *minor, hipDevice_t device) |
| Returns the compute capability of the device. More... | |
| hipError_t | hipDeviceGetName (char *name, int len, hipDevice_t device) |
| Returns an identifer string for the device. More... | |
| hipError_t | hipDeviceGetPCIBusId (char *pciBusId, int len, int device) |
| Returns a PCI Bus Id string for the device, overloaded to take int device ID. More... | |
| hipError_t | hipDeviceGetByPCIBusId (int *device, const int *pciBusId) |
| Returns a handle to a compute device. More... | |
| hipError_t | hipDeviceTotalMem (size_t *bytes, hipDevice_t device) |
| Returns the total amount of memory on the device. More... | |
| hipError_t | hipDriverGetVersion (int *driverVersion) |
| Returns the approximate HIP driver version. More... | |
| hipError_t | hipRuntimeGetVersion (int *runtimeVersion) |
| Returns the approximate HIP Runtime version. More... | |
| hipError_t | hipModuleLoad (hipModule_t *module, const char *fname) |
| Loads code object from file into a hipModule_t. More... | |
| hipError_t | hipModuleUnload (hipModule_t module) |
| Frees the module. More... | |
| hipError_t | hipModuleGetFunction (hipFunction_t *function, hipModule_t module, const char *kname) |
| Function with kname will be extracted if present in module. More... | |
| hipError_t | hipModuleGetGlobal (hipDeviceptr_t *dptr, size_t *bytes, hipModule_t hmod, const char *name) |
returns device memory pointer and size of the kernel present in the module with symbol name More... | |
| hipError_t | hipModuleLoadData (hipModule_t *module, const void *image) |
| builds module from code object which resides in host memory. Image is pointer to that location. More... | |
| hipError_t | hipModuleLaunchKernel (hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, hipStream_t stream, void **kernelParams, void **extra) |
| launches kernel f with launch parameters and shared memory on stream with arguments passed to kernelparams or extra More... | |
| hipError_t hipDeviceComputeCapability | +( | +int * | +major, | +
| + | + | int * | +minor, | +
| + | + | hipDevice_t | +device | +
| + | ) | ++ |
Returns the compute capability of the device.
+| [out] | major | |
| [out] | minor | |
| [in] | device |
| hipError_t hipDeviceGet | +( | +hipDevice_t * | +device, | +
| + | + | int | +ordinal | +
| + | ) | ++ |
Returns a handle to a compute device.
+| [out] | device | |
| [in] | ordinal |
| hipError_t hipDeviceGetByPCIBusId | +( | +int * | +device, | +
| + | + | const int * | +pciBusId | +
| + | ) | ++ |
Returns a handle to a compute device.
+| [out] | device | handle |
| [in] | PCI | Bus ID |
| hipError_t hipDeviceGetName | +( | +char * | +name, | +
| + | + | int | +len, | +
| + | + | hipDevice_t | +device | +
| + | ) | ++ |
Returns an identifer string for the device.
+| [out] | name | |
| [in] | len | |
| [in] | device |
| hipError_t hipDeviceGetPCIBusId | +( | +char * | +pciBusId, | +
| + | + | int | +len, | +
| + | + | int | +device | +
| + | ) | ++ |
Returns a PCI Bus Id string for the device, overloaded to take int device ID.
+| [out] | pciBusId | |
| [in] | len | |
| [in] | device |
| hipError_t hipDeviceTotalMem | +( | +size_t * | +bytes, | +
| + | + | hipDevice_t | +device | +
| + | ) | ++ |
Returns the total amount of memory on the device.
+| [out] | bytes | |
| [in] | device |
| hipError_t hipDriverGetVersion | +( | +int * | +driverVersion | ) | ++ |
Returns the approximate HIP driver version.
+| [out] | driverVersion |
| hipError_t hipInit | +( | +unsigned int | +flags | ) | ++ |
Explicitly initializes the HIP runtime.
+Most HIP APIs implicitly initialize the HIP runtime. This API provides control over the timing of the initialization.
+ +| hipError_t hipModuleGetFunction | +( | +hipFunction_t * | +function, | +
| + | + | hipModule_t | +module, | +
| + | + | const char * | +kname | +
| + | ) | ++ |
Function with kname will be extracted if present in module.
+| [in] | module | |
| [in] | kname | |
| [out] | function |
| hipError_t hipModuleGetGlobal | +( | +hipDeviceptr_t * | +dptr, | +
| + | + | size_t * | +bytes, | +
| + | + | hipModule_t | +hmod, | +
| + | + | const char * | +name | +
| + | ) | ++ |
returns device memory pointer and size of the kernel present in the module with symbol name
| [out] | dptr | |
| [out[ | bytes | |
| [in] | hmod | |
| [in] | name |
| hipError_t hipModuleLaunchKernel | +( | +hipFunction_t | +f, | +
| + | + | unsigned int | +gridDimX, | +
| + | + | unsigned int | +gridDimY, | +
| + | + | unsigned int | +gridDimZ, | +
| + | + | unsigned int | +blockDimX, | +
| + | + | unsigned int | +blockDimY, | +
| + | + | unsigned int | +blockDimZ, | +
| + | + | unsigned int | +sharedMemBytes, | +
| + | + | hipStream_t | +stream, | +
| + | + | void ** | +kernelParams, | +
| + | + | void ** | +extra | +
| + | ) | ++ |
launches kernel f with launch parameters and shared memory on stream with arguments passed to kernelparams or extra
+| [in[ | f | |
| [in] | gridDimX | |
| [in] | gridDimY | |
| [in] | gridDimZ | |
| [in] | blockDimX | |
| [in] | blockDimY | |
| [in] | blockDimZ | |
| [in] | sharedMemBytes | |
| [in] | stream | |
| [in] | kernelParams | |
| [in] | extraa | The function takes the above arguments and run the kernel in hipFunction_t f. with launch parameters specified in gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY and blockDimmZ. The amount of shared memory is specificed and can be used with HIP_DYNAMIC_SHARED. The arguemt extra is used to pass in the arguments for the kernel. |
| hipError_t hipModuleLoad | +( | +hipModule_t * | +module, | +
| + | + | const char * | +fname | +
| + | ) | ++ |
Loads code object from file into a hipModule_t.
+| [in] | fname | |
| [out] | module |
| hipError_t hipModuleLoadData | +( | +hipModule_t * | +module, | +
| + | + | const void * | +image | +
| + | ) | ++ |
builds module from code object which resides in host memory. Image is pointer to that location.
+| [in] | image | |
| [out] | module |
| hipError_t hipModuleUnload | +( | +hipModule_t | +module | ) | ++ |
Frees the module.
+| [in] | module |
| hipError_t hipRuntimeGetVersion | +( | +int * | +runtimeVersion | ) | ++ |
Returns the approximate HIP Runtime version.
+| [out] | runtimeVersion |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Error.html b/docs/RuntimeAPI/html/group__Error.html
new file mode 100644
index 0000000000..03d5f89643
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Error.html
@@ -0,0 +1,206 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipError_t | hipGetLastError (void) |
| Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess. More... | |
| hipError_t | hipPeekAtLastError (void) |
| Return last error returned by any HIP runtime API call. More... | |
| const char * | hipGetErrorName (hipError_t hip_error) |
| Return name of the specified error code in text form. More... | |
| const char * | hipGetErrorString (hipError_t hipError) |
| Return handy text string message to explain the error which occurred. More... | |
| const char* hipGetErrorName | +( | +hipError_t | +hip_error | ) | ++ |
Return name of the specified error code in text form.
+| hip_error | Error code to convert to name. |
| const char* hipGetErrorString | +( | +hipError_t | +hipError | ) | ++ |
Return handy text string message to explain the error which occurred.
+| hipError | Error code to convert to string. |
| hipError_t hipGetLastError | +( | +void | +) | ++ |
Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess.
+Returns the last error that has been returned by any of the runtime calls in the same host thread, and then resets the saved error to hipSuccess.
+| hipError_t hipPeekAtLastError | +( | +void | +) | ++ |
Return last error returned by any HIP runtime API call.
+Returns the last error that has been returned by any of the runtime calls in the same host thread. Unlike hipGetLastError, this function does not reset the saved error code.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Event.html b/docs/RuntimeAPI/html/group__Event.html
new file mode 100644
index 0000000000..73095e0234
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Event.html
@@ -0,0 +1,356 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipError_t | hipEventCreateWithFlags (hipEvent_t *event, unsigned flags) |
| Create an event with the specified flags. More... | |
| hipError_t | hipEventCreate (hipEvent_t *event) |
| hipError_t | hipEventRecord (hipEvent_t event, hipStream_t stream) |
| Record an event in the specified stream. More... | |
| hipError_t | hipEventDestroy (hipEvent_t event) |
| Destroy the specified event. More... | |
| hipError_t | hipEventSynchronize (hipEvent_t event) |
| Wait for an event to complete. More... | |
| hipError_t | hipEventElapsedTime (float *ms, hipEvent_t start, hipEvent_t stop) |
| Return the elapsed time between two events. More... | |
| hipError_t | hipEventQuery (hipEvent_t event) |
| Query event status. More... | |
| hipError_t hipEventCreate | +( | +hipEvent_t * | +event | ) | ++ |
Create an event
+| [in,out] | event | Returns the newly created event. |
| hipError_t hipEventCreateWithFlags | +( | +hipEvent_t * | +event, | +
| + | + | unsigned | +flags | +
| + | ) | ++ |
Create an event with the specified flags.
+| [in,out] | event | Returns the newly created event. |
| [in] | flags | Flags to control event behavior. Valid values are hipEventDefault, hipEventBlockingSync, hipEventDisableTiming, hipEventInterprocess |
hipEventDefault : Default flag. The event will use active synchronization and will support timing. Blocking synchronization provides lowest possible latency at the expense of dedicating a CPU to poll on the eevent. hipEventBlockingSync : The event will use blocking synchronization : if hipEventSynchronize is called on this event, the thread will block until the event completes. This can increase latency for the synchroniation but can result in lower power and more resources for other CPU threads. hipEventDisableTiming : Disable recording of timing information. On ROCM platform, timing information is always recorded and this flag has no performance benefit.
+| hipError_t hipEventDestroy | +( | +hipEvent_t | +event | ) | ++ |
Destroy the specified event.
+| [in] | event | Event to destroy. |
Releases memory associated with the event. If the event is recording but has not completed recording when hipEventDestroy() is called, the function will return immediately and the completion_future resources will be released later, when the hipDevice is synchronized.
+| hipError_t hipEventElapsedTime | +( | +float * | +ms, | +
| + | + | hipEvent_t | +start, | +
| + | + | hipEvent_t | +stop | +
| + | ) | ++ |
Return the elapsed time between two events.
+| [out] | ms | : Return time between start and stop in ms. |
| [in] | start | : Start event. |
| [in] | stop | : Stop event. |
Computes the elapsed time between two events. Time is computed in ms, with a resolution of approximately 1 us.
+Events which are recorded in a NULL stream will block until all commands on all other streams complete execution, and then record the timestamp.
+Events which are recorded in a non-NULL stream will record their timestamp when they reach the head of the specified stream, after all previous commands in that stream have completed executing. Thus the time that the event recorded may be significantly after the host calls hipEventRecord().
+If hipEventRecord() has not been called on either event, then hipErrorInvalidResourceHandle is returned. If hipEventRecord() has been called on both events, but the timestamp has not yet been recorded on one or both events (that is, hipEventQuery() would return hipErrorNotReady on at least one of the events), then hipErrorNotReady is returned.
+ + +| hipError_t hipEventQuery | +( | +hipEvent_t | +event | ) | ++ |
Query event status.
+| [in] | event | Event to query. |
Query the status of the specified event. This function will return hipErrorNotReady if all commands in the appropriate stream (specified to hipEventRecord()) have completed. If that work has not completed, or if hipEventRecord() was not called on the event, then hipSuccess is returned.
+ + +| hipError_t hipEventRecord | +( | +hipEvent_t | +event, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Record an event in the specified stream.
+| [in] | event | event to record. |
| [in] | stream | stream in which to record event. |
hipEventQuery() or hipEventSynchronize() must be used to determine when the event transitions from "recording" (after hipEventRecord() is called) to "recorded" (when timestamps are set, if requested).
+Events which are recorded in a non-NULL stream will transition to from recording to "recorded" state when they reach the head of the specified stream, after all previous commands in that stream have completed executing.
+If hipEventRecord() has been previously called aon event, then this call will overwrite any existing state in event.
+If this function is called on a an event that is currently being recorded, results are undefined - either outstanding recording may save state into the event, and the order is not guaranteed. This shoul be avoided.
+ + +| hipError_t hipEventSynchronize | +( | +hipEvent_t | +event | ) | ++ |
Wait for an event to complete.
+This function will block until the event is ready, waiting for all previous work in the stream specified when event was recorded with hipEventRecord().
+If hipEventRecord() has not been called on event, this function returns immediately.
TODO-hcc - This function needs to support hipEventBlockingSync parameter.
+| [in] | event | Event on which to wait. |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Fence.html b/docs/RuntimeAPI/html/group__Fence.html
new file mode 100644
index 0000000000..bb73801cca
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Fence.html
@@ -0,0 +1,211 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| __device__ void | __threadfence_block (void) |
| threadfence_block makes writes visible to threads running in same block. More... | |
| __device__ void | __threadfence (void) |
| threadfence makes wirtes visible to other threads running on same GPU. More... | |
| __device__ void | __threadfence_system (void) |
| threadfence_system makes writes to pinned system memory visible on host CPU. More... | |
| +__device__ unsigned | __hip_ds_bpermute (int index, unsigned src) |
| +__device__ float | __hip_ds_bpermutef (int index, float src) |
| +__device__ unsigned | __hip_ds_permute (int index, unsigned src) |
| +__device__ float | __hip_ds_permutef (int index, float src) |
| +__device__ unsigned | __hip_ds_swizzle (unsigned int src, int pattern) |
| +__device__ float | __hip_ds_swizzlef (float src, int pattern) |
| +__device__ int | __hip_move_dpp (int src, int dpp_ctrl, int row_mask, int bank_mask, bool bound_ctrl) |
CUDA 8 device function features
+On AMD platforms, the threadfence* routines are currently empty stubs.
+| __device__ void __threadfence | +( | +void | +) | ++ |
threadfence makes wirtes visible to other threads running on same GPU.
+void
+| void |
| __device__ void __threadfence_block | +( | +void | +) | ++ |
threadfence_block makes writes visible to threads running in same block.
+void
+| void |
| __device__ void __threadfence_system | +( | +void | +) | ++ |
threadfence_system makes writes to pinned system memory visible on host CPU.
+void
+| void |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__GlobalDefs.html b/docs/RuntimeAPI/html/group__GlobalDefs.html
new file mode 100644
index 0000000000..4182019c94
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__GlobalDefs.html
@@ -0,0 +1,700 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Classes | |
| struct | dim3 |
+Macros | |
| #define | hipStreamDefault 0x00 |
| Flags that can be used with hipStreamCreateWithFlags. More... | |
| +#define | hipStreamNonBlocking 0x01 |
| Stream does not implicitly synchronize with null stream. | |
| #define | hipEventDefault 0x0 |
| Flags that can be used with hipEventCreateWithFlags: More... | |
| +#define | hipEventBlockingSync 0x1 |
| Waiting will yield CPU. Power-friendly and usage-friendly but may increase latency. | |
| +#define | hipEventDisableTiming 0x2 |
| Disable event's capability to record timing information. May improve performance. | |
| #define | hipEventInterprocess 0x4 |
| Event can support IPC. More... | |
| +#define | hipHostMallocDefault 0x0 |
| Flags that can be used with hipHostMalloc. | |
| +#define | hipHostMallocPortable 0x1 |
| +#define | hipHostMallocMapped 0x2 |
| +#define | hipHostMallocWriteCombined 0x4 |
| #define | hipHostRegisterDefault 0x0 |
| Flags that can be used with hipHostRegister. More... | |
| +#define | hipHostRegisterPortable 0x1 |
| Memory is considered registered by all contexts. HIP only supports one context so this is always assumed true. | |
| +#define | hipHostRegisterMapped 0x2 |
| Map the allocation into the address space for the current device. The device pointer can be obtained with hipHostGetDevicePointer. | |
| +#define | hipHostRegisterIoMemory 0x4 |
| Not supported. | |
| +#define | hipDeviceScheduleAuto 0x0 |
| Automatically select between Spin and Yield. | |
| +#define | hipDeviceScheduleSpin 0x1 |
| Dedicate a CPU core to spin-wait. Provides lowest latency, but burns a CPU core and may consume more power. | |
| +#define | hipDeviceScheduleYield 0x2 |
| Yield the CPU to the operating system when waiting. May increase latency, but lowers power and is friendlier to other threads in the system. | |
| +#define | hipDeviceScheduleBlockingSync 0x4 |
| +#define | hipDeviceScheduleMask 0x7 |
| +#define | hipDeviceMapHost 0x8 |
| +#define | hipDeviceLmemResizeToMax 0x16 |
+Typedefs | |
| +typedef enum hipError_t | hipError_t |
| +typedef enum hipDeviceAttribute_t | hipDeviceAttribute_t |
| typedef enum hipFuncCache_t | hipFuncCache_t |
| typedef enum hipSharedMemConfig | hipSharedMemConfig |
| typedef struct dim3 | dim3 |
| typedef enum hipMemcpyKind | hipMemcpyKind |
| #define hipEventDefault 0x0 | +
Flags that can be used with hipEventCreateWithFlags:
+Default flags
+ +| #define hipEventInterprocess 0x4 | +
Event can support IPC.
+| #define hipHostRegisterDefault 0x0 | +
Flags that can be used with hipHostRegister.
+Memory is Mapped and Portable
+ +| #define hipStreamDefault 0x00 | +
Flags that can be used with hipStreamCreateWithFlags.
+Default stream creation flags. These are used with hipStreamCreate().
+ +| typedef enum hipFuncCache_t hipFuncCache_t | +
| typedef enum hipMemcpyKind hipMemcpyKind | +
Memory copy types
+ +| typedef enum hipSharedMemConfig hipSharedMemConfig | +
| enum hipDeviceAttribute_t | +
| enum hipError_t | +
| enum hipFuncCache_t | +
| enum hipMemcpyKind | +
Memory copy types
+| enum hipSharedMemConfig | +
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__HCC__Specific.html b/docs/RuntimeAPI/html/group__HCC__Specific.html
new file mode 100644
index 0000000000..b9940e0a53
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__HCC__Specific.html
@@ -0,0 +1,96 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
The following calls are only supported when compiler HIP with HCC. To produce portable code, use of these calls must be guarded #ifdef checks:
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__HIP-ENV.html b/docs/RuntimeAPI/html/group__HIP-ENV.html
new file mode 100644
index 0000000000..f38a717247
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__HIP-ENV.html
@@ -0,0 +1,90 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Memory.html b/docs/RuntimeAPI/html/group__Memory.html
new file mode 100644
index 0000000000..338ce818a2
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Memory.html
@@ -0,0 +1,1319 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipError_t | hipPointerGetAttributes (hipPointerAttribute_t *attributes, void *ptr) |
| Return attributes for the specified pointer. More... | |
| hipError_t | hipMalloc (void **ptr, size_t size) |
| Allocate memory on the default accelerator. More... | |
| hipError_t | hipMallocHost (void **ptr, size_t size) __attribute__((deprecated("use hipHostMalloc instead"))) |
| Allocate pinned host memory [Deprecated]. More... | |
| hipError_t | hipHostMalloc (void **ptr, size_t size, unsigned int flags) |
| Allocate device accessible page locked host memory. More... | |
| hipError_t | hipHostAlloc (void **ptr, size_t size, unsigned int flags) __attribute__((deprecated("use hipHostMalloc instead"))) |
| Allocate device accessible page locked host memory [Deprecated]. More... | |
| hipError_t | hipHostGetDevicePointer (void **devPtr, void *hstPtr, unsigned int flags) |
| Get Device pointer from Host Pointer allocated through hipHostMalloc. More... | |
| hipError_t | hipHostGetFlags (unsigned int *flagsPtr, void *hostPtr) |
| Return flags associated with host pointer. More... | |
| hipError_t | hipHostRegister (void *hostPtr, size_t sizeBytes, unsigned int flags) |
| Register host memory so it can be accessed from the current device. More... | |
| hipError_t | hipHostUnregister (void *hostPtr) |
| Un-register host pointer. More... | |
| hipError_t | hipMallocPitch (void **ptr, size_t *pitch, size_t width, size_t height) |
| hipError_t | hipFree (void *ptr) |
| Free memory allocated by the hcc hip memory allocation API. This API performs an implicit hipDeviceSynchronize() call. If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. More... | |
| hipError_t | hipFreeHost (void *ptr) __attribute__((deprecated("use hipHostFree instead"))) |
| Free memory allocated by the hcc hip host memory allocation API. [Deprecated]. More... | |
| hipError_t | hipHostFree (void *ptr) |
| Free memory allocated by the hcc hip host memory allocation API This API performs an implicit hipDeviceSynchronize() call. If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. More... | |
| hipError_t | hipMemcpy (void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind) |
| Copy data from src to dst. More... | |
| hipError_t | hipMemcpyHtoD (hipDeviceptr_t dst, void *src, size_t sizeBytes) |
| Copy data from Host to Device. More... | |
| hipError_t | hipMemcpyDtoH (void *dst, hipDeviceptr_t src, size_t sizeBytes) |
| Copy data from Device to Host. More... | |
| hipError_t | hipMemcpyDtoD (hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes) |
| Copy data from Device to Device. More... | |
| hipError_t | hipMemcpyHtoDAsync (hipDeviceptr_t dst, void *src, size_t sizeBytes, hipStream_t stream) |
| Copy data from Host to Device asynchronously. More... | |
| hipError_t | hipMemcpyDtoHAsync (void *dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream) |
| Copy data from Device to Host asynchronously. More... | |
| hipError_t | hipMemcpyDtoDAsync (hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream) |
| Copy data from Device to Device asynchronously. More... | |
| hipError_t | hipMemcpyToSymbol (const char *symbolName, const void *src, size_t sizeBytes, size_t offset, hipMemcpyKind kind) |
Copies sizeBytes bytes from the memory area pointed to by src to the memory area pointed to by offset bytes from the start of symbol symbol. More... | |
| hipError_t | hipMemcpyToSymbolAsync (const char *symbolName, const void *src, size_t sizeBytes, size_t offset, hipMemcpyKind kind, hipStream_t stream) |
Copies sizeBytes bytes from the memory area pointed to by src to the memory area pointed to by offset bytes from the start of symbol symbol. More... | |
| hipError_t | hipMemcpyAsync (void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind, hipStream_t stream) |
| Copy data from src to dst asynchronously. More... | |
| hipError_t | hipMemset (void *dst, int value, size_t sizeBytes) |
| Copy data from src to dst asynchronously. More... | |
| hipError_t | hipMemsetAsync (void *dst, int value, size_t sizeBytes, hipStream_t stream) |
| Fills the first sizeBytes bytes of the memory area pointed to by dev with the constant byte value value. More... | |
| hipError_t | hipMemGetInfo (size_t *free, size_t *total) |
| Query memory info. Return snapshot of free memory, and total allocatable memory on the device. More... | |
The following CUDA APIs are not currently supported:
+| hipError_t hipFree | +( | +void * | +ptr | ) | ++ |
Free memory allocated by the hcc hip memory allocation API. This API performs an implicit hipDeviceSynchronize() call. If pointer is NULL, the hip runtime is initialized and hipSuccess is returned.
+| [in] | ptr | Pointer to memory to be freed |
| hipError_t hipFreeHost | +( | +void * | +ptr | ) | ++ |
Free memory allocated by the hcc hip host memory allocation API. [Deprecated].
+| [in] | ptr | Pointer to memory to be freed |
| hipError_t hipHostAlloc | +( | +void ** | +ptr, | +
| + | + | size_t | +size, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Allocate device accessible page locked host memory [Deprecated].
+| [out] | ptr | Pointer to the allocated host pinned memory |
| [in] | size | Requested memory size |
| [in] | flags | Type of host memory allocation |
| hipError_t hipHostFree | +( | +void * | +ptr | ) | ++ |
Free memory allocated by the hcc hip host memory allocation API This API performs an implicit hipDeviceSynchronize() call. If pointer is NULL, the hip runtime is initialized and hipSuccess is returned.
+| [in] | ptr | Pointer to memory to be freed |
| hipError_t hipHostGetDevicePointer | +( | +void ** | +devPtr, | +
| + | + | void * | +hstPtr, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Get Device pointer from Host Pointer allocated through hipHostMalloc.
+| [out] | dstPtr | Device Pointer mapped to passed host pointer |
| [in] | hstPtr | Host Pointer allocated through hipHostMalloc |
| [in] | flags | Flags to be passed for extension |
| hipError_t hipHostGetFlags | +( | +unsigned int * | +flagsPtr, | +
| + | + | void * | +hostPtr | +
| + | ) | ++ |
Return flags associated with host pointer.
+| [out] | flagsPtr | Memory location to store flags |
| [in] | hostPtr | Host Pointer allocated through hipHostMalloc |
| hipError_t hipHostMalloc | +( | +void ** | +ptr, | +
| + | + | size_t | +size, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Allocate device accessible page locked host memory.
+| [out] | ptr | Pointer to the allocated host pinned memory |
| [in] | size | Requested memory size |
| [in] | flags | Type of host memory allocation |
| hipError_t hipHostRegister | +( | +void * | +hostPtr, | +
| + | + | size_t | +sizeBytes, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Register host memory so it can be accessed from the current device.
+| [out] | hostPtr | Pointer to host memory to be registered. |
| [in] | sizeBytes | size of the host memory |
| [in] | flags. | See below. |
Flags:
+After registering the memory, use hipHostGetDevicePointer to obtain the mapped device pointer. On many systems, the mapped device pointer will have a different value than the mapped host pointer. Applications must use the device pointer in device code, and the host pointer in device code.
+On some systems, registered memory is pinned. On some systems, registered memory may not be actually be pinned but uses OS or hardware facilities to all GPU access to the host memory.
+Developers are strongly encouraged to register memory blocks which are aligned to the host cache-line size. (typically 64-bytes but can be obtains from the CPUID instruction).
+If registering non-aligned pointers, the application must take care when register pointers from the same cache line on different devices. HIP's coarse-grained synchronization model does not guarantee correct results if different devices write to different parts of the same cache block - typically one of the writes will "win" and overwrite data from the other registered memory region.
+| hipError_t hipHostUnregister | +( | +void * | +hostPtr | ) | ++ |
Un-register host pointer.
+| [in] | hostPtr | Host pointer previously registered with hipHostRegister |
| hipError_t hipMalloc | +( | +void ** | +ptr, | +
| + | + | size_t | +size | +
| + | ) | ++ |
Allocate memory on the default accelerator.
+| [out] | ptr | Pointer to the allocated memory |
| [in] | size | Requested memory size |
| hipError_t hipMallocHost | +( | +void ** | +ptr, | +
| + | + | size_t | +size | +
| + | ) | ++ |
Allocate pinned host memory [Deprecated].
+| [out] | ptr | Pointer to the allocated host pinned memory |
| [in] | size | Requested memory size |
| hipError_t hipMallocPitch | +( | +void ** | +ptr, | +
| + | + | size_t * | +pitch, | +
| + | + | size_t | +width, | +
| + | + | size_t | +height | +
| + | ) | ++ |
Allocates at least width (in bytes) * height bytes of linear memory Padding may occur to ensure alighnment requirements are met for the given row The change in width size due to padding will be returned in *pitch. Currently the alignment is set to 128 bytes
+| [out] | ptr | Pointer to the allocated device memory |
| [out] | pitch | Pitch for allocation (in bytes) |
| [in] | width | Requested pitched allocation width (in bytes) |
| [in] | height | Requested pitched allocation height |
| hipError_t hipMemcpy | +( | +void * | +dst, | +
| + | + | const void * | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipMemcpyKind | +kind | +
| + | ) | ++ |
Copy data from src to dst.
+It supports memory from host to device, device to host, device to device and host to host The src and dst must not overlap.
+For hipMemcpy, the copy is always performed by the current device (set by hipSetDevice). For multi-gpu or peer-to-peer configurations, it is recommended to set the current device to the device where the src data is physically located. For optimal peer-to-peer copies, the copy device must be able to access the src and dst pointers (by calling hipDeviceEnablePeerAccess with copy agent as the current device and src/dest as the peerDevice argument. if this is not done, the hipMemcpy will still work, but will perform the copy using a staging buffer on the host.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| [in] | copyType | Memory copy type |
| hipError_t hipMemcpyAsync | +( | +void * | +dst, | +
| + | + | const void * | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipMemcpyKind | +kind, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Copy data from src to dst asynchronously.
+For multi-gpu or peer-to-peer configurations, it is recommended to use a stream which is a attached to the device where the src data is physically located. For optimal peer-to-peer copies, the copy device must be able to access the src and dst pointers (by calling hipDeviceEnablePeerAccess with copy agent as the current device and src/dest as the peerDevice argument. if this is not done, the hipMemcpy will still work, but will perform the copy using a staging buffer on the host.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| [in] | accelerator_view | Accelerator view which the copy is being enqueued |
| hipError_t hipMemcpyDtoD | +( | +hipDeviceptr_t | +dst, | +
| + | + | hipDeviceptr_t | +src, | +
| + | + | size_t | +sizeBytes | +
| + | ) | ++ |
Copy data from Device to Device.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| hipError_t hipMemcpyDtoDAsync | +( | +hipDeviceptr_t | +dst, | +
| + | + | hipDeviceptr_t | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Copy data from Device to Device asynchronously.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| hipError_t hipMemcpyDtoH | +( | +void * | +dst, | +
| + | + | hipDeviceptr_t | +src, | +
| + | + | size_t | +sizeBytes | +
| + | ) | ++ |
Copy data from Device to Host.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| hipError_t hipMemcpyDtoHAsync | +( | +void * | +dst, | +
| + | + | hipDeviceptr_t | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Copy data from Device to Host asynchronously.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| hipError_t hipMemcpyHtoD | +( | +hipDeviceptr_t | +dst, | +
| + | + | void * | +src, | +
| + | + | size_t | +sizeBytes | +
| + | ) | ++ |
Copy data from Host to Device.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| hipError_t hipMemcpyHtoDAsync | +( | +hipDeviceptr_t | +dst, | +
| + | + | void * | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Copy data from Host to Device asynchronously.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| hipError_t hipMemcpyToSymbol | +( | +const char * | +symbolName, | +
| + | + | const void * | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | size_t | +offset, | +
| + | + | hipMemcpyKind | +kind | +
| + | ) | ++ |
Copies sizeBytes bytes from the memory area pointed to by src to the memory area pointed to by offset bytes from the start of symbol symbol.
The memory areas may not overlap. Symbol can either be a variable that resides in global or constant memory space, or it can be a character string, naming a variable that resides in global or constant memory space. Kind can be either hipMemcpyHostToDevice or hipMemcpyDeviceToDevice TODO: cudaErrorInvalidSymbol and cudaErrorInvalidMemcpyDirection is not supported, use hipErrorUnknown for now.
+| [in] | symbolName | - Symbol destination on device |
| [in] | src | - Data being copy from |
| [in] | sizeBytes | - Data size in bytes |
| [in] | offset | - Offset from start of symbol in bytes |
| [in] | kind | - Type of transfer |
| hipError_t hipMemcpyToSymbolAsync | +( | +const char * | +symbolName, | +
| + | + | const void * | +src, | +
| + | + | size_t | +sizeBytes, | +
| + | + | size_t | +offset, | +
| + | + | hipMemcpyKind | +kind, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Copies sizeBytes bytes from the memory area pointed to by src to the memory area pointed to by offset bytes from the start of symbol symbol.
The memory areas may not overlap. Symbol can either be a variable that resides in global or constant memory space, or it can be a character string, naming a variable that resides in global or constant memory space. Kind can be either hipMemcpyHostToDevice or hipMemcpyDeviceToDevice hipMemcpyToSymbolAsync() is asynchronous with respect to the host, so the call may return before copy is complete. TODO: cudaErrorInvalidSymbol and cudaErrorInvalidMemcpyDirection is not supported, use hipErrorUnknown for now.
+| [in] | symbolName | - Symbol destination on device |
| [in] | src | - Data being copy from |
| [in] | sizeBytes | - Data size in bytes |
| [in] | offset | - Offset from start of symbol in bytes |
| [in] | kind | - Type of transfer |
| hipError_t hipMemGetInfo | +( | +size_t * | +free, | +
| + | + | size_t * | +total | +
| + | ) | ++ |
Query memory info. Return snapshot of free memory, and total allocatable memory on the device.
+Returns in *free a snapshot of the current free memory.
+ +| hipError_t hipMemset | +( | +void * | +dst, | +
| + | + | int | +value, | +
| + | + | size_t | +sizeBytes | +
| + | ) | ++ |
Copy data from src to dst asynchronously.
+It supports memory from host to device, device to host, device to device and host to host.
+| [out] | dst | Data being copy to |
| [in] | src | Data being copy from |
| [in] | sizeBytes | Data size in bytes |
| [in] | accelerator_view | Accelerator view which the copy is being enqueued |
| hipError_t hipMemsetAsync | +( | +void * | +dst, | +
| + | + | int | +value, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Fills the first sizeBytes bytes of the memory area pointed to by dev with the constant byte value value.
+hipMemsetAsync() is asynchronous with respect to the host, so the call may return before the memset is complete. The operation can optionally be associated to a stream by passing a non-zero stream argument. If stream is non-zero, the operation may overlap with operations in other streams.
+| [out] | dst | Pointer to device memory |
| [in] | value | - Value to set for each byte of specified memory |
| [in] | sizeBytes | - Size in bytes to set |
| [in] | stream | - Stream identifier |
| hipError_t hipPointerGetAttributes | +( | +hipPointerAttribute_t * | +attributes, | +
| + | + | void * | +ptr | +
| + | ) | ++ |
Return attributes for the specified pointer.
+| [out] | attributes | for the specified pointer |
| [in] | pointer | to get attributes for |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__PeerToPeer.html b/docs/RuntimeAPI/html/group__PeerToPeer.html
new file mode 100644
index 0000000000..6038b9a5e5
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__PeerToPeer.html
@@ -0,0 +1,404 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Macros | |
| +#define | USE_PEER_NON_UNIFIED 1 |
+Functions | |
| hipError_t | hipDeviceCanAccessPeer (int *canAccessPeer, int deviceId, int peerDeviceId) |
| Determine if a device can access a peer's memory. More... | |
| hipError_t | hipDeviceEnablePeerAccess (int peerDeviceId, unsigned int flags) |
| Enable direct access from current device's virtual address space to memory allocations physically located on a peer device. More... | |
| hipError_t | hipDeviceDisablePeerAccess (int peerDeviceId) |
| Disable direct access from current device's virtual address space to memory allocations physically located on a peer device. More... | |
| hipError_t | hipMemGetAddressRange (hipDeviceptr_t *pbase, size_t *psize, hipDeviceptr_t dptr) |
| Get information on memory allocations. More... | |
| hipError_t | hipMemcpyPeer (void *dst, int dstDeviceId, const void *src, int srcDeviceId, size_t sizeBytes) |
| Copies memory from one device to memory on another device. More... | |
| hipError_t | hipMemcpyPeerAsync (void *dst, int dstDevice, const void *src, int srcDevice, size_t sizeBytes, hipStream_t stream) |
| Copies memory from one device to memory on another device. More... | |
| hipError_t hipDeviceCanAccessPeer | +( | +int * | +canAccessPeer, | +
| + | + | int | +deviceId, | +
| + | + | int | +peerDeviceId | +
| + | ) | ++ |
Determine if a device can access a peer's memory.
+| [out] | canAccessPeer | Returns the peer access capability (0 or 1) |
| [in] | device | - device from where memory may be accessed. |
| [in] | peerDevice | - device where memory is physically located |
Returns "1" in canAccessPeer if the specified device is capable of directly accessing memory physically located on peerDevice , or "0" if not.
Returns "0" in canAccessPeer if deviceId == peerDeviceId, and both are valid devices : a device is not a peer of itself.
| hipError_t hipDeviceDisablePeerAccess | +( | +int | +peerDeviceId | ) | ++ |
Disable direct access from current device's virtual address space to memory allocations physically located on a peer device.
+Returns hipErrorPeerAccessNotEnabled if direct access to memory on peerDevice has not yet been enabled from the current device.
+| [in] | peerDeviceId |
| hipError_t hipDeviceEnablePeerAccess | +( | +int | +peerDeviceId, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Enable direct access from current device's virtual address space to memory allocations physically located on a peer device.
+Memory which already allocated on peer device will be mapped into the address space of the current device. In addition, all future memory allocations on peerDeviceId will be mapped into the address space of the current device when the memory is allocated. The peer memory remains accessible from the current device until a call to hipDeviceDisablePeerAccess or hipDeviceReset.
+| [in] | peerDeviceId | |
| [in] | flags | Returns hipSuccess, hipErrorInvalidDevice, hipErrorInvalidValue, |
| hipError_t hipMemcpyPeer | +( | +void * | +dst, | +
| + | + | int | +dstDeviceId, | +
| + | + | const void * | +src, | +
| + | + | int | +srcDeviceId, | +
| + | + | size_t | +sizeBytes | +
| + | ) | ++ |
Copies memory from one device to memory on another device.
+| [out] | dst | - Destination device pointer. |
| [in] | dstDeviceId | - Destination device |
| [in] | src | - Source device pointer |
| [in] | srcDeviceId | - Source device |
| [in] | sizeBytes | - Size of memory copy in bytes |
| hipError_t hipMemcpyPeerAsync | +( | +void * | +dst, | +
| + | + | int | +dstDevice, | +
| + | + | const void * | +src, | +
| + | + | int | +srcDevice, | +
| + | + | size_t | +sizeBytes, | +
| + | + | hipStream_t | +stream | +
| + | ) | ++ |
Copies memory from one device to memory on another device.
+| [out] | dst | - Destination device pointer. |
| [in] | dstDevice | - Destination device |
| [in] | src | - Source device pointer |
| [in] | srcDevice | - Source device |
| [in] | sizeBytes | - Size of memory copy in bytes |
| [in] | stream | - Stream identifier |
| hipError_t hipMemGetAddressRange | +( | +hipDeviceptr_t * | +pbase, | +
| + | + | size_t * | +psize, | +
| + | + | hipDeviceptr_t | +dptr | +
| + | ) | ++ |
Get information on memory allocations.
+| [out] | pbase | - BAse pointer address |
| [out] | psize | - Size of allocation |
| [in] | dptr- | Device Pointer |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Profiler.html b/docs/RuntimeAPI/html/group__Profiler.html
new file mode 100644
index 0000000000..ab54cc9f59
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Profiler.html
@@ -0,0 +1,142 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipError_t | hipProfilerStart () |
| Start recording of profiling information When using this API, start the profiler with profiling disabled. (–startdisabled) More... | |
| hipError_t | hipProfilerStop () |
| Stop recording of profiling information. When using this API, start the profiler with profiling disabled. (–startdisabled) More... | |
| hipError_t hipProfilerStart | +( | +) | ++ |
Start recording of profiling information When using this API, start the profiler with profiling disabled. (–startdisabled)
+| hipError_t hipProfilerStop | +( | +) | ++ |
Stop recording of profiling information. When using this API, start the profiler with profiling disabled. (–startdisabled)
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Stream.html b/docs/RuntimeAPI/html/group__Stream.html
new file mode 100644
index 0000000000..4230158ab1
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Stream.html
@@ -0,0 +1,437 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Typedefs | |
| typedef void(* | hipStreamCallback_t )(hipStream_t stream, hipError_t status, void *userData) |
+Functions | |
| hipError_t | hipStreamCreate (hipStream_t *stream) |
| Create an asynchronous stream. More... | |
| hipError_t | hipStreamCreateWithFlags (hipStream_t *stream, unsigned int flags) |
| Create an asynchronous stream. More... | |
| hipError_t | hipStreamDestroy (hipStream_t stream) |
| Destroys the specified stream. More... | |
| hipError_t | hipStreamQuery (hipStream_t stream) |
Return hipSuccess if all of the operations in the specified stream have completed, or hipErrorNotReady if not. More... | |
| hipError_t | hipStreamSynchronize (hipStream_t stream) |
| Wait for all commands in stream to complete. More... | |
| hipError_t | hipStreamWaitEvent (hipStream_t stream, hipEvent_t event, unsigned int flags) |
| Make the specified compute stream wait for an event. More... | |
| hipError_t | hipStreamGetFlags (hipStream_t stream, unsigned int *flags) |
| Return flags associated with this stream. More... | |
| hipError_t | hipStreamAddCallback (hipStream_t stream, hipStreamCallback_t callback, void *userData, unsigned int flags) |
| Adds a callback to be called on the host after all currently enqueued items in the stream have completed. For each cudaStreamAddCallback call, a callback will be executed exactly once. The callback will block later work in the stream until it is finished. More... | |
The following Stream APIs are not (yet) supported in HIP:
+| typedef void(* hipStreamCallback_t)(hipStream_t stream, hipError_t status, void *userData) | +
Stream CallBack struct
+ +| hipError_t hipStreamAddCallback | +( | +hipStream_t | +stream, | +
| + | + | hipStreamCallback_t | +callback, | +
| + | + | void * | +userData, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Adds a callback to be called on the host after all currently enqueued items in the stream have completed. For each cudaStreamAddCallback call, a callback will be executed exactly once. The callback will block later work in the stream until it is finished.
+| [in] | stream | - Stream to add callback to |
| [in] | callback | - The function to call once preceding stream operations are complete |
| [in] | userData | - User specified data to be passed to the callback function |
| [in] | flags | - Reserved for future use, must be 0 |
| hipError_t hipStreamCreate | +( | +hipStream_t * | +stream | ) | ++ |
Create an asynchronous stream.
+| [in,out] | stream | Valid pointer to hipStream_t. This function writes the memory with the newly created stream. |
Create a new asynchronous stream. stream returns an opaque handle that can be used to reference the newly created stream in subsequent hipStream* commands. The stream is allocated on the heap and will remain allocated even if the handle goes out-of-scope. To release the memory used by the stream, applicaiton must call hipStreamDestroy.
| hipError_t hipStreamCreateWithFlags | +( | +hipStream_t * | +stream, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Create an asynchronous stream.
+| [in,out] | stream | Pointer to new stream |
| [in] | flags | to control stream creation. |
Create a new asynchronous stream. stream returns an opaque handle that can be used to reference the newly created stream in subsequent hipStream* commands. The stream is allocated on the heap and will remain allocated even if the handle goes out-of-scope. To release the memory used by the stream, applicaiton must call hipStreamDestroy. Flags controls behavior of the stream. See hipStreamDefault, hipStreamNonBlocking.
| hipError_t hipStreamDestroy | +( | +hipStream_t | +stream | ) | ++ |
Destroys the specified stream.
+| [in,out] | stream | Valid pointer to hipStream_t. This function writes the memory with the newly created stream. |
Destroys the specified stream.
+If commands are still executing on the specified stream, some may complete execution before the queue is deleted.
+The queue may be destroyed while some commands are still inflight, or may wait for all commands queued to the stream before destroying it.
+ + + +| hipError_t hipStreamGetFlags | +( | +hipStream_t | +stream, | +
| + | + | unsigned int * | +flags | +
| + | ) | ++ |
Return flags associated with this stream.
+| [in] | stream | stream to be queried |
| [in,out] | flags | Pointer to an unsigned integer in which the stream's flags are returned |
Return flags associated with this stream in *flags.
| hipError_t hipStreamQuery | +( | +hipStream_t | +stream | ) | ++ |
Return hipSuccess if all of the operations in the specified stream have completed, or hipErrorNotReady if not.
| [in] | stream | stream to query |
This is thread-safe and returns a snapshot of the current state of the queue. However, if other host threads are sending work to the stream, the status may change immediately after the function is called. It is typically used for debug.
+ + +| hipError_t hipStreamSynchronize | +( | +hipStream_t | +stream | ) | ++ |
Wait for all commands in stream to complete.
+| [in] | stream | stream identifier. |
If the null stream is specified, this command blocks until all This command honors the hipDeviceLaunchBlocking flag, which controls whether the wait is active or blocking. This command is host-synchronous : the host will block until the stream is empty.
+ + +| hipError_t hipStreamWaitEvent | +( | +hipStream_t | +stream, | +
| + | + | hipEvent_t | +event, | +
| + | + | unsigned int | +flags | +
| + | ) | ++ |
Make the specified compute stream wait for an event.
+| [in] | stream | stream to make wait. |
| [in] | event | event to wait on |
| [in] | flags | control operation [must be 0] |
This function inserts a wait operation into the specified stream. All future work submitted to stream will wait until event reports completion before beginning execution. This function is host-asynchronous and the function may return before the wait has completed.
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/group__Texture.html b/docs/RuntimeAPI/html/group__Texture.html
new file mode 100644
index 0000000000..21560396c7
--- /dev/null
+++ b/docs/RuntimeAPI/html/group__Texture.html
@@ -0,0 +1,214 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Functions | |
| hipChannelFormatDesc | hipCreateChannelDesc (int x, int y, int z, int w, hipChannelFormatKind f) |
| Returns a channel descriptor using the specified format. More... | |
| +template<typename T > | |
| hipChannelFormatDesc | hipCreateChannelDesc () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< int > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< unsigned int > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< long > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< unsigned long > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< float > () |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipBindTexture (size_t *offset, struct texture< T, dim, readMode > &tex, const void *devPtr, const struct hipChannelFormatDesc *desc, size_t size=UINT_MAX) |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipBindTexture (size_t *offset, struct texture< T, dim, readMode > &tex, const void *devPtr, size_t size=UINT_MAX) |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipBindTextureToArray (struct texture< T, dim, readMode > &tex, hipArray *array) |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipUnbindTexture (struct texture< T, dim, readMode > &tex) |
The HIP texture support is intended to allow use of texture cache on hardware where this is beneficial.
+The following CUDA APIs are not currently supported:
+| hipChannelFormatDesc hipCreateChannelDesc | +( | +int | +x, | +
| + | + | int | +y, | +
| + | + | int | +z, | +
| + | + | int | +w, | +
| + | + | hipChannelFormatKind | +f | +
| + | ) | ++ |
Returns a channel descriptor using the specified format.
+| [in] | x | X component |
| [in] | y | Y component |
| [in] | z | Z component |
| [in] | w | W component |
| [in] | f | Channel format |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc_8h_source.html b/docs/RuntimeAPI/html/hcc_8h_source.html
new file mode 100644
index 0000000000..720e8ffa6e
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc_8h_source.html
@@ -0,0 +1,130 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__acc_8h_source.html b/docs/RuntimeAPI/html/hcc__acc_8h_source.html
new file mode 100644
index 0000000000..06918d855c
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__acc_8h_source.html
@@ -0,0 +1,138 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__complex_8h_source.html b/docs/RuntimeAPI/html/hcc__detail_2hip__complex_8h_source.html
new file mode 100644
index 0000000000..ba44cc5c16
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__complex_8h_source.html
@@ -0,0 +1,276 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__fp16_8h_source.html b/docs/RuntimeAPI/html/hcc__detail_2hip__fp16_8h_source.html
new file mode 100644
index 0000000000..27e7ea4ddb
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__fp16_8h_source.html
@@ -0,0 +1,278 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__runtime_8h.html b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime_8h.html
new file mode 100644
index 0000000000..9b7b4d8f90
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime_8h.html
@@ -0,0 +1,1191 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
Contains definitions of APIs for HIP runtime. +More...
+#include <math.h>#include <string.h>#include <stddef.h>#include <hip/hip_runtime_api.h>#include <grid_launch.h>#include <hip/hcc_detail/host_defines.h>Go to the source code of this file.
++Macros | |
| +#define | NVCC_COMPAT |
| +#define | CUDA_SUCCESS hipSuccess |
| +#define | hipLaunchParm grid_launch_parm |
| +#define | __launch_bounds__(requiredMaxThreadsPerBlock, minBlocksPerMultiprocessor) |
| +#define | clock_t long long int |
| +#define | hipThreadIdx_x (hc_get_workitem_id(0)) |
| +#define | hipThreadIdx_y (hc_get_workitem_id(1)) |
| +#define | hipThreadIdx_z (hc_get_workitem_id(2)) |
| +#define | hipBlockIdx_x (hc_get_group_id(0)) |
| +#define | hipBlockIdx_y (hc_get_group_id(1)) |
| +#define | hipBlockIdx_z (hc_get_group_id(2)) |
| +#define | hipBlockDim_x (hc_get_group_size(0)) |
| +#define | hipBlockDim_y (hc_get_group_size(1)) |
| +#define | hipBlockDim_z (hc_get_group_size(2)) |
| +#define | hipGridDim_x (hc_get_num_groups(0)) |
| +#define | hipGridDim_y (hc_get_num_groups(1)) |
| +#define | hipGridDim_z (hc_get_num_groups(2)) |
| +#define | __syncthreads() hc_barrier(CLK_LOCAL_MEM_FENCE) |
| +#define | HIP_KERNEL_NAME(...) __VA_ARGS__ |
| +#define | HIP_SYMBOL(X) #X |
| #define | HIP_DYNAMIC_SHARED(type, var) |
| +#define | HIP_DYNAMIC_SHARED_ATTRIBUTE __attribute__((address_space(3))) |
+Functions | |
| +__device__ float | acosf (float x) |
| +__device__ float | acoshf (float x) |
| +__device__ float | asinf (float x) |
| +__device__ float | asinhf (float x) |
| +__device__ float | atan2f (float y, float x) |
| +__device__ float | atanf (float x) |
| +__device__ float | atanhf (float x) |
| +__device__ float | cbrtf (float x) |
| +__device__ float | ceilf (float x) |
| +__device__ float | copysignf (float x, float y) |
| +__device__ float | coshf (float x) |
| +__device__ float | cyl_bessel_i0f (float x) |
| +__device__ float | cyl_bessel_i1f (float x) |
| +__device__ float | erfcf (float x) |
| +__device__ float | erfcinvf (float y) |
| +__device__ float | erfcxf (float x) |
| +__device__ float | erff (float x) |
| +__device__ float | erfinvf (float y) |
| +__device__ float | exp2f (float x) |
| +__device__ float | expm1f (float x) |
| +__device__ float | fabsf (float x) |
| +__device__ float | fdimf (float x, float y) |
| +__device__ __host__ float | fdividef (float x, float y) |
| +__device__ float | floorf (float x) |
| +__device__ float | fmaf (float x, float y, float z) |
| +__device__ float | fmaxf (float x, float y) |
| +__device__ float | fminf (float x, float y) |
| +__device__ float | fmodf (float x, float y) |
| +__device__ float | frexpf (float x, float y) |
| +__device__ float | hypotf (float x, float y) |
| +__device__ float | ilogbf (float x) |
| +__host__ __device__ unsigned | isfinite (float a) |
| +__device__ unsigned | isinf (float a) |
| +__device__ unsigned | isnan (float a) |
| +__device__ float | j0f (float x) |
| +__device__ float | j1f (float x) |
| +__device__ float | jnf (int n, float x) |
| +__device__ float | ldexpf (float x, int exp) |
| +__device__ float | lgammaf (float x) |
| +__device__ long long int | llrintf (float x) |
| +__device__ long long int | llroundf (float x) |
| +__device__ float | log1pf (float x) |
| +__device__ float | logbf (float x) |
| +__device__ long int | lrintf (float x) |
| +__device__ long int | lroundf (float x) |
| +__device__ float | modff (float x, float *iptr) |
| +__device__ float | nanf (const char *tagp) |
| +__device__ float | nearbyintf (float x) |
| +__device__ float | nextafterf (float x, float y) |
| +__device__ float | norm3df (float a, float b, float c) |
| +__device__ float | norm4df (float a, float b, float c, float d) |
| +__device__ float | normcdff (float y) |
| +__device__ float | normcdfinvf (float y) |
| +__device__ float | normf (int dim, const float *a) |
| +__device__ float | rcbrtf (float x) |
| +__device__ float | remainderf (float x, float y) |
| +__device__ float | remquof (float x, float y, int *quo) |
| +__device__ float | rhypotf (float x, float y) |
| +__device__ float | rintf (float x) |
| +__device__ float | rnorm3df (float a, float b, float c) |
| +__device__ float | rnorm4df (float a, float b, float c, float d) |
| +__device__ float | rnormf (int dim, const float *a) |
| +__device__ float | roundf (float x) |
| +__device__ float | rsqrtf (float x) |
| +__device__ float | scalblnf (float x, long int n) |
| +__device__ float | scalbnf (float x, int n) |
| +__host__ __device__ unsigned | signbit (float a) |
| +__device__ void | sincospif (float x, float *sptr, float *cptr) |
| +__device__ float | sinhf (float x) |
| +__device__ float | sinpif (float x) |
| +__device__ float | sqrtf (float x) |
| +__device__ float | tanhf (float x) |
| +__device__ float | tgammaf (float x) |
| +__device__ float | truncf (float x) |
| +__device__ float | y0f (float x) |
| +__device__ float | y1f (float x) |
| +__device__ float | ynf (int n, float x) |
| +__host__ __device__ float | cospif (float x) |
| +__device__ double | acos (double x) |
| +__device__ double | acosh (double x) |
| +__device__ double | asin (double x) |
| +__device__ double | asinh (double x) |
| +__device__ double | atan (double x) |
| +__device__ double | atan2 (double y, double x) |
| +__device__ double | atanh (double x) |
| +__device__ double | cbrt (double x) |
| +__device__ double | ceil (double x) |
| +__device__ double | copysign (double x, double y) |
| +__device__ double | cos (double x) |
| +__device__ double | cosh (double x) |
| +__host__ __device__ double | cospi (double x) |
| +__device__ double | cyl_bessel_i0 (double x) |
| +__device__ double | cyl_bessel_i1 (double x) |
| +__device__ double | erf (double x) |
| +__device__ double | erfc (double x) |
| +__device__ double | erfcinv (double y) |
| +__device__ double | erfcx (double x) |
| +__device__ double | erfinv (double x) |
| +__device__ double | exp (double x) |
| +__device__ double | exp10 (double x) |
| +__device__ double | exp2 (double x) |
| +__device__ double | expm1 (double x) |
| +__device__ double | fabs (double x) |
| +__device__ double | fdim (double x, double y) |
| +__device__ double | fdivide (double x, double y) |
| +__device__ double | floor (double x) |
| +__device__ double | fma (double x, double y, double z) |
| +__device__ double | fmax (double x, double y) |
| +__device__ double | fmin (double x, double y) |
| +__device__ double | fmod (double x, double y) |
| +__device__ double | frexp (double x, int *nptr) |
| +__device__ double | hypot (double x, double y) |
| +__device__ double | ilogb (double x) |
| +__host__ __device__ unsigned | isfinite (double x) |
| +__device__ unsigned | isinf (double x) |
| +__device__ unsigned | isnan (double x) |
| +__device__ double | j0 (double x) |
| +__device__ double | j1 (double x) |
| +__device__ double | jn (int n, double x) |
| +__device__ double | ldexp (double x, int exp) |
| +__device__ double | lgamma (double x) |
| +__device__ long long | llrint (double x) |
| +__device__ long long | llround (double x) |
| +__device__ double | log (double x) |
| +__device__ double | log10 (double x) |
| +__device__ double | log1p (double x) |
| +__device__ double | log2 (double x) |
| +__device__ double | logb (double x) |
| +__device__ long int | lrint (double x) |
| +__device__ long int | lround (double x) |
| +__device__ double | modf (double x, double *iptr) |
| +__device__ double | nan (const char *tagp) |
| +__device__ double | nearbyint (double x) |
| +__device__ double | nextafter (double x, double y) |
| +__device__ double | norm (int dim, const double *t) |
| +__device__ double | norm3d (double a, double b, double c) |
| +__device__ double | norm4d (double a, double b, double c, double d) |
| +__device__ double | normcdf (double y) |
| +__device__ double | normcdfinv (double y) |
| +__device__ double | pow (double x, double y) |
| +__device__ double | rcbrt (double x) |
| +__device__ double | remainder (double x, double y) |
| +__device__ double | remquo (double x, double y, int *quo) |
| +__device__ double | rhypot (double x, double y) |
| +__device__ double | rint (double x) |
| +__device__ double | rnorm (int dim, const double *t) |
| +__device__ double | rnorm3d (double a, double b, double c) |
| +__device__ double | rnorm4d (double a, double b, double c, double d) |
| +__device__ double | round (double x) |
| +__host__ __device__ double | rsqrt (double x) |
| +__device__ double | scalbln (double x, long int n) |
| +__device__ double | scalbn (double x, int n) |
| +__host__ __device__ unsigned | signbit (double a) |
| +__device__ double | sin (double a) |
| +__device__ void | sincos (double x, double *sptr, double *cptr) |
| +__device__ void | sincospi (double x, double *sptr, double *cptr) |
| +__device__ double | sinh (double x) |
| +__host__ __device__ double | sinpi (double x) |
| +__device__ double | sqrt (double x) |
| +__device__ double | tan (double x) |
| +__device__ double | tanh (double x) |
| +__device__ double | tgamma (double x) |
| +__device__ double | trunc (double x) |
| +__device__ double | y0 (double x) |
| +__device__ double | y1 (double y) |
| +__device__ double | yn (int n, double x) |
| +__device__ long long int | clock64 () |
| +__device__ clock_t | clock () |
| +__device__ int | atomicAdd (int *address, int val) |
| +__device__ unsigned int | atomicAdd (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicAdd (unsigned long long int *address, unsigned long long int val) |
| +__device__ float | atomicAdd (float *address, float val) |
| +__device__ int | atomicSub (int *address, int val) |
| +__device__ unsigned int | atomicSub (unsigned int *address, unsigned int val) |
| +__device__ int | atomicExch (int *address, int val) |
| +__device__ unsigned int | atomicExch (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicExch (unsigned long long int *address, unsigned long long int val) |
| +__device__ float | atomicExch (float *address, float val) |
| +__device__ int | atomicMin (int *address, int val) |
| +__device__ unsigned int | atomicMin (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicMin (unsigned long long int *address, unsigned long long int val) |
| +__device__ int | atomicMax (int *address, int val) |
| +__device__ unsigned int | atomicMax (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicMax (unsigned long long int *address, unsigned long long int val) |
| +__device__ int | atomicCAS (int *address, int compare, int val) |
| +__device__ unsigned int | atomicCAS (unsigned int *address, unsigned int compare, unsigned int val) |
| +__device__ unsigned long long int | atomicCAS (unsigned long long int *address, unsigned long long int compare, unsigned long long int val) |
| +__device__ int | atomicAnd (int *address, int val) |
| +__device__ unsigned int | atomicAnd (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicAnd (unsigned long long int *address, unsigned long long int val) |
| +__device__ int | atomicOr (int *address, int val) |
| +__device__ unsigned int | atomicOr (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicOr (unsigned long long int *address, unsigned long long int val) |
| +__device__ int | atomicXor (int *address, int val) |
| +__device__ unsigned int | atomicXor (unsigned int *address, unsigned int val) |
| +__device__ unsigned long long int | atomicXor (unsigned long long int *address, unsigned long long int val) |
| +__device__ unsigned int | atomicInc (unsigned int *address, unsigned int val) |
| +__device__ unsigned int | atomicDec (unsigned int *address, unsigned int val) |
| +__device__ int | __mul24 (int arg1, int arg2) |
| +__device__ unsigned int | __umul24 (unsigned int arg1, unsigned int arg2) |
| +__device__ unsigned int | __popc (unsigned int input) |
| +__device__ unsigned int | __popcll (unsigned long long int input) |
| +__device__ unsigned int | __clz (unsigned int input) |
| +__device__ unsigned int | __clzll (unsigned long long int input) |
| +__device__ unsigned int | __clz (int input) |
| +__device__ unsigned int | __clzll (long long int input) |
| +__device__ unsigned int | __ffs (unsigned int input) |
| +__device__ unsigned int | __ffsll (unsigned long long int input) |
| +__device__ unsigned int | __ffs (int input) |
| +__device__ unsigned int | __ffsll (long long int input) |
| +__device__ unsigned int | __brev (unsigned int input) |
| +__device__ unsigned long long int | __brevll (unsigned long long int input) |
| +__device__ int | __all (int input) |
| +__device__ int | __any (int input) |
| +__device__ unsigned long long int | __ballot (int input) |
| +__device__ int | __shfl (int input, int lane, int width) |
| +__device__ int | __shfl_up (int input, unsigned int lane_delta, int width) |
| +__device__ int | __shfl_down (int input, unsigned int lane_delta, int width) |
| +__device__ int | __shfl_xor (int input, int lane_mask, int width) |
| +__device__ float | __shfl (float input, int lane, int width) |
| +__device__ float | __shfl_up (float input, unsigned int lane_delta, int width) |
| +__device__ float | __shfl_down (float input, unsigned int lane_delta, int width) |
| +__device__ float | __shfl_xor (float input, int lane_mask, int width) |
| +__host__ __device__ int | min (int arg1, int arg2) |
| +__host__ __device__ int | max (int arg1, int arg2) |
| +__device__ | __attribute__ ((address_space(3))) void *__get_dynamicgroupbaseptr() |
| +__device__ float | __hip_precise_cosf (float) |
| +__device__ float | __hip_precise_exp10f (float) |
| +__device__ float | __hip_precise_expf (float) |
| +__device__ float | __hip_precise_frsqrt_rn (float) |
| +__device__ float | __hip_precise_fsqrt_rd (float) |
| +__device__ float | __hip_precise_fsqrt_rn (float) |
| +__device__ float | __hip_precise_fsqrt_ru (float) |
| +__device__ float | __hip_precise_fsqrt_rz (float) |
| +__device__ float | __hip_precise_log10f (float) |
| +__device__ float | __hip_precise_log2f (float) |
| +__device__ float | __hip_precise_logf (float) |
| +__device__ float | __hip_precise_powf (float, float) |
| +__device__ void | __hip_precise_sincosf (float, float *, float *) |
| +__device__ float | __hip_precise_sinf (float) |
| +__device__ float | __hip_precise_tanf (float) |
| +__device__ double | __hip_precise_dsqrt_rd (double) |
| +__device__ double | __hip_precise_dsqrt_rn (double) |
| +__device__ double | __hip_precise_dsqrt_ru (double) |
| +__device__ double | __hip_precise_dsqrt_rz (double) |
| + | __attribute__ ((const)) float __hip_fast_cosf(float) __asm("llvm.cos.f32") |
| +__device__ float | __hip_fast_exp10f (float) |
| +__device__ float | __hip_fast_expf (float) |
| +__device__ float | __hip_fast_frsqrt_rn (float) |
| +__device__ float | __hip_fast_fsqrt_rn (float) |
| +__device__ float | __hip_fast_fsqrt_ru (float) |
| +__device__ float | __hip_fast_fsqrt_rz (float) |
| +__device__ float | __hip_fast_log10f (float) |
| +__device__ float | __hip_fast_logf (float) |
| +__device__ float | __hip_fast_powf (float, float) |
| +__device__ void | __hip_fast_sincosf (float, float *, float *) |
| +__device__ float | __hip_fast_tanf (float) |
| +float | __asm ("llvm.fma.f32") |
| +double | __asm ("llvm.fma.f64") |
| +__device__ float | sinf (float) |
| +__device__ float | cosf (float) |
| +__device__ float | tanf (float) |
| +__device__ void | sincosf (float, float *, float *) |
| +__device__ float | logf (float) |
| +__device__ float | log2f (float) |
| +__device__ float | log10f (float) |
| +__device__ float | expf (float) |
| +__device__ float | exp10f (float) |
| +__device__ float | powf (float, float) |
| +__device__ float | __cosf (float x) |
| +__device__ float | __exp10f (float x) |
| +__device__ float | __expf (float x) |
| +__device__ float | __frsqrt_rn (float x) |
| +__device__ float | __fsqrt_rd (float x) |
| +__device__ float | __fsqrt_rn (float x) |
| +__device__ float | __fsqrt_ru (float x) |
| +__device__ float | __fsqrt_rz (float x) |
| +__device__ float | __log10f (float x) |
| +__device__ float | __log2f (float x) |
| +__device__ float | __logf (float x) |
| +__device__ float | __powf (float base, float exponent) |
| +__device__ void | __sincosf (float x, float *s, float *c) |
| +__device__ float | __sinf (float x) |
| +__device__ float | __tanf (float x) |
| +__device__ float | __fmaf_rd (float x, float y, float z) |
| +__device__ float | __fmaf_rn (float x, float y, float z) |
| +__device__ float | __fmaf_ru (float x, float y, float z) |
| +__device__ float | __fmaf_rz (float x, float y, float z) |
| +__device__ float | __frcp_rd (float x) |
| +__device__ float | __frcp_rn (float x) |
| +__device__ float | __frcp_ru (float x) |
| +__device__ float | __frcp_rz (float x) |
| +__device__ double | __dsqrt_rd (double x) |
| +__device__ double | __dsqrt_rn (double x) |
| +__device__ double | __dsqrt_ru (double x) |
| +__device__ double | __dsqrt_rz (double x) |
| +__device__ double | __fma_rd (double x, double y, double z) |
| +__device__ double | __fma_rn (double x, double y, double z) |
| +__device__ double | __fma_ru (double x, double y, double z) |
| +__device__ double | __fma_rz (double x, double y, double z) |
| +__device__ double | __drcp_rd (double x) |
| +__device__ double | __drcp_rn (double x) |
| +__device__ double | __drcp_ru (double x) |
| +__device__ double | __drcp_rz (double x) |
| __device__ void | __threadfence_block (void) |
| threadfence_block makes writes visible to threads running in same block. More... | |
| __device__ void | __threadfence (void) |
| threadfence makes wirtes visible to other threads running on same GPU. More... | |
| __device__ void | __threadfence_system (void) |
| threadfence_system makes writes to pinned system memory visible on host CPU. More... | |
| +__device__ unsigned | __hip_ds_bpermute (int index, unsigned src) |
| +__device__ float | __hip_ds_bpermutef (int index, float src) |
| +__device__ unsigned | __hip_ds_permute (int index, unsigned src) |
| +__device__ float | __hip_ds_permutef (int index, float src) |
| +__device__ unsigned | __hip_ds_swizzle (unsigned int src, int pattern) |
| +__device__ float | __hip_ds_swizzlef (float src, int pattern) |
| +__device__ int | __hip_move_dpp (int src, int dpp_ctrl, int row_mask, int bank_mask, bool bound_ctrl) |
| +__device__ void * | __hip_hc_malloc (size_t) |
| +__device__ void * | __hip_hc_free (void *ptr) |
| +__device__ char4 | __hip_hc_add8pk (char4, char4) |
| +__device__ char4 | __hip_hc_sub8pk (char4, char4) |
| +__device__ char4 | __hip_hc_mul8pk (char4, char4) |
+Variables | |
| +int | HIP_TRACE_API |
| +const int | warpSize |
| + | float |
| + | double |
Contains definitions of APIs for HIP runtime.
+| #define HIP_DYNAMIC_SHARED | +( | ++ | type, | +
| + | + | + | var | +
| + | ) | ++ |
extern shared
+ +
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__runtime_8h_source.html b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime_8h_source.html
new file mode 100644
index 0000000000..7ad654c0d0
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime_8h_source.html
@@ -0,0 +1,915 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__runtime__api_8h.html b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime__api_8h.html
new file mode 100644
index 0000000000..5de643b669
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime__api_8h.html
@@ -0,0 +1,589 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
Contains C function APIs for HIP runtime. This file does not use any HCC builtin or special language extensions (-hc mode) ; those functions in hip_runtime.h. +More...
+#include <stdint.h>#include <stddef.h>#include <hip/hcc_detail/host_defines.h>#include <hip/hip_runtime_api.h>Go to the source code of this file.
++Classes | |
| struct | dim3 |
+Macros | |
| +#define | HIP_LAUNCH_PARAM_BUFFER_POINTER ((void*) 0x01) |
| +#define | HIP_LAUNCH_PARAM_BUFFER_SIZE ((void*) 0x02) |
| +#define | HIP_LAUNCH_PARAM_END ((void*) 0x03) |
| +#define | hipIpcMemLazyEnablePeerAccess 0 |
| #define | hipStreamDefault 0x00 |
| Flags that can be used with hipStreamCreateWithFlags. More... | |
| +#define | hipStreamNonBlocking 0x01 |
| Stream does not implicitly synchronize with null stream. | |
| #define | hipEventDefault 0x0 |
| Flags that can be used with hipEventCreateWithFlags: More... | |
| +#define | hipEventBlockingSync 0x1 |
| Waiting will yield CPU. Power-friendly and usage-friendly but may increase latency. | |
| +#define | hipEventDisableTiming 0x2 |
| Disable event's capability to record timing information. May improve performance. | |
| #define | hipEventInterprocess 0x4 |
| Event can support IPC. More... | |
| +#define | hipHostMallocDefault 0x0 |
| Flags that can be used with hipHostMalloc. | |
| +#define | hipHostMallocPortable 0x1 |
| +#define | hipHostMallocMapped 0x2 |
| +#define | hipHostMallocWriteCombined 0x4 |
| #define | hipHostRegisterDefault 0x0 |
| Flags that can be used with hipHostRegister. More... | |
| +#define | hipHostRegisterPortable 0x1 |
| Memory is considered registered by all contexts. HIP only supports one context so this is always assumed true. | |
| +#define | hipHostRegisterMapped 0x2 |
| Map the allocation into the address space for the current device. The device pointer can be obtained with hipHostGetDevicePointer. | |
| +#define | hipHostRegisterIoMemory 0x4 |
| Not supported. | |
| +#define | hipDeviceScheduleAuto 0x0 |
| Automatically select between Spin and Yield. | |
| +#define | hipDeviceScheduleSpin 0x1 |
| Dedicate a CPU core to spin-wait. Provides lowest latency, but burns a CPU core and may consume more power. | |
| +#define | hipDeviceScheduleYield 0x2 |
| Yield the CPU to the operating system when waiting. May increase latency, but lowers power and is friendlier to other threads in the system. | |
| +#define | hipDeviceScheduleBlockingSync 0x4 |
| +#define | hipDeviceScheduleMask 0x7 |
| +#define | hipDeviceMapHost 0x8 |
| +#define | hipDeviceLmemResizeToMax 0x16 |
| +#define | USE_PEER_NON_UNIFIED 1 |
+Typedefs | |
| +typedef struct ihipCtx_t * | hipCtx_t |
| +typedef struct ihipDevice_t * | hipDevice_t |
| +typedef struct ihipStream_t * | hipStream_t |
| +typedef struct ihipIpcMemHandle_t * | hipIpcMemHandle_t |
|
+typedef struct +ihipIpcEventHandle_t * | hipIpcEventHandle_t |
| +typedef struct ihipModule_t * | hipModule_t |
| +typedef struct ihipFunction_t * | hipFunction_t |
| +typedef void * | hipDeviceptr_t |
| +typedef struct ihipEvent_t * | hipEvent_t |
| typedef enum hipFuncCache_t | hipFuncCache_t |
| typedef enum hipSharedMemConfig | hipSharedMemConfig |
| typedef struct dim3 | dim3 |
| typedef enum hipMemcpyKind | hipMemcpyKind |
| typedef void(* | hipStreamCallback_t )(hipStream_t stream, hipError_t status, void *userData) |
+Enumerations | |
| enum | hipLimit_t { hipLimitMallocHeapSize = 0x02 + } |
| enum | hipFuncCache_t { hipFuncCachePreferNone, +hipFuncCachePreferShared, +hipFuncCachePreferL1, +hipFuncCachePreferEqual + } |
| enum | hipSharedMemConfig { hipSharedMemBankSizeDefault, +hipSharedMemBankSizeFourByte, +hipSharedMemBankSizeEightByte + } |
| enum | hipMemcpyKind { + hipMemcpyHostToHost = 0, +hipMemcpyHostToDevice = 1, +hipMemcpyDeviceToHost = 2, +hipMemcpyDeviceToDevice =3, + + hipMemcpyDefault = 4 + + } |
+Functions | |
| hipError_t | hipDeviceSynchronize (void) |
| Waits on all active streams on current device. More... | |
| hipError_t | hipDeviceReset (void) |
| The state of current device is discarded and updated to a fresh state. More... | |
| hipError_t | hipSetDevice (int deviceId) |
| Set default device to be used for subsequent hip API calls from this thread. More... | |
| hipError_t | hipGetDevice (int *deviceId) |
| Return the default device id for the calling host thread. More... | |
| hipError_t | hipGetDeviceCount (int *count) |
| Return number of compute-capable devices. More... | |
| hipError_t | hipDeviceGetAttribute (int *pi, hipDeviceAttribute_t attr, int deviceId) |
| Query for a specific device attribute. More... | |
| hipError_t | hipGetDeviceProperties (hipDeviceProp_t *prop, int deviceId) |
| Returns device properties. More... | |
| hipError_t | hipDeviceSetCacheConfig (hipFuncCache_t cacheConfig) |
| Set L1/Shared cache partition. More... | |
| hipError_t | hipDeviceGetCacheConfig (hipFuncCache_t *cacheConfig) |
| Set Cache configuration for a specific function. More... | |
| hipError_t | hipDeviceGetLimit (size_t *pValue, hipLimit_t limit) |
| Get Resource limits of current device. More... | |
| hipError_t | hipFuncSetCacheConfig (hipFuncCache_t config) |
| Set Cache configuration for a specific function. More... | |
| hipError_t | hipDeviceGetSharedMemConfig (hipSharedMemConfig *pConfig) |
| Returns bank width of shared memory for current device. More... | |
| hipError_t | hipDeviceSetSharedMemConfig (hipSharedMemConfig config) |
| The bank width of shared memory on current device is set. More... | |
| hipError_t | hipSetDeviceFlags (unsigned flags) |
| The current device behavior is changed according the flags passed. More... | |
| hipError_t | hipChooseDevice (int *device, const hipDeviceProp_t *prop) |
| Device which matches hipDeviceProp_t is returned. More... | |
| hipError_t | hipGetLastError (void) |
| Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess. More... | |
| hipError_t | hipPeekAtLastError (void) |
| Return last error returned by any HIP runtime API call. More... | |
| const char * | hipGetErrorName (hipError_t hip_error) |
| Return name of the specified error code in text form. More... | |
| const char * | hipGetErrorString (hipError_t hipError) |
| Return handy text string message to explain the error which occurred. More... | |
| hipError_t | hipStreamCreate (hipStream_t *stream) |
| Create an asynchronous stream. More... | |
| hipError_t | hipStreamCreateWithFlags (hipStream_t *stream, unsigned int flags) |
| Create an asynchronous stream. More... | |
| hipError_t | hipStreamDestroy (hipStream_t stream) |
| Destroys the specified stream. More... | |
| hipError_t | hipStreamQuery (hipStream_t stream) |
Return hipSuccess if all of the operations in the specified stream have completed, or hipErrorNotReady if not. More... | |
| hipError_t | hipStreamSynchronize (hipStream_t stream) |
| Wait for all commands in stream to complete. More... | |
| hipError_t | hipStreamWaitEvent (hipStream_t stream, hipEvent_t event, unsigned int flags) |
| Make the specified compute stream wait for an event. More... | |
| hipError_t | hipStreamGetFlags (hipStream_t stream, unsigned int *flags) |
| Return flags associated with this stream. More... | |
| hipError_t | hipStreamAddCallback (hipStream_t stream, hipStreamCallback_t callback, void *userData, unsigned int flags) |
| Adds a callback to be called on the host after all currently enqueued items in the stream have completed. For each cudaStreamAddCallback call, a callback will be executed exactly once. The callback will block later work in the stream until it is finished. More... | |
| hipError_t | hipEventCreateWithFlags (hipEvent_t *event, unsigned flags) |
| Create an event with the specified flags. More... | |
| hipError_t | hipEventCreate (hipEvent_t *event) |
| hipError_t | hipEventRecord (hipEvent_t event, hipStream_t stream) |
| Record an event in the specified stream. More... | |
| hipError_t | hipEventDestroy (hipEvent_t event) |
| Destroy the specified event. More... | |
| hipError_t | hipEventSynchronize (hipEvent_t event) |
| Wait for an event to complete. More... | |
| hipError_t | hipEventElapsedTime (float *ms, hipEvent_t start, hipEvent_t stop) |
| Return the elapsed time between two events. More... | |
| hipError_t | hipEventQuery (hipEvent_t event) |
| Query event status. More... | |
| hipError_t | hipPointerGetAttributes (hipPointerAttribute_t *attributes, void *ptr) |
| Return attributes for the specified pointer. More... | |
| hipError_t | hipMalloc (void **ptr, size_t size) |
| Allocate memory on the default accelerator. More... | |
| hipError_t | hipMallocHost (void **ptr, size_t size) __attribute__((deprecated("use hipHostMalloc instead"))) |
| Allocate pinned host memory [Deprecated]. More... | |
| hipError_t | hipHostMalloc (void **ptr, size_t size, unsigned int flags) |
| Allocate device accessible page locked host memory. More... | |
| hipError_t | hipHostAlloc (void **ptr, size_t size, unsigned int flags) __attribute__((deprecated("use hipHostMalloc instead"))) |
| Allocate device accessible page locked host memory [Deprecated]. More... | |
| hipError_t | hipHostGetDevicePointer (void **devPtr, void *hstPtr, unsigned int flags) |
| Get Device pointer from Host Pointer allocated through hipHostMalloc. More... | |
| hipError_t | hipHostGetFlags (unsigned int *flagsPtr, void *hostPtr) |
| Return flags associated with host pointer. More... | |
| hipError_t | hipHostRegister (void *hostPtr, size_t sizeBytes, unsigned int flags) |
| Register host memory so it can be accessed from the current device. More... | |
| hipError_t | hipHostUnregister (void *hostPtr) |
| Un-register host pointer. More... | |
| hipError_t | hipMallocPitch (void **ptr, size_t *pitch, size_t width, size_t height) |
| hipError_t | hipFree (void *ptr) |
| Free memory allocated by the hcc hip memory allocation API. This API performs an implicit hipDeviceSynchronize() call. If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. More... | |
| hipError_t | hipFreeHost (void *ptr) __attribute__((deprecated("use hipHostFree instead"))) |
| Free memory allocated by the hcc hip host memory allocation API. [Deprecated]. More... | |
| hipError_t | hipHostFree (void *ptr) |
| Free memory allocated by the hcc hip host memory allocation API This API performs an implicit hipDeviceSynchronize() call. If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. More... | |
| hipError_t | hipMemcpy (void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind) |
| Copy data from src to dst. More... | |
| hipError_t | hipMemcpyHtoD (hipDeviceptr_t dst, void *src, size_t sizeBytes) |
| Copy data from Host to Device. More... | |
| hipError_t | hipMemcpyDtoH (void *dst, hipDeviceptr_t src, size_t sizeBytes) |
| Copy data from Device to Host. More... | |
| hipError_t | hipMemcpyDtoD (hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes) |
| Copy data from Device to Device. More... | |
| hipError_t | hipMemcpyHtoDAsync (hipDeviceptr_t dst, void *src, size_t sizeBytes, hipStream_t stream) |
| Copy data from Host to Device asynchronously. More... | |
| hipError_t | hipMemcpyDtoHAsync (void *dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream) |
| Copy data from Device to Host asynchronously. More... | |
| hipError_t | hipMemcpyDtoDAsync (hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream) |
| Copy data from Device to Device asynchronously. More... | |
| hipError_t | hipMemcpyToSymbol (const char *symbolName, const void *src, size_t sizeBytes, size_t offset, hipMemcpyKind kind) |
Copies sizeBytes bytes from the memory area pointed to by src to the memory area pointed to by offset bytes from the start of symbol symbol. More... | |
| hipError_t | hipMemcpyToSymbolAsync (const char *symbolName, const void *src, size_t sizeBytes, size_t offset, hipMemcpyKind kind, hipStream_t stream) |
Copies sizeBytes bytes from the memory area pointed to by src to the memory area pointed to by offset bytes from the start of symbol symbol. More... | |
| hipError_t | hipMemcpyAsync (void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind, hipStream_t stream) |
| Copy data from src to dst asynchronously. More... | |
| hipError_t | hipMemset (void *dst, int value, size_t sizeBytes) |
| Copy data from src to dst asynchronously. More... | |
| hipError_t | hipMemsetAsync (void *dst, int value, size_t sizeBytes, hipStream_t stream) |
| Fills the first sizeBytes bytes of the memory area pointed to by dev with the constant byte value value. More... | |
| hipError_t | hipMemGetInfo (size_t *free, size_t *total) |
| Query memory info. Return snapshot of free memory, and total allocatable memory on the device. More... | |
| hipError_t | hipDeviceCanAccessPeer (int *canAccessPeer, int deviceId, int peerDeviceId) |
| Determine if a device can access a peer's memory. More... | |
| hipError_t | hipDeviceEnablePeerAccess (int peerDeviceId, unsigned int flags) |
| Enable direct access from current device's virtual address space to memory allocations physically located on a peer device. More... | |
| hipError_t | hipDeviceDisablePeerAccess (int peerDeviceId) |
| Disable direct access from current device's virtual address space to memory allocations physically located on a peer device. More... | |
| hipError_t | hipMemGetAddressRange (hipDeviceptr_t *pbase, size_t *psize, hipDeviceptr_t dptr) |
| Get information on memory allocations. More... | |
| hipError_t | hipMemcpyPeer (void *dst, int dstDeviceId, const void *src, int srcDeviceId, size_t sizeBytes) |
| Copies memory from one device to memory on another device. More... | |
| hipError_t | hipMemcpyPeerAsync (void *dst, int dstDevice, const void *src, int srcDevice, size_t sizeBytes, hipStream_t stream) |
| Copies memory from one device to memory on another device. More... | |
| hipError_t | hipInit (unsigned int flags) |
| Explicitly initializes the HIP runtime. More... | |
| hipError_t | hipCtxCreate (hipCtx_t *ctx, unsigned int flags, hipDevice_t device) |
| Create a context and set it as current/ default context. More... | |
| hipError_t | hipCtxDestroy (hipCtx_t ctx) |
| Destroy a HIP context. More... | |
| hipError_t | hipCtxPopCurrent (hipCtx_t *ctx) |
| Pop the current/default context and return the popped context. More... | |
| hipError_t | hipCtxPushCurrent (hipCtx_t ctx) |
| Push the context to be set as current/ default context. More... | |
| hipError_t | hipCtxSetCurrent (hipCtx_t ctx) |
| Set the passed context as current/default. More... | |
| hipError_t | hipCtxGetCurrent (hipCtx_t *ctx) |
| Get the handle of the current/ default context. More... | |
| hipError_t | hipCtxGetDevice (hipDevice_t *device) |
| Get the handle of the device associated with current/default context. More... | |
| hipError_t | hipCtxGetApiVersion (hipCtx_t ctx, int *apiVersion) |
| Returns the approximate HIP api version. More... | |
| hipError_t | hipCtxGetCacheConfig (hipFuncCache_t *cacheConfig) |
| Set Cache configuration for a specific function. More... | |
| hipError_t | hipCtxSetCacheConfig (hipFuncCache_t cacheConfig) |
| Set L1/Shared cache partition. More... | |
| hipError_t | hipCtxSetSharedMemConfig (hipSharedMemConfig config) |
| Set Shared memory bank configuration. More... | |
| hipError_t | hipCtxGetSharedMemConfig (hipSharedMemConfig *pConfig) |
| Get Shared memory bank configuration. More... | |
| hipError_t | hipCtxSynchronize (void) |
| Blocks until the default context has completed all preceding requested tasks. More... | |
| hipError_t | hipCtxGetFlags (unsigned int *flags) |
| Return flags used for creating default context. More... | |
| hipError_t | hipCtxEnablePeerAccess (hipCtx_t peerCtx, unsigned int flags) |
| Enables direct access to memory allocations in a peer context. More... | |
| hipError_t | hipCtxDisablePeerAccess (hipCtx_t peerCtx) |
| Disable direct access from current context's virtual address space to memory allocations physically located on a peer context.Disables direct access to memory allocations in a peer context and unregisters any registered allocations. More... | |
| hipError_t | hipDeviceGet (hipDevice_t *device, int ordinal) |
| Returns a handle to a compute device. More... | |
| hipError_t | hipDeviceComputeCapability (int *major, int *minor, hipDevice_t device) |
| Returns the compute capability of the device. More... | |
| hipError_t | hipDeviceGetName (char *name, int len, hipDevice_t device) |
| Returns an identifer string for the device. More... | |
| hipError_t | hipDeviceGetPCIBusId (char *pciBusId, int len, int device) |
| Returns a PCI Bus Id string for the device, overloaded to take int device ID. More... | |
| hipError_t | hipDeviceGetByPCIBusId (int *device, const int *pciBusId) |
| Returns a handle to a compute device. More... | |
| hipError_t | hipDeviceTotalMem (size_t *bytes, hipDevice_t device) |
| Returns the total amount of memory on the device. More... | |
| hipError_t | hipDriverGetVersion (int *driverVersion) |
| Returns the approximate HIP driver version. More... | |
| hipError_t | hipRuntimeGetVersion (int *runtimeVersion) |
| Returns the approximate HIP Runtime version. More... | |
| hipError_t | hipModuleLoad (hipModule_t *module, const char *fname) |
| Loads code object from file into a hipModule_t. More... | |
| hipError_t | hipModuleUnload (hipModule_t module) |
| Frees the module. More... | |
| hipError_t | hipModuleGetFunction (hipFunction_t *function, hipModule_t module, const char *kname) |
| Function with kname will be extracted if present in module. More... | |
| hipError_t | hipModuleGetGlobal (hipDeviceptr_t *dptr, size_t *bytes, hipModule_t hmod, const char *name) |
returns device memory pointer and size of the kernel present in the module with symbol name More... | |
| hipError_t | hipModuleLoadData (hipModule_t *module, const void *image) |
| builds module from code object which resides in host memory. Image is pointer to that location. More... | |
| hipError_t | hipModuleLaunchKernel (hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, hipStream_t stream, void **kernelParams, void **extra) |
| launches kernel f with launch parameters and shared memory on stream with arguments passed to kernelparams or extra More... | |
| hipError_t | hipProfilerStart () |
| Start recording of profiling information When using this API, start the profiler with profiling disabled. (–startdisabled) More... | |
| hipError_t | hipProfilerStop () |
| Stop recording of profiling information. When using this API, start the profiler with profiling disabled. (–startdisabled) More... | |
| hipError_t | hipIpcGetMemHandle (hipIpcMemHandle_t *handle, void *devPtr) |
| Gets an interprocess memory handle for an existing device memory allocation. More... | |
| hipError_t | hipIpcOpenMemHandle (void **devPtr, hipIpcMemHandle_t handle, unsigned int flags) |
| Opens an interprocess memory handle exported from another process and returns a device pointer usable in the local process. More... | |
| hipError_t | hipIpcCloseMemHandle (void *devPtr) |
| Close memory mapped with hipIpcOpenMemHandle. More... | |
Contains C function APIs for HIP runtime. This file does not use any HCC builtin or special language extensions (-hc mode) ; those functions in hip_runtime.h.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__runtime__api_8h_source.html b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime__api_8h_source.html
new file mode 100644
index 0000000000..16efd64a38
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__runtime__api_8h_source.html
@@ -0,0 +1,718 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__texture_8h.html b/docs/RuntimeAPI/html/hcc__detail_2hip__texture_8h.html
new file mode 100644
index 0000000000..5aa672dda3
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__texture_8h.html
@@ -0,0 +1,560 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
HIP C++ Texture API for hcc compiler. +More...
+#include <limits.h>Go to the source code of this file.
++Classes | |
| struct | hipChannelFormatDesc |
| struct | textureReference |
| struct | hipArray |
+Typedefs | |
| +typedef struct hipChannelFormatDesc | hipChannelFormatDesc |
| +typedef enum hipTextureReadMode | hipTextureReadMode |
| +typedef enum hipTextureFilterMode | hipTextureFilterMode |
+Enumerations | |
| enum | hipChannelFormatKind { hipChannelFormatKindSigned = 0, +hipChannelFormatKindUnsigned, +hipChannelFormatKindFloat, +hipChannelFormatKindNone + } |
| enum | hipTextureReadMode { hipReadModeElementType + } |
| enum | hipTextureFilterMode { hipFilterModePoint + } |
+Functions | |
| hipError_t | hipMallocArray (hipArray **array, const hipChannelFormatDesc *desc, size_t width, size_t height=0, unsigned int flags=0) |
| Allocate an array on the device. More... | |
| hipError_t | hipFreeArray (hipArray *array) |
| Frees an array on the device. More... | |
| hipError_t | hipMemcpy2D (void *dst, size_t dpitch, const void *src, size_t spitch, size_t width, size_t height, hipMemcpyKind kind) |
| Copies data between host and device. More... | |
| hipError_t | hipMemcpy2DToArray (hipArray *dst, size_t wOffset, size_t hOffset, const void *src, size_t spitch, size_t width, size_t height, hipMemcpyKind kind) |
| Copies data between host and device. More... | |
| hipError_t | hipMemcpyToArray (hipArray *dst, size_t wOffset, size_t hOffset, const void *src, size_t count, hipMemcpyKind kind) |
| Copies data between host and device. More... | |
| hipChannelFormatDesc | hipCreateChannelDesc (int x, int y, int z, int w, hipChannelFormatKind f) |
| Returns a channel descriptor using the specified format. More... | |
| +template<typename T > | |
| hipChannelFormatDesc | hipCreateChannelDesc () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< int > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< unsigned int > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< long > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< unsigned long > () |
| +template<> | |
| hipChannelFormatDesc | hipCreateChannelDesc< float > () |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipBindTexture (size_t *offset, struct texture< T, dim, readMode > &tex, const void *devPtr, const struct hipChannelFormatDesc *desc, size_t size=UINT_MAX) |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipBindTexture (size_t *offset, struct texture< T, dim, readMode > &tex, const void *devPtr, size_t size=UINT_MAX) |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipBindTextureToArray (struct texture< T, dim, readMode > &tex, hipArray *array) |
| +template<class T , int dim, enum hipTextureReadMode readMode> | |
| hipError_t | hipUnbindTexture (struct texture< T, dim, readMode > &tex) |
HIP C++ Texture API for hcc compiler.
+| enum hipTextureFilterMode | +
| enum hipTextureReadMode | +
| hipError_t hipFreeArray | +( | +hipArray * | +array | ) | ++ |
Frees an array on the device.
+| [in] | array | Pointer to array to free |
| hipError_t hipMallocArray | +( | +hipArray ** | +array, | +
| + | + | const hipChannelFormatDesc * | +desc, | +
| + | + | size_t | +width, | +
| + | + | size_t | +height = 0, |
+
| + | + | unsigned int | +flags = 0 |
+
| + | ) | ++ |
Allocate an array on the device.
+| [out] | array | Pointer to allocated array in device memory |
| [in] | desc | Requested channel format |
| [in] | width | Requested array allocation width |
| [in] | height | Requested array allocation height |
| [in] | flags | Requested properties of allocated array |
| hipError_t hipMemcpy2D | +( | +void * | +dst, | +
| + | + | size_t | +dpitch, | +
| + | + | const void * | +src, | +
| + | + | size_t | +spitch, | +
| + | + | size_t | +width, | +
| + | + | size_t | +height, | +
| + | + | hipMemcpyKind | +kind | +
| + | ) | ++ |
Copies data between host and device.
+| [in] | dst | Destination memory address |
| [in] | dpitch | Pitch of destination memory |
| [in] | src | Source memory address |
| [in] | spitch | Pitch of source memory |
| [in] | width | Width of matrix transfer (columns in bytes) |
| [in] | height | Height of matrix transfer (rows) |
| [in] | kind | Type of transfer |
| hipError_t hipMemcpy2DToArray | +( | +hipArray * | +dst, | +
| + | + | size_t | +wOffset, | +
| + | + | size_t | +hOffset, | +
| + | + | const void * | +src, | +
| + | + | size_t | +spitch, | +
| + | + | size_t | +width, | +
| + | + | size_t | +height, | +
| + | + | hipMemcpyKind | +kind | +
| + | ) | ++ |
Copies data between host and device.
+| [in] | dst | Destination memory address |
| [in] | dpitch | Pitch of destination memory |
| [in] | src | Source memory address |
| [in] | spitch | Pitch of source memory |
| [in] | width | Width of matrix transfer (columns in bytes) |
| [in] | height | Height of matrix transfer (rows) |
| [in] | kind | Type of transfer |
| hipError_t hipMemcpyToArray | +( | +hipArray * | +dst, | +
| + | + | size_t | +wOffset, | +
| + | + | size_t | +hOffset, | +
| + | + | const void * | +src, | +
| + | + | size_t | +count, | +
| + | + | hipMemcpyKind | +kind | +
| + | ) | ++ |
Copies data between host and device.
+| [in] | dst | Destination memory address |
| [in] | dpitch | Pitch of destination memory |
| [in] | src | Source memory address |
| [in] | spitch | Pitch of source memory |
| [in] | width | Width of matrix transfer (columns in bytes) |
| [in] | height | Height of matrix transfer (rows) |
| [in] | kind | Type of transfer |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__texture_8h_source.html b/docs/RuntimeAPI/html/hcc__detail_2hip__texture_8h_source.html
new file mode 100644
index 0000000000..17dbbe2e7e
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__texture_8h_source.html
@@ -0,0 +1,333 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__vector__types_8h.html b/docs/RuntimeAPI/html/hcc__detail_2hip__vector__types_8h.html
new file mode 100644
index 0000000000..80b9f0458f
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__vector__types_8h.html
@@ -0,0 +1,431 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
Defines the different newt vector types for HIP runtime. +More...
+#include "hip/hcc_detail/host_defines.h"Go to the source code of this file.
++Classes | |
| struct | char3 |
| struct | uchar3 |
| struct | char4 |
| struct | uchar4 |
| struct | short3 |
| struct | ushort3 |
| struct | int3 |
| struct | uint3 |
| struct | long3 |
| struct | ulong3 |
| struct | float1 |
| struct | float3 |
| struct | longlong3 |
| struct | ulonglong3 |
| struct | double1 |
| struct | double3 |
+Macros | |
| #define | __hip_align(name, val, data) |
| +#define | __HIP_DEVICE__ __device__ __host__ |
+Functions | |
| +struct | __hip_align (char1, 1, signed char x;) |
| +struct | __hip_align (uchar1, 1, unsigned char x;) |
| +struct | __hip_align (char2, 2, signed char x;signed char y;) |
| +struct | __hip_align (uchar2, 2, unsigned char x;unsigned char y;) |
| +struct | __hip_align (short1, 2, signed short x;) |
| +struct | __hip_align (ushort1, 2, unsigned short x;) |
| +struct | __hip_align (short2, 4, signed short x;signed short y;) |
| +struct | __hip_align (ushort2, 4, unsigned short x;unsigned short y;) |
| +struct | __hip_align (short4, 8, signed short x;signed short y;signed short z;signed short w;) |
| +struct | __hip_align (ushort4, 8, unsigned short x;unsigned short y;unsigned short z;unsigned short w;) |
| +struct | __hip_align (int1, 4, signed int x;) |
| +struct | __hip_align (uint1, 4, unsigned int x;) |
| +struct | __hip_align (int2, 8, signed int x;signed int y;) |
| +struct | __hip_align (uint2, 8, unsigned int x;unsigned int y;) |
| +struct | __hip_align (int4, 16, signed int x;signed int y;signed int z;signed int w;) |
| +struct | __hip_align (uint4, 16, unsigned int x;unsigned int y;unsigned int z;unsigned int w;) |
| +struct | __hip_align (long1, 8, long int x;) |
| +struct | __hip_align (ulong1, 8, unsigned long x;) |
| +struct | __hip_align (long2, 16, long int x;long int y;) |
| +struct | __hip_align (ulong2, 16, unsigned long x;unsigned long y;) |
| +struct | __hip_align (long4, 32, long int x;long int y;long int z;long int w;) |
| +struct | __hip_align (ulong4, 32, unsigned long x;unsigned long y;unsigned long z;unsigned long w;) |
| +struct | __hip_align (float2, 8, float x;float y;) |
| +struct | __hip_align (float4, 16, float x;float y;float z;float w;) |
| +struct | __hip_align (longlong1, 16, long long int x;) |
| +struct | __hip_align (ulonglong1, 16, unsigned long long int x;) |
| +struct | __attribute__ ((aligned(32))) longlong2 |
| +struct | __attribute__ ((aligned(64))) longlong4 |
| +struct | __attribute__ ((aligned(16))) double2 |
| +__HIP_DEVICE__ char1 | make_char1 (signed char) |
| +__HIP_DEVICE__ char2 | make_char2 (signed char, signed char) |
| +__HIP_DEVICE__ char3 | make_char3 (signed char, signed char, signed char) |
| +__HIP_DEVICE__ char4 | make_char4 (signed char, signed char, signed char, signed char) |
| +__HIP_DEVICE__ short1 | make_short1 (short) |
| +__HIP_DEVICE__ short2 | make_short2 (short, short) |
| +__HIP_DEVICE__ short3 | make_short3 (short, short, short) |
| +__HIP_DEVICE__ short4 | make_short4 (short, short, short, short) |
| +__HIP_DEVICE__ int1 | make_int1 (int) |
| +__HIP_DEVICE__ int2 | make_int2 (int, int) |
| +__HIP_DEVICE__ int3 | make_int3 (int, int, int) |
| +__HIP_DEVICE__ int4 | make_int4 (int, int, int, int) |
| +__HIP_DEVICE__ long1 | make_long1 (long) |
| +__HIP_DEVICE__ long2 | make_long2 (long, long) |
| +__HIP_DEVICE__ long3 | make_long3 (long, long, long) |
| +__HIP_DEVICE__ long4 | make_long4 (long, long, long, long) |
| +__HIP_DEVICE__ longlong1 | make_longlong1 (long long) |
| +__HIP_DEVICE__ longlong2 | make_longlong2 (long long, long long) |
| +__HIP_DEVICE__ longlong3 | make_longlong3 (long long, long long, long long) |
| +__HIP_DEVICE__ longlong4 | make_longlong4 (long long, long long, long long, long long) |
| +__HIP_DEVICE__ uchar1 | make_uchar1 (unsigned char) |
| +__HIP_DEVICE__ uchar2 | make_uchar2 (unsigned char, unsigned char) |
| +__HIP_DEVICE__ uchar3 | make_uchar3 (unsigned char, unsigned char, unsigned char) |
| +__HIP_DEVICE__ uchar4 | make_uchar4 (unsigned char, unsigned char, unsigned char, unsigned char) |
| +__HIP_DEVICE__ ushort1 | make_ushort1 (unsigned short) |
| +__HIP_DEVICE__ ushort2 | make_ushort2 (unsigned short, unsigned short) |
| +__HIP_DEVICE__ ushort3 | make_ushort3 (unsigned short, unsigned short, unsigned short) |
| +__HIP_DEVICE__ ushort4 | make_ushort4 (unsigned short, unsigned short, unsigned short, unsigned short) |
| +__HIP_DEVICE__ uint1 | make_uint1 (unsigned int) |
| +__HIP_DEVICE__ uint2 | make_uint2 (unsigned int, unsigned int) |
| +__HIP_DEVICE__ uint3 | make_uint3 (unsigned int, unsigned int, unsigned int) |
| +__HIP_DEVICE__ uint4 | make_uint4 (unsigned int, unsigned int, unsigned int, unsigned int) |
| +__HIP_DEVICE__ ulong1 | make_ulong1 (unsigned long) |
| +__HIP_DEVICE__ ulong2 | make_ulong2 (unsigned long, unsigned long) |
| +__HIP_DEVICE__ ulong3 | make_ulong3 (unsigned long, unsigned long, unsigned long) |
| +__HIP_DEVICE__ ulong4 | make_ulong4 (unsigned long, unsigned long, unsigned long, unsigned long) |
| +__HIP_DEVICE__ ulonglong1 | make_ulonglong1 (unsigned long long) |
| +__HIP_DEVICE__ ulonglong2 | make_ulonglong2 (unsigned long long, unsigned long long) |
| +__HIP_DEVICE__ ulonglong3 | make_ulonglong3 (unsigned long long, unsigned long long, unsigned long long) |
| +__HIP_DEVICE__ ulonglong4 | make_ulonglong4 (unsigned long long, unsigned long long, unsigned long long, unsigned long long) |
| +__HIP_DEVICE__ float1 | make_float1 (float) |
| +__HIP_DEVICE__ float2 | make_float2 (float, float) |
| +__HIP_DEVICE__ float3 | make_float3 (float, float, float) |
| +__HIP_DEVICE__ float4 | make_float4 (float, float, float, float) |
| +__HIP_DEVICE__ double1 | make_double1 (double) |
| +__HIP_DEVICE__ double2 | make_double2 (double, double) |
| +__HIP_DEVICE__ double3 | make_double3 (double, double, double) |
| +__HIP_DEVICE__ double4 | make_double4 (double, double, double, double) |
| +__HIP_DEVICE__ double | __longlong_as_double (long long int x) |
| +__HIP_DEVICE__ long long int | __double_as_longlong (double x) |
Defines the different newt vector types for HIP runtime.
+| #define __hip_align | +( | ++ | name, | +
| + | + | + | val, | +
| + | + | + | data | +
| + | ) | ++ |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hcc__detail_2hip__vector__types_8h_source.html b/docs/RuntimeAPI/html/hcc__detail_2hip__vector__types_8h_source.html
new file mode 100644
index 0000000000..94a8896392
--- /dev/null
+++ b/docs/RuntimeAPI/html/hcc__detail_2hip__vector__types_8h_source.html
@@ -0,0 +1,547 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hierarchy.html b/docs/RuntimeAPI/html/hierarchy.html
new file mode 100644
index 0000000000..7a51e86a9f
--- /dev/null
+++ b/docs/RuntimeAPI/html/hierarchy.html
@@ -0,0 +1,150 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__common_8h_source.html b/docs/RuntimeAPI/html/hip__common_8h_source.html
new file mode 100644
index 0000000000..fbe04a41b0
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__common_8h_source.html
@@ -0,0 +1,186 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__complex_8h_source.html b/docs/RuntimeAPI/html/hip__complex_8h_source.html
new file mode 100644
index 0000000000..94525b02a3
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__complex_8h_source.html
@@ -0,0 +1,134 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__fp16_8h_source.html b/docs/RuntimeAPI/html/hip__fp16_8h_source.html
new file mode 100644
index 0000000000..219cf2d03c
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__fp16_8h_source.html
@@ -0,0 +1,133 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__hcc_8cpp.html b/docs/RuntimeAPI/html/hip__hcc_8cpp.html
new file mode 100644
index 0000000000..7a1c376dc0
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__hcc_8cpp.html
@@ -0,0 +1,486 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
#include <assert.h>#include <stdint.h>#include <iostream>#include <sstream>#include <list>#include <sys/types.h>#include <unistd.h>#include <deque>#include <vector>#include <algorithm>#include <atomic>#include <hc.hpp>#include <hc_am.hpp>#include "hsa/hsa_ext_amd.h"#include "libhsakmt/hsakmt.h"#include "hip/hip_runtime.h"#include "hip_hcc.h"#include "trace_helper.h"+Macros | |
| +#define | USE_COPY_EXT_V2 1 |
| +#define | HIP_USE_PRODUCT_NAME 1 |
| +#define | ErrorCheck(x) error_check(x, __LINE__, __FILE__) |
| +#define | DeviceErrorCheck(x) if (x != HSA_STATUS_SUCCESS) { return hipErrorInvalidDevice; } |
| #define | READ_ENV_I(_build, _ENV_VAR, _ENV_VAR2, _description) |
| #define | READ_ENV_S(_build, _ENV_VAR, _ENV_VAR2, _description) |
| #define | READ_ENV_C(_build, _ENV_VAR, _ENV_VAR2, _description, _callback) |
| +#define | CASE_STRING(X) case X: return #X ;break; |
+Functions | |
| +std::string | HIP_TRACE_API_COLOR ("green") |
| +std::atomic< int > | g_lastShortTid (1) |
| +void | recordApiTrace (std::string *fullStr, const std::string &apiStr) |
| +ihipDevice_t * | ihipGetDevice (int deviceIndex) |
| +ihipCtx_t * | ihipGetPrimaryCtx (unsigned deviceIndex) |
| +void | ihipSetTlsDefaultCtx (ihipCtx_t *ctx) |
| +ihipCtx_t * | ihipGetTlsDefaultCtx () |
| +hipError_t | ihipSynchronize (void) |
| +void | error_check (hsa_status_t hsa_error_code, int line_num, std::string str) |
| +hsa_status_t | FindGpuDevice (hsa_agent_t agent, void *data) |
| +hsa_status_t | GetDevicePool (hsa_amd_memory_pool_t pool, void *data) |
| +int | checkAccess (hsa_agent_t agent, hsa_amd_memory_pool_t pool) |
| +hsa_status_t | get_region_info (hsa_region_t region, void *data) |
| +void | ihipReadEnv_I (int *var_ptr, const char *var_name1, const char *var_name2, const char *description) |
| +void | ihipReadEnv_S (std::string *var_ptr, const char *var_name1, const char *var_name2, const char *description) |
| +void | ihipReadEnv_Callback (void *var_ptr, const char *var_name1, const char *var_name2, const char *description, std::string(*setterCallback)(void *var_ptr, const char *env)) |
| +void | parseTrigger (std::string triggerString, std::vector< ProfTrigger > &profTriggers) |
| +std::string | HIP_DB_string (unsigned db) |
| +std::string | HIP_DB_callback (void *var_ptr, const char *envVarString) |
| +std::string | HIP_VISIBLE_DEVICES_callback (void *var_ptr, const char *envVarString) |
| +void | ihipInit () |
| +hipStream_t | ihipSyncAndResolveStream (hipStream_t stream) |
| +void | ihipPrintKernelLaunch (const char *kernelName, const grid_launch_parm *lp, const hipStream_t stream) |
| +hipStream_t | ihipPreLaunchKernel (hipStream_t stream, dim3 grid, dim3 block, grid_launch_parm *lp, const char *kernelNameStr) |
| +hipStream_t | ihipPreLaunchKernel (hipStream_t stream, size_t grid, dim3 block, grid_launch_parm *lp, const char *kernelNameStr) |
| +hipStream_t | ihipPreLaunchKernel (hipStream_t stream, dim3 grid, size_t block, grid_launch_parm *lp, const char *kernelNameStr) |
| +hipStream_t | ihipPreLaunchKernel (hipStream_t stream, size_t grid, size_t block, grid_launch_parm *lp, const char *kernelNameStr) |
| +void | ihipPostLaunchKernel (const char *kernelName, hipStream_t stream, grid_launch_parm &lp) |
| +const char * | ihipErrorString (hipError_t hip_error) |
| +void | ihipSetTs (hipEvent_t e) |
| +const char * | hipMemcpyStr (unsigned memKind) |
| +const char * | hcMemcpyStr (hc::hcCommandKind memKind) |
| hipError_t | hipProfilerStart () |
| Start recording of profiling information When using this API, start the profiler with profiling disabled. (–startdisabled) More... | |
| hipError_t | hipProfilerStop () |
| Stop recording of profiling information. When using this API, start the profiler with profiling disabled. (–startdisabled) More... | |
| +hipError_t | hipHccGetAccelerator (int deviceId, hc::accelerator *acc) |
| +hipError_t | hipHccGetAcceleratorView (hipStream_t stream, hc::accelerator_view **av) |
+Variables | |
| +const int | release = 1 |
| +const char * | API_COLOR = KGRN |
| +const char * | API_COLOR_END = KNRM |
| +int | HIP_LAUNCH_BLOCKING = 0 |
| +std::string | HIP_LAUNCH_BLOCKING_KERNELS |
| +std::vector< std::string > | g_hipLaunchBlockingKernels |
| +int | HIP_API_BLOCKING = 0 |
| +int | HIP_PRINT_ENV = 0 |
| +int | HIP_TRACE_API = 0 |
| +int | HIP_PROFILE_API = 0 |
| +std::string | HIP_DB_START_API |
| +std::string | HIP_DB_STOP_API |
| +int | HIP_DB = 0 |
| +int | HIP_VISIBLE_DEVICES = 0 |
| +int | HIP_NUM_KERNELS_INFLIGHT = 128 |
| +int | HIP_WAIT_MODE = 0 |
| +int | HIP_FORCE_P2P_HOST = 0 |
| +int | HIP_DENY_PEER_ACCESS = 0 |
| +int | HIP_FORCE_SYNC_COPY = 0 |
| +int | HIP_COHERENT_HOST_ALLOC = 0 |
| +std::once_flag | hip_initialized |
| +ihipDevice_t ** | g_deviceArray |
| +bool | g_visible_device = false |
| +unsigned | g_deviceCnt |
| +std::vector< int > | g_hip_visible_devices |
| +hsa_agent_t | g_cpu_agent |
| +unsigned | g_numLogicalThreads |
| +std::vector< ProfTrigger > | g_dbStartTriggers |
| +std::vector< ProfTrigger > | g_dbStopTriggers |
| +thread_local hipError_t | tls_lastHipError = hipSuccess |
| +thread_local ShortTid | tls_shortTid |
Contains definitions for functions that are large enough that we don't want to inline them everywhere. This file is compiled and linked into apps running HIP / HCC path.
+| #define READ_ENV_C | +( | ++ | _build, | +
| + | + | + | _ENV_VAR, | +
| + | + | + | _ENV_VAR2, | +
| + | + | + | _description, | +
| + | + | + | _callback | +
| + | ) | ++ |
| #define READ_ENV_I | +( | ++ | _build, | +
| + | + | + | _ENV_VAR, | +
| + | + | + | _ENV_VAR2, | +
| + | + | + | _description | +
| + | ) | ++ |
| #define READ_ENV_S | +( | ++ | _build, | +
| + | + | + | _ENV_VAR, | +
| + | + | + | _ENV_VAR2, | +
| + | + | + | _description | +
| + | ) | ++ |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__hcc_8h_source.html b/docs/RuntimeAPI/html/hip__hcc_8h_source.html
new file mode 100644
index 0000000000..47908b7e34
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__hcc_8h_source.html
@@ -0,0 +1,922 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__ldg_8h_source.html b/docs/RuntimeAPI/html/hip__ldg_8h_source.html
new file mode 100644
index 0000000000..3fe22d965f
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__ldg_8h_source.html
@@ -0,0 +1,181 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__profile_8h_source.html b/docs/RuntimeAPI/html/hip__profile_8h_source.html
new file mode 100644
index 0000000000..e11e0a46f3
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__profile_8h_source.html
@@ -0,0 +1,138 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__runtime_8h_source.html b/docs/RuntimeAPI/html/hip__runtime_8h_source.html
new file mode 100644
index 0000000000..6989a57f94
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__runtime_8h_source.html
@@ -0,0 +1,155 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__runtime__api_8h_source.html b/docs/RuntimeAPI/html/hip__runtime__api_8h_source.html
new file mode 100644
index 0000000000..61781f127d
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__runtime__api_8h_source.html
@@ -0,0 +1,431 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__texture_8h_source.html b/docs/RuntimeAPI/html/hip__texture_8h_source.html
new file mode 100644
index 0000000000..6fdfd354c0
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__texture_8h_source.html
@@ -0,0 +1,138 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__util_8h_source.html b/docs/RuntimeAPI/html/hip__util_8h_source.html
new file mode 100644
index 0000000000..b3ecdd89b1
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__util_8h_source.html
@@ -0,0 +1,138 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/hip__vector__types_8h_source.html b/docs/RuntimeAPI/html/hip__vector__types_8h_source.html
new file mode 100644
index 0000000000..dcc0703001
--- /dev/null
+++ b/docs/RuntimeAPI/html/hip__vector__types_8h_source.html
@@ -0,0 +1,138 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/host__defines_8h.html b/docs/RuntimeAPI/html/host__defines_8h.html
new file mode 100644
index 0000000000..9b8eb086e1
--- /dev/null
+++ b/docs/RuntimeAPI/html/host__defines_8h.html
@@ -0,0 +1,147 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
TODO-doc. +More...
+ +Go to the source code of this file.
++Macros | |
| #define | __host__ __attribute__((cpu)) |
| +#define | __device__ __attribute__((hc)) |
| +#define | __global__ __attribute__((hc_grid_launch)) |
| +#define | __noinline__ __attribute__((noinline)) |
| +#define | __forceinline__ __attribute__((always_inline)) |
| +#define | __shared__ tile_static |
| +#define | __constant__ __attribute__((address_space(1))) |
TODO-doc.
+| #define __host__ __attribute__((cpu)) | +
Function and kernel markers
+ +
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/host__defines_8h_source.html b/docs/RuntimeAPI/html/host__defines_8h_source.html
new file mode 100644
index 0000000000..f8eac1b2a7
--- /dev/null
+++ b/docs/RuntimeAPI/html/host__defines_8h_source.html
@@ -0,0 +1,160 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/index.html b/docs/RuntimeAPI/html/index.html
new file mode 100644
index 0000000000..a5823c259c
--- /dev/null
+++ b/docs/RuntimeAPI/html/index.html
@@ -0,0 +1,99 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
The HIP interface makes it very easy to port existing CUDA apps to run on AMD GPUs, or to develop new apps that can run on either CUDA or AMD GPUs from a common source base.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/jquery.js b/docs/RuntimeAPI/html/jquery.js
new file mode 100644
index 0000000000..c197801c5d
--- /dev/null
+++ b/docs/RuntimeAPI/html/jquery.js
@@ -0,0 +1,31 @@
+/*!
+ * jQuery JavaScript Library v1.7.1
+ * http://jquery.com/
+ *
+ * Copyright 2011, John Resig
+ * Dual licensed under the MIT or GPL Version 2 licenses.
+ * http://jquery.org/license
+ *
+ * Includes Sizzle.js
+ * http://sizzlejs.com/
+ * Copyright 2011, The Dojo Foundation
+ * Released under the MIT, BSD, and GPL Licenses.
+ *
+ * Date: Mon Nov 21 21:11:03 2011 -0500
+ */
+(function(bb,L){var av=bb.document,bu=bb.navigator,bl=bb.location;var b=(function(){var bF=function(b0,b1){return new bF.fn.init(b0,b1,bD)},bU=bb.jQuery,bH=bb.$,bD,bY=/^(?:[^#<]*(<[\w\W]+>)[^>]*$|#([\w\-]*)$)/,bM=/\S/,bI=/^\s+/,bE=/\s+$/,bA=/^<(\w+)\s*\/?>(?:<\/\1>)?$/,bN=/^[\],:{}\s]*$/,bW=/\\(?:["\\\/bfnrt]|u[0-9a-fA-F]{4})/g,bP=/"[^"\\\n\r]*"|true|false|null|-?\d+(?:\.\d*)?(?:[eE][+\-]?\d+)?/g,bJ=/(?:^|:|,)(?:\s*\[)+/g,by=/(webkit)[ \/]([\w.]+)/,bR=/(opera)(?:.*version)?[ \/]([\w.]+)/,bQ=/(msie) ([\w.]+)/,bS=/(mozilla)(?:.*? rv:([\w.]+))?/,bB=/-([a-z]|[0-9])/ig,bZ=/^-ms-/,bT=function(b0,b1){return(b1+"").toUpperCase()},bX=bu.userAgent,bV,bC,e,bL=Object.prototype.toString,bG=Object.prototype.hasOwnProperty,bz=Array.prototype.push,bK=Array.prototype.slice,bO=String.prototype.trim,bv=Array.prototype.indexOf,bx={};bF.fn=bF.prototype={constructor:bF,init:function(b0,b4,b3){var b2,b5,b1,b6;if(!b0){return this}if(b0.nodeType){this.context=this[0]=b0;this.length=1;return this}if(b0==="body"&&!b4&&av.body){this.context=av;this[0]=av.body;this.selector=b0;this.length=1;return this}if(typeof b0==="string"){if(b0.charAt(0)==="<"&&b0.charAt(b0.length-1)===">"&&b0.length>=3){b2=[null,b0,null]}else{b2=bY.exec(b0)}if(b2&&(b2[1]||!b4)){if(b2[1]){b4=b4 instanceof bF?b4[0]:b4;b6=(b4?b4.ownerDocument||b4:av);b1=bA.exec(b0);if(b1){if(bF.isPlainObject(b4)){b0=[av.createElement(b1[1])];bF.fn.attr.call(b0,b4,true)}else{b0=[b6.createElement(b1[1])]}}else{b1=bF.buildFragment([b2[1]],[b6]);b0=(b1.cacheable?bF.clone(b1.fragment):b1.fragment).childNodes}return bF.merge(this,b0)}else{b5=av.getElementById(b2[2]);if(b5&&b5.parentNode){if(b5.id!==b2[2]){return b3.find(b0)}this.length=1;this[0]=b5}this.context=av;this.selector=b0;return this}}else{if(!b4||b4.jquery){return(b4||b3).find(b0)}else{return this.constructor(b4).find(b0)}}}else{if(bF.isFunction(b0)){return b3.ready(b0)}}if(b0.selector!==L){this.selector=b0.selector;this.context=b0.context}return bF.makeArray(b0,this)},selector:"",jquery:"1.7.1",length:0,size:function(){return this.length},toArray:function(){return bK.call(this,0)},get:function(b0){return b0==null?this.toArray():(b0<0?this[this.length+b0]:this[b0])},pushStack:function(b1,b3,b0){var b2=this.constructor();if(bF.isArray(b1)){bz.apply(b2,b1)}else{bF.merge(b2,b1)}b2.prevObject=this;b2.context=this.context;if(b3==="find"){b2.selector=this.selector+(this.selector?" ":"")+b0}else{if(b3){b2.selector=this.selector+"."+b3+"("+b0+")"}}return b2},each:function(b1,b0){return bF.each(this,b1,b0)},ready:function(b0){bF.bindReady();bC.add(b0);return this},eq:function(b0){b0=+b0;return b0===-1?this.slice(b0):this.slice(b0,b0+1)},first:function(){return this.eq(0)},last:function(){return this.eq(-1)},slice:function(){return this.pushStack(bK.apply(this,arguments),"slice",bK.call(arguments).join(","))},map:function(b0){return this.pushStack(bF.map(this,function(b2,b1){return b0.call(b2,b1,b2)}))},end:function(){return this.prevObject||this.constructor(null)},push:bz,sort:[].sort,splice:[].splice};bF.fn.init.prototype=bF.fn;bF.extend=bF.fn.extend=function(){var b9,b2,b0,b1,b6,b7,b5=arguments[0]||{},b4=1,b3=arguments.length,b8=false;if(typeof b5==="boolean"){b8=b5;b5=arguments[1]||{};b4=2}if(typeof b5!=="object"&&!bF.isFunction(b5)){b5={}}if(b3===b4){b5=this;--b4}for(;b4| t |
|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/nav_f.png b/docs/RuntimeAPI/html/nav_f.png
new file mode 100644
index 0000000000..72a58a529e
Binary files /dev/null and b/docs/RuntimeAPI/html/nav_f.png differ
diff --git a/docs/RuntimeAPI/html/nav_g.png b/docs/RuntimeAPI/html/nav_g.png
new file mode 100644
index 0000000000..2093a237a9
Binary files /dev/null and b/docs/RuntimeAPI/html/nav_g.png differ
diff --git a/docs/RuntimeAPI/html/nav_h.png b/docs/RuntimeAPI/html/nav_h.png
new file mode 100644
index 0000000000..33389b101d
Binary files /dev/null and b/docs/RuntimeAPI/html/nav_h.png differ
diff --git a/docs/RuntimeAPI/html/open.png b/docs/RuntimeAPI/html/open.png
new file mode 100644
index 0000000000..30f75c7efe
Binary files /dev/null and b/docs/RuntimeAPI/html/open.png differ
diff --git a/docs/RuntimeAPI/html/pages.html b/docs/RuntimeAPI/html/pages.html
new file mode 100644
index 0000000000..2236c6e7e0
--- /dev/null
+++ b/docs/RuntimeAPI/html/pages.html
@@ -0,0 +1,97 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/search/all_0.html b/docs/RuntimeAPI/html/search/all_0.html
new file mode 100644
index 0000000000..17b6da85df
--- /dev/null
+++ b/docs/RuntimeAPI/html/search/all_0.html
@@ -0,0 +1,26 @@
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for DbName, including all inherited members.
+| _color (defined in DbName) | DbName | |
| _shortName (defined in DbName) | DbName |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structDbName.html b/docs/RuntimeAPI/html/structDbName.html
new file mode 100644
index 0000000000..5d14f3369c
--- /dev/null
+++ b/docs/RuntimeAPI/html/structDbName.html
@@ -0,0 +1,114 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +const char * | _color |
| +const char * | _shortName |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structLockedBase-members.html b/docs/RuntimeAPI/html/structLockedBase-members.html
new file mode 100644
index 0000000000..6672fa92f6
--- /dev/null
+++ b/docs/RuntimeAPI/html/structLockedBase-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for LockedBase< MUTEX_TYPE >, including all inherited members.
+| _mutex (defined in LockedBase< MUTEX_TYPE >) | LockedBase< MUTEX_TYPE > | |
| lock() (defined in LockedBase< MUTEX_TYPE >) | LockedBase< MUTEX_TYPE > | inline |
| unlock() (defined in LockedBase< MUTEX_TYPE >) | LockedBase< MUTEX_TYPE > | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structLockedBase.html b/docs/RuntimeAPI/html/structLockedBase.html
new file mode 100644
index 0000000000..3dfbff92a4
--- /dev/null
+++ b/docs/RuntimeAPI/html/structLockedBase.html
@@ -0,0 +1,131 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+
+ +Public Member Functions | |
| +void | lock () |
| +void | unlock () |
+Public Attributes | |
| +MUTEX_TYPE | _mutex |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structLockedBase.png b/docs/RuntimeAPI/html/structLockedBase.png
new file mode 100644
index 0000000000..41977d7d58
Binary files /dev/null and b/docs/RuntimeAPI/html/structLockedBase.png differ
diff --git a/docs/RuntimeAPI/html/structProfTrigger-members.html b/docs/RuntimeAPI/html/structProfTrigger-members.html
new file mode 100644
index 0000000000..7467446c8d
--- /dev/null
+++ b/docs/RuntimeAPI/html/structProfTrigger-members.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ProfTrigger, including all inherited members.
+| add(uint64_t trigger) (defined in ProfTrigger) | ProfTrigger | inline |
| MAX_TRIGGER (defined in ProfTrigger) | ProfTrigger | static |
| nextTrigger() (defined in ProfTrigger) | ProfTrigger | inline |
| print(int tid) (defined in ProfTrigger) | ProfTrigger | inline |
| sort() (defined in ProfTrigger) | ProfTrigger | inline |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structProfTrigger.html b/docs/RuntimeAPI/html/structProfTrigger.html
new file mode 100644
index 0000000000..a62d6dfb48
--- /dev/null
+++ b/docs/RuntimeAPI/html/structProfTrigger.html
@@ -0,0 +1,127 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Member Functions | |
| +void | print (int tid) |
| +uint64_t | nextTrigger () |
| +void | add (uint64_t trigger) |
| +void | sort () |
+Static Public Attributes | |
| +static const uint64_t | MAX_TRIGGER = std::numeric_limits<uint64_t>::max() |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/struct____half-members.html b/docs/RuntimeAPI/html/struct____half-members.html
new file mode 100644
index 0000000000..5eb5166825
--- /dev/null
+++ b/docs/RuntimeAPI/html/struct____half-members.html
@@ -0,0 +1,102 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for __half, including all inherited members.
+| x (defined in __half) | __half |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/struct____half.html b/docs/RuntimeAPI/html/struct____half.html
new file mode 100644
index 0000000000..73172bbe87
--- /dev/null
+++ b/docs/RuntimeAPI/html/struct____half.html
@@ -0,0 +1,111 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned | x: 16 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structchar3-members.html b/docs/RuntimeAPI/html/structchar3-members.html
new file mode 100644
index 0000000000..84f58bd6c8
--- /dev/null
+++ b/docs/RuntimeAPI/html/structchar3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for char3, including all inherited members.
+| x (defined in char3) | char3 | |
| y (defined in char3) | char3 | |
| z (defined in char3) | char3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structchar3.html b/docs/RuntimeAPI/html/structchar3.html
new file mode 100644
index 0000000000..e6b4a355e6
--- /dev/null
+++ b/docs/RuntimeAPI/html/structchar3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +signed char | x |
| +signed char | y |
| +signed char | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structchar4-members.html b/docs/RuntimeAPI/html/structchar4-members.html
new file mode 100644
index 0000000000..37df9b2b9b
--- /dev/null
+++ b/docs/RuntimeAPI/html/structchar4-members.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for char4, including all inherited members.
+| val (defined in char4) | char4 | |
| w (defined in char4) | char4 | |
| x (defined in char4) | char4 | |
| y (defined in char4) | char4 | |
| z (defined in char4) | char4 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structchar4.html b/docs/RuntimeAPI/html/structchar4.html
new file mode 100644
index 0000000000..ea4aff9f7a
--- /dev/null
+++ b/docs/RuntimeAPI/html/structchar4.html
@@ -0,0 +1,127 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +union { | |
| + signed char x | |
| + signed char y | |
| + signed char z | |
| + signed char w | |
| + unsigned int val | |
| }; | |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structdim3-members.html b/docs/RuntimeAPI/html/structdim3-members.html
new file mode 100644
index 0000000000..231fa8d0f9
--- /dev/null
+++ b/docs/RuntimeAPI/html/structdim3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for dim3, including all inherited members.
+| x | dim3 | |
| y | dim3 | |
| z | dim3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structdim3.html b/docs/RuntimeAPI/html/structdim3.html
new file mode 100644
index 0000000000..a93484f438
--- /dev/null
+++ b/docs/RuntimeAPI/html/structdim3.html
@@ -0,0 +1,124 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
#include <hip_runtime_api.h>
+Public Attributes | |
| +uint32_t | x |
| x | |
| +uint32_t | y |
| y | |
| +uint32_t | z |
| z | |
Struct for data in 3D
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structdouble1-members.html b/docs/RuntimeAPI/html/structdouble1-members.html
new file mode 100644
index 0000000000..39e0794417
--- /dev/null
+++ b/docs/RuntimeAPI/html/structdouble1-members.html
@@ -0,0 +1,102 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for double1, including all inherited members.
+| x (defined in double1) | double1 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structdouble1.html b/docs/RuntimeAPI/html/structdouble1.html
new file mode 100644
index 0000000000..2c80f23d2d
--- /dev/null
+++ b/docs/RuntimeAPI/html/structdouble1.html
@@ -0,0 +1,111 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +double | x |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structdouble3-members.html b/docs/RuntimeAPI/html/structdouble3-members.html
new file mode 100644
index 0000000000..5dac28d9cf
--- /dev/null
+++ b/docs/RuntimeAPI/html/structdouble3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for double3, including all inherited members.
+| x (defined in double3) | double3 | |
| y (defined in double3) | double3 | |
| z (defined in double3) | double3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structdouble3.html b/docs/RuntimeAPI/html/structdouble3.html
new file mode 100644
index 0000000000..6ad945ab3b
--- /dev/null
+++ b/docs/RuntimeAPI/html/structdouble3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +double | x |
| +double | y |
| +double | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structfloat1-members.html b/docs/RuntimeAPI/html/structfloat1-members.html
new file mode 100644
index 0000000000..ac66596d17
--- /dev/null
+++ b/docs/RuntimeAPI/html/structfloat1-members.html
@@ -0,0 +1,102 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for float1, including all inherited members.
+| x (defined in float1) | float1 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structfloat1.html b/docs/RuntimeAPI/html/structfloat1.html
new file mode 100644
index 0000000000..33b66ec49f
--- /dev/null
+++ b/docs/RuntimeAPI/html/structfloat1.html
@@ -0,0 +1,111 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +float | x |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structfloat3-members.html b/docs/RuntimeAPI/html/structfloat3-members.html
new file mode 100644
index 0000000000..20edd625b0
--- /dev/null
+++ b/docs/RuntimeAPI/html/structfloat3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for float3, including all inherited members.
+| x (defined in float3) | float3 | |
| y (defined in float3) | float3 | |
| z (defined in float3) | float3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structfloat3.html b/docs/RuntimeAPI/html/structfloat3.html
new file mode 100644
index 0000000000..edcb5b0788
--- /dev/null
+++ b/docs/RuntimeAPI/html/structfloat3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +float | x |
| +float | y |
| +float | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipArray-members.html b/docs/RuntimeAPI/html/structhipArray-members.html
new file mode 100644
index 0000000000..395a5a1ada
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipArray-members.html
@@ -0,0 +1,105 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipArray, including all inherited members.
+| data (defined in hipArray) | hipArray | |
| f (defined in hipArray) | hipArray | |
| height (defined in hipArray) | hipArray | |
| width (defined in hipArray) | hipArray |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipArray.html b/docs/RuntimeAPI/html/structhipArray.html
new file mode 100644
index 0000000000..feba6e7a2d
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipArray.html
@@ -0,0 +1,120 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned int | width |
| +unsigned int | height |
| +hipChannelFormatKind | f |
| +void * | data |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipChannelFormatDesc-members.html b/docs/RuntimeAPI/html/structhipChannelFormatDesc-members.html
new file mode 100644
index 0000000000..276fe8b79b
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipChannelFormatDesc-members.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipChannelFormatDesc, including all inherited members.
+| f (defined in hipChannelFormatDesc) | hipChannelFormatDesc | |
| w (defined in hipChannelFormatDesc) | hipChannelFormatDesc | |
| x (defined in hipChannelFormatDesc) | hipChannelFormatDesc | |
| y (defined in hipChannelFormatDesc) | hipChannelFormatDesc | |
| z (defined in hipChannelFormatDesc) | hipChannelFormatDesc |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipChannelFormatDesc.html b/docs/RuntimeAPI/html/structhipChannelFormatDesc.html
new file mode 100644
index 0000000000..98bf065336
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipChannelFormatDesc.html
@@ -0,0 +1,123 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +int | x |
| +int | y |
| +int | z |
| +int | w |
| +hipChannelFormatKind | f |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipDeviceArch__t-members.html b/docs/RuntimeAPI/html/structhipDeviceArch__t-members.html
new file mode 100644
index 0000000000..0810a6ca90
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipDeviceArch__t-members.html
@@ -0,0 +1,118 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipDeviceArch_t, including all inherited members.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipDeviceArch__t.html b/docs/RuntimeAPI/html/structhipDeviceArch__t.html
new file mode 100644
index 0000000000..7c66d3cbc9
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipDeviceArch__t.html
@@ -0,0 +1,176 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned | hasGlobalInt32Atomics: 1 |
| 32-bit integer atomics for global memory. | |
| +unsigned | hasGlobalFloatAtomicExch: 1 |
| 32-bit float atomic exch for global memory. | |
| +unsigned | hasSharedInt32Atomics: 1 |
| 32-bit integer atomics for shared memory. | |
| +unsigned | hasSharedFloatAtomicExch: 1 |
| 32-bit float atomic exch for shared memory. | |
| +unsigned | hasFloatAtomicAdd: 1 |
| 32-bit float atomic add in global and shared memory. | |
| +unsigned | hasGlobalInt64Atomics: 1 |
| 64-bit integer atomics for global memory. | |
| +unsigned | hasSharedInt64Atomics: 1 |
| 64-bit integer atomics for shared memory. | |
| +unsigned | hasDoubles: 1 |
| Double-precision floating point. | |
| +unsigned | hasWarpVote: 1 |
| Warp vote instructions (__any, __all). | |
| +unsigned | hasWarpBallot: 1 |
| Warp ballot instructions (__ballot). | |
| +unsigned | hasWarpShuffle: 1 |
| Warp shuffle operations. (__shfl_*). | |
| +unsigned | hasFunnelShift: 1 |
| Funnel two words into one with shift&mask caps. | |
| +unsigned | hasThreadFenceSystem: 1 |
| __threadfence_system. | |
| +unsigned | hasSyncThreadsExt: 1 |
| __syncthreads_count, syncthreads_and, syncthreads_or. | |
| +unsigned | hasSurfaceFuncs: 1 |
| Surface functions. | |
| +unsigned | has3dGrid: 1 |
| Grid and group dims are 3D (rather than 2D). | |
| +unsigned | hasDynamicParallelism: 1 |
| Dynamic parallelism. | |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipDeviceProp__t-members.html b/docs/RuntimeAPI/html/structhipDeviceProp__t-members.html
new file mode 100644
index 0000000000..1bdc39fa96
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipDeviceProp__t-members.html
@@ -0,0 +1,127 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipDeviceProp_t, including all inherited members.
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipDeviceProp__t.html b/docs/RuntimeAPI/html/structhipDeviceProp__t.html
new file mode 100644
index 0000000000..c3ec16cdec
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipDeviceProp__t.html
@@ -0,0 +1,216 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
#include <hip_runtime_api.h>
+Public Attributes | |
| +char | name [256] |
| Device name. | |
| +size_t | totalGlobalMem |
| Size of global memory region (in bytes). | |
| +size_t | sharedMemPerBlock |
| Size of shared memory region (in bytes). | |
| +int | regsPerBlock |
| Registers per block. | |
| +int | warpSize |
| Warp size. | |
| +int | maxThreadsPerBlock |
| Max work items per work group or workgroup max size. | |
| +int | maxThreadsDim [3] |
| Max number of threads in each dimension (XYZ) of a block. | |
| +int | maxGridSize [3] |
| Max grid dimensions (XYZ). | |
| +int | clockRate |
| Max clock frequency of the multiProcessors in khz. | |
| +int | memoryClockRate |
| Max global memory clock frequency in khz. | |
| +int | memoryBusWidth |
| Global memory bus width in bits. | |
| +size_t | totalConstMem |
| Size of shared memory region (in bytes). | |
| +int | major |
| Major compute capability. On HCC, this is an approximation and features may differ from CUDA CC. See the arch feature flags for portable ways to query feature caps. | |
| +int | minor |
| Minor compute capability. On HCC, this is an approximation and features may differ from CUDA CC. See the arch feature flags for portable ways to query feature caps. | |
| +int | multiProcessorCount |
| Number of multi-processors (compute units). | |
| +int | l2CacheSize |
| L2 cache size. | |
| +int | maxThreadsPerMultiProcessor |
| Maximum resident threads per multi-processor. | |
| +int | computeMode |
| Compute mode. | |
| +int | clockInstructionRate |
| Frequency in khz of the timer used by the device-side "clock*" instructions. New for HIP. | |
| +hipDeviceArch_t | arch |
| Architectural feature flags. New for HIP. | |
| +int | concurrentKernels |
| Device can possibly execute multiple kernels concurrently. | |
| +int | pciBusID |
| PCI Bus ID. | |
| +int | pciDeviceID |
| PCI Device ID. | |
| +size_t | maxSharedMemoryPerMultiProcessor |
| Maximum Shared Memory Per Multiprocessor. | |
| +int | isMultiGpuBoard |
| 1 if device is on a multi-GPU board, 0 if not. | |
| +int | canMapHostMemory |
| Check whether HIP can map host memory. | |
hipDeviceProp
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipDoubleComplex-members.html b/docs/RuntimeAPI/html/structhipDoubleComplex-members.html
new file mode 100644
index 0000000000..8af91a6348
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipDoubleComplex-members.html
@@ -0,0 +1,103 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipDoubleComplex, including all inherited members.
+| x (defined in hipDoubleComplex) | hipDoubleComplex | |
| y (defined in hipDoubleComplex) | hipDoubleComplex |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipDoubleComplex.html b/docs/RuntimeAPI/html/structhipDoubleComplex.html
new file mode 100644
index 0000000000..96315b9ef2
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipDoubleComplex.html
@@ -0,0 +1,114 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +double | x |
| +double | y |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipFloatComplex-members.html b/docs/RuntimeAPI/html/structhipFloatComplex-members.html
new file mode 100644
index 0000000000..1cf90de8f3
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipFloatComplex-members.html
@@ -0,0 +1,103 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipFloatComplex, including all inherited members.
+| x (defined in hipFloatComplex) | hipFloatComplex | |
| y (defined in hipFloatComplex) | hipFloatComplex |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipFloatComplex.html b/docs/RuntimeAPI/html/structhipFloatComplex.html
new file mode 100644
index 0000000000..14bb04fc9f
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipFloatComplex.html
@@ -0,0 +1,114 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +float | x |
| +float | y |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipPointerAttribute__t-members.html b/docs/RuntimeAPI/html/structhipPointerAttribute__t-members.html
new file mode 100644
index 0000000000..b600b4fa3f
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipPointerAttribute__t-members.html
@@ -0,0 +1,107 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for hipPointerAttribute_t, including all inherited members.
+| allocationFlags (defined in hipPointerAttribute_t) | hipPointerAttribute_t | |
| device (defined in hipPointerAttribute_t) | hipPointerAttribute_t | |
| devicePointer (defined in hipPointerAttribute_t) | hipPointerAttribute_t | |
| hostPointer (defined in hipPointerAttribute_t) | hipPointerAttribute_t | |
| isManaged (defined in hipPointerAttribute_t) | hipPointerAttribute_t | |
| memoryType (defined in hipPointerAttribute_t) | hipPointerAttribute_t |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structhipPointerAttribute__t.html b/docs/RuntimeAPI/html/structhipPointerAttribute__t.html
new file mode 100644
index 0000000000..6c6fb0d5b9
--- /dev/null
+++ b/docs/RuntimeAPI/html/structhipPointerAttribute__t.html
@@ -0,0 +1,130 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
#include <hip_runtime_api.h>
+Public Attributes | |
| +enum hipMemoryType | memoryType |
| +int | device |
| +void * | devicePointer |
| +void * | hostPointer |
| +int | isManaged |
| +unsigned | allocationFlags |
Pointer attributes
+
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structihipEvent__t-members.html b/docs/RuntimeAPI/html/structihipEvent__t-members.html
new file mode 100644
index 0000000000..0ed940c02e
--- /dev/null
+++ b/docs/RuntimeAPI/html/structihipEvent__t-members.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ihipEvent_t, including all inherited members.
+| _flags (defined in ihipEvent_t) | ihipEvent_t | |
| _marker (defined in ihipEvent_t) | ihipEvent_t | |
| _state (defined in ihipEvent_t) | ihipEvent_t | |
| _stream (defined in ihipEvent_t) | ihipEvent_t | |
| _timestamp (defined in ihipEvent_t) | ihipEvent_t |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structihipEvent__t.html b/docs/RuntimeAPI/html/structihipEvent__t.html
new file mode 100644
index 0000000000..7092e3dc44
--- /dev/null
+++ b/docs/RuntimeAPI/html/structihipEvent__t.html
@@ -0,0 +1,123 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +hipEventStatus_t | _state |
| +hipStream_t | _stream |
| +unsigned | _flags |
| +hc::completion_future | _marker |
| +uint64_t | _timestamp |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structint3-members.html b/docs/RuntimeAPI/html/structint3-members.html
new file mode 100644
index 0000000000..fc82310b40
--- /dev/null
+++ b/docs/RuntimeAPI/html/structint3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for int3, including all inherited members.
+| x (defined in int3) | int3 | |
| y (defined in int3) | int3 | |
| z (defined in int3) | int3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structint3.html b/docs/RuntimeAPI/html/structint3.html
new file mode 100644
index 0000000000..57b6e81773
--- /dev/null
+++ b/docs/RuntimeAPI/html/structint3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +signed int | x |
| +signed int | y |
| +signed int | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structlong3-members.html b/docs/RuntimeAPI/html/structlong3-members.html
new file mode 100644
index 0000000000..001b1cf117
--- /dev/null
+++ b/docs/RuntimeAPI/html/structlong3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for long3, including all inherited members.
+| x (defined in long3) | long3 | |
| y (defined in long3) | long3 | |
| z (defined in long3) | long3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structlong3.html b/docs/RuntimeAPI/html/structlong3.html
new file mode 100644
index 0000000000..15f9630874
--- /dev/null
+++ b/docs/RuntimeAPI/html/structlong3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +long int | x |
| +long int | y |
| +long int | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structlonglong3-members.html b/docs/RuntimeAPI/html/structlonglong3-members.html
new file mode 100644
index 0000000000..d9b512c754
--- /dev/null
+++ b/docs/RuntimeAPI/html/structlonglong3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for longlong3, including all inherited members.
+| x (defined in longlong3) | longlong3 | |
| y (defined in longlong3) | longlong3 | |
| z (defined in longlong3) | longlong3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structlonglong3.html b/docs/RuntimeAPI/html/structlonglong3.html
new file mode 100644
index 0000000000..2167c4f811
--- /dev/null
+++ b/docs/RuntimeAPI/html/structlonglong3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +long long int | x |
| +long long int | y |
| +long long int | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structshort3-members.html b/docs/RuntimeAPI/html/structshort3-members.html
new file mode 100644
index 0000000000..e16bf8b5c3
--- /dev/null
+++ b/docs/RuntimeAPI/html/structshort3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for short3, including all inherited members.
+| x (defined in short3) | short3 | |
| y (defined in short3) | short3 | |
| z (defined in short3) | short3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structshort3.html b/docs/RuntimeAPI/html/structshort3.html
new file mode 100644
index 0000000000..f5075a1305
--- /dev/null
+++ b/docs/RuntimeAPI/html/structshort3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +signed short | x |
| +signed short | y |
| +signed short | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structstruct__float-members.html b/docs/RuntimeAPI/html/structstruct__float-members.html
new file mode 100644
index 0000000000..5a3aab1708
--- /dev/null
+++ b/docs/RuntimeAPI/html/structstruct__float-members.html
@@ -0,0 +1,103 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for struct_float, including all inherited members.
+| f (defined in struct_float) | struct_float | |
| u (defined in struct_float) | struct_float |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structstruct__float.html b/docs/RuntimeAPI/html/structstruct__float.html
new file mode 100644
index 0000000000..438a7868d7
--- /dev/null
+++ b/docs/RuntimeAPI/html/structstruct__float.html
@@ -0,0 +1,118 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +union { | |
| + float f | |
| + unsigned u | |
| }; | |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structtextureReference-members.html b/docs/RuntimeAPI/html/structtextureReference-members.html
new file mode 100644
index 0000000000..09b0950f1f
--- /dev/null
+++ b/docs/RuntimeAPI/html/structtextureReference-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for textureReference, including all inherited members.
+| channelDesc (defined in textureReference) | textureReference | |
| filterMode (defined in textureReference) | textureReference | |
| normalized (defined in textureReference) | textureReference |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structtextureReference.html b/docs/RuntimeAPI/html/structtextureReference.html
new file mode 100644
index 0000000000..23cdba0ce7
--- /dev/null
+++ b/docs/RuntimeAPI/html/structtextureReference.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +hipTextureFilterMode | filterMode |
| +bool | normalized |
| +hipChannelFormatDesc | channelDesc |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structuchar3-members.html b/docs/RuntimeAPI/html/structuchar3-members.html
new file mode 100644
index 0000000000..8a71a7aad5
--- /dev/null
+++ b/docs/RuntimeAPI/html/structuchar3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for uchar3, including all inherited members.
+| x (defined in uchar3) | uchar3 | |
| y (defined in uchar3) | uchar3 | |
| z (defined in uchar3) | uchar3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structuchar3.html b/docs/RuntimeAPI/html/structuchar3.html
new file mode 100644
index 0000000000..dce48635b2
--- /dev/null
+++ b/docs/RuntimeAPI/html/structuchar3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned char | x |
| +unsigned char | y |
| +unsigned char | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structuchar4-members.html b/docs/RuntimeAPI/html/structuchar4-members.html
new file mode 100644
index 0000000000..1dba273012
--- /dev/null
+++ b/docs/RuntimeAPI/html/structuchar4-members.html
@@ -0,0 +1,106 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for uchar4, including all inherited members.
+| val (defined in uchar4) | uchar4 | |
| w (defined in uchar4) | uchar4 | |
| x (defined in uchar4) | uchar4 | |
| y (defined in uchar4) | uchar4 | |
| z (defined in uchar4) | uchar4 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structuchar4.html b/docs/RuntimeAPI/html/structuchar4.html
new file mode 100644
index 0000000000..c4a79303d6
--- /dev/null
+++ b/docs/RuntimeAPI/html/structuchar4.html
@@ -0,0 +1,127 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +union { | |
| + unsigned char x | |
| + unsigned char y | |
| + unsigned char z | |
| + unsigned char w | |
| + unsigned int val | |
| }; | |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structuint3-members.html b/docs/RuntimeAPI/html/structuint3-members.html
new file mode 100644
index 0000000000..1d2bc9ffd4
--- /dev/null
+++ b/docs/RuntimeAPI/html/structuint3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for uint3, including all inherited members.
+| x (defined in uint3) | uint3 | |
| y (defined in uint3) | uint3 | |
| z (defined in uint3) | uint3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structuint3.html b/docs/RuntimeAPI/html/structuint3.html
new file mode 100644
index 0000000000..efbd9f5194
--- /dev/null
+++ b/docs/RuntimeAPI/html/structuint3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned int | x |
| +unsigned int | y |
| +unsigned int | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structulong3-members.html b/docs/RuntimeAPI/html/structulong3-members.html
new file mode 100644
index 0000000000..59ae827ac7
--- /dev/null
+++ b/docs/RuntimeAPI/html/structulong3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ulong3, including all inherited members.
+| x (defined in ulong3) | ulong3 | |
| y (defined in ulong3) | ulong3 | |
| z (defined in ulong3) | ulong3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structulong3.html b/docs/RuntimeAPI/html/structulong3.html
new file mode 100644
index 0000000000..490a0233a0
--- /dev/null
+++ b/docs/RuntimeAPI/html/structulong3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned long | x |
| +unsigned long | y |
| +unsigned long | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structulonglong3-members.html b/docs/RuntimeAPI/html/structulonglong3-members.html
new file mode 100644
index 0000000000..99328e4c6c
--- /dev/null
+++ b/docs/RuntimeAPI/html/structulonglong3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ulonglong3, including all inherited members.
+| x (defined in ulonglong3) | ulonglong3 | |
| y (defined in ulonglong3) | ulonglong3 | |
| z (defined in ulonglong3) | ulonglong3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structulonglong3.html b/docs/RuntimeAPI/html/structulonglong3.html
new file mode 100644
index 0000000000..5906b64824
--- /dev/null
+++ b/docs/RuntimeAPI/html/structulonglong3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned long long int | x |
| +unsigned long long int | y |
| +unsigned long long int | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structushort3-members.html b/docs/RuntimeAPI/html/structushort3-members.html
new file mode 100644
index 0000000000..05559529c4
--- /dev/null
+++ b/docs/RuntimeAPI/html/structushort3-members.html
@@ -0,0 +1,104 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
This is the complete list of members for ushort3, including all inherited members.
+| x (defined in ushort3) | ushort3 | |
| y (defined in ushort3) | ushort3 | |
| z (defined in ushort3) | ushort3 |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/structushort3.html b/docs/RuntimeAPI/html/structushort3.html
new file mode 100644
index 0000000000..2a24ed4382
--- /dev/null
+++ b/docs/RuntimeAPI/html/structushort3.html
@@ -0,0 +1,117 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+Public Attributes | |
| +unsigned short | x |
| +unsigned short | y |
| +unsigned short | z |
+ 1.8.6
+
+
+
diff --git a/docs/RuntimeAPI/html/sync_off.png b/docs/RuntimeAPI/html/sync_off.png
new file mode 100644
index 0000000000..3b443fc628
Binary files /dev/null and b/docs/RuntimeAPI/html/sync_off.png differ
diff --git a/docs/RuntimeAPI/html/sync_on.png b/docs/RuntimeAPI/html/sync_on.png
new file mode 100644
index 0000000000..e08320fb64
Binary files /dev/null and b/docs/RuntimeAPI/html/sync_on.png differ
diff --git a/docs/RuntimeAPI/html/tab_a.png b/docs/RuntimeAPI/html/tab_a.png
new file mode 100644
index 0000000000..3b725c41c5
Binary files /dev/null and b/docs/RuntimeAPI/html/tab_a.png differ
diff --git a/docs/RuntimeAPI/html/tab_b.png b/docs/RuntimeAPI/html/tab_b.png
new file mode 100644
index 0000000000..e2b4a8638c
Binary files /dev/null and b/docs/RuntimeAPI/html/tab_b.png differ
diff --git a/docs/RuntimeAPI/html/tab_h.png b/docs/RuntimeAPI/html/tab_h.png
new file mode 100644
index 0000000000..fd5cb70548
Binary files /dev/null and b/docs/RuntimeAPI/html/tab_h.png differ
diff --git a/docs/RuntimeAPI/html/tab_s.png b/docs/RuntimeAPI/html/tab_s.png
new file mode 100644
index 0000000000..ab478c95b6
Binary files /dev/null and b/docs/RuntimeAPI/html/tab_s.png differ
diff --git a/docs/RuntimeAPI/html/tabs.css b/docs/RuntimeAPI/html/tabs.css
new file mode 100644
index 0000000000..9cf578f23a
--- /dev/null
+++ b/docs/RuntimeAPI/html/tabs.css
@@ -0,0 +1,60 @@
+.tabs, .tabs2, .tabs3 {
+ background-image: url('tab_b.png');
+ width: 100%;
+ z-index: 101;
+ font-size: 13px;
+ font-family: 'Lucida Grande',Geneva,Helvetica,Arial,sans-serif;
+}
+
+.tabs2 {
+ font-size: 10px;
+}
+.tabs3 {
+ font-size: 9px;
+}
+
+.tablist {
+ margin: 0;
+ padding: 0;
+ display: table;
+}
+
+.tablist li {
+ float: left;
+ display: table-cell;
+ background-image: url('tab_b.png');
+ line-height: 36px;
+ list-style: none;
+}
+
+.tablist a {
+ display: block;
+ padding: 0 20px;
+ font-weight: bold;
+ background-image:url('tab_s.png');
+ background-repeat:no-repeat;
+ background-position:right;
+ color: #283A5D;
+ text-shadow: 0px 1px 1px rgba(255, 255, 255, 0.9);
+ text-decoration: none;
+ outline: none;
+}
+
+.tabs3 .tablist a {
+ padding: 0 10px;
+}
+
+.tablist a:hover {
+ background-image: url('tab_h.png');
+ background-repeat:repeat-x;
+ color: #fff;
+ text-shadow: 0px 1px 1px rgba(0, 0, 0, 1.0);
+ text-decoration: none;
+}
+
+.tablist li.current a {
+ background-image: url('tab_a.png');
+ background-repeat:repeat-x;
+ color: #fff;
+ text-shadow: 0px 1px 1px rgba(0, 0, 0, 1.0);
+}
diff --git a/docs/RuntimeAPI/html/trace__helper_8h_source.html b/docs/RuntimeAPI/html/trace__helper_8h_source.html
new file mode 100644
index 0000000000..dcd5ea1eb7
--- /dev/null
+++ b/docs/RuntimeAPI/html/trace__helper_8h_source.html
@@ -0,0 +1,238 @@
+
+
+
+
+
+
+|
+ HIP: Heterogenous-computing Interface for Portability
+
+ |
+
+ 1.8.6
+
+
+