30cb2d0e67
SWDEV-498061 - Add capture support for hipModuleLaunchCooperativeKernel
...
Change-Id: I5ed188e046c680c2785b3952391f59ed1d0c21b8
2025-01-16 10:54:30 -05:00
db8527f655
SWDEV-489619 - Fix memcpy tests with capture stream enabled
...
- Added missing validation as graph node should not be created
if parameters are invalid
- Fix conversion of input params to graphNode params
Change-Id: I37ab04942b5fb2eb07386850cb7dbbf26f9ca967
2025-01-16 10:31:04 -05:00
c46f843b99
SWDEV-504084 - Make hipModuleGetFunction use the device the module is loaded on
...
If a module is loaded on one device, hipModuleGetFunction and other similar APIs should be able to run successfully from another device.
Change-Id: I96084cbd6c6dcf2a81019779a6ab1842ef2f35d1
2025-01-16 10:16:42 -05:00
5e3a29078d
SWDEV-505503 - Use internal device synchronize function in __hipUnregisterFatBinary
...
This is to avoid calling the HIP_INIT macro during the shutdown process.
Change-Id: I2e65f6e10491918a17445ee1e8ddd08286070358
2025-01-15 18:57:34 -05:00
9d8d35ae40
SWDEV-507960 - Return with error code if stream of type hipStreamLegacy is being attempted to destroy
...
Change-Id: Iee7ada6a5a905b44360a7e4049fc8b1a45c80db0
2025-01-13 18:17:37 -05:00
44b6b6813d
SWDEV-503760 - Only consider allocations that are less than X% larger in a mempool request
...
Change-Id: I94acbca606fd4c575e2e1a9e34959ce650571867
2025-01-13 16:57:26 -05:00
2b32d9aada
SWDEV-497288 - Add validation checks to hipGraphExecNodeSetParams
...
Change-Id: If8cde47bc8e62414333768e01064298d8a3d80ee
2025-01-13 16:49:45 -05:00
93cff75928
SWDEV-492165 - Add support for 16 bit atomicAdd and atomicCAS
...
Change-Id: I7f1e4876fe2960dff1775d27cb6443a89e146c86
2025-01-13 13:35:40 -05:00
805462a77b
SWDEV-477039 - Fix spelling typos
...
Change-Id: Ia46e07ec0a001b7e19bec999597028acd4ee7077
2025-01-13 12:17:46 -05:00
683a942364
SWDEV-480209 - Make internal callbacks non-blocking
...
Change-Id: Ic918d08f341abfd9a7c167d09f9c723cdc43157f
2025-01-10 02:16:11 -05:00
a22c45d635
SWDEV-508004 - Improve hipEventRecord
...
- Resolve stream once for event record. We should avoid calling
getStream again in addMarker
Change-Id: I78448c4f151ae10a5c8e8c248b2f4078b84191cb
2025-01-09 16:47:46 -05:00
45a12208b6
SWDEV-507019 - Change the function lock to the module lock
...
Multiple functions can be located in the same module.
Change-Id: Ia4ca3db64fe5b0822584059d3770c91103665c63
2025-01-09 12:35:29 -05:00
05baf9ff22
SWDEV-504215 - fix rocalution perf drop by disabling cpu wait
...
Change-Id: I878f3420073b05cc6241f524ac428e47c0ce823d
2025-01-07 17:02:24 -05:00
7e152bb0f3
SWDEV-506234 - Refactor validation in hip_memory
...
Change-Id: I9d69695e4b6668e6de00f1f6b060862872358340
2024-12-31 00:35:25 +02:00
b8ba4ccf9c
SWDEV-495789 - revert Fix ambiguity of fma for _Float16 for libc++ ( #1976 )
...
Change-Id: I45ae4711a047f4484a018b9409c9f6ecf09720ce
2024-12-29 10:56:32 -05:00
dff8197b1d
SWDEV-505276 - Parent graph of orig node and original graph of cloned node should be same.
...
Change-Id: I6ebc21cc42e41ad5d952a69fb3b3cb095f32cffb
2024-12-24 04:32:14 -05:00
d82d6a78cf
SWDEV-479958 - Support different address mode
...
Support different address modes in X, Y, Z directions
Change-Id: If1db5a8af33c92dd14b48968c3e8eceb97daea6c
2024-12-23 16:39:54 -05:00
158b6a29e0
SWDEV-505504 - Disable vectorization in GetHipDispatchTable
...
Change-Id: Id33144623555a5d25e029ca644f6274610dcd0ad
2024-12-20 17:47:07 -05:00
a05a02e527
SWDEV-505205 - Fix hipStreamLegacy segfault with hipStreamWaitEvent.
...
Change-Id: I17fdaf7ac323507f99a7c071066944296537489c
2024-12-20 04:18:21 -05:00
0640d36019
SWDEV-504658 - Reduce the lock scope for kernel look-up
...
The vector with all kernels is preallocated on the executable init.
Thus, reduce the scope of global lock to the binary creation only.
Change-Id: I73035013a6562175069137e895bba815f466ee35
2024-12-18 17:04:51 -05:00
cd9db5a2fa
SWDEV-505277 - Adds hipStreamBatchMemOp in the enum of hcc_map
...
Change-Id: I6e58dfbe4ba13db8717edc36020fefabc9ddbe23
2024-12-18 05:38:58 -05:00
e3efce20be
SWDEV-504650 - Switch to shared_mutex for events
...
Use shared mutex for events validation
Change-Id: Iff291c758d9edd65717c506150f3b9d39e5306ba
2024-12-17 11:04:58 -05:00
fccf0fa2f0
SWDEV-377518 - Fix bf16/fp8 header to be compileable with hiprtc
...
Change-Id: I2093a39d79a46da7e102266c04c2a71e03dcb88e
2024-12-17 08:57:15 -05:00
e8b2fdab96
SWDEV-483134 - Remove hipExtHostAlloc API
...
Change-Id: I60777ef5c56b60dd8100d0d794ca10fb3b96a555
2024-12-16 17:13:49 -05:00
13e2e797c0
SWDEV-469422 - Derive GraphExec from Graph and ChildGraphNode from GraphExec
...
Change-Id: I54d67a1665355579bc249d8ff4f9806e9ee14588
2024-12-16 00:43:57 -05:00
3c863dad91
SWDEV-502543 - Update doxygen to surface funtions and Coop Group API
...
Change-Id: Id4df63b8ae64a1113f85d89aa250ac9f7cc8b9bb
2024-12-14 14:11:37 -05:00
f1c05e9026
SWDEV-421020 - Adds hipGraphAddBatchMemOp, SetGetParams and execSetParams APIs
...
Change-Id: Ieccecfe6173cc68fd3c01f86c99f7cc09fe194a3
2024-12-13 06:23:39 +00:00
03dbcd8ca7
SWDEV-440866 - [hip-roclr] Adds support to batch memory operations APIs
...
Change-Id: I5ac63a6626af8c2b4ac382c52dfe1aaf0b3716b8
2024-12-12 19:29:24 -05:00
3ad8f1b811
SWDEV-496667 - Support gfx9-4-generic target
...
Support gfx9-4-generic target to cover mi3XX.
Support features sramecc and xnack in generic target.
Improve some code formats.
Add more log on compiler.
Change-Id: I6b3c6af55c60cffd43ce6f17b75998f751b75713
2024-12-12 14:43:39 -05:00
537f2fffc9
SWDEV-301667 - Improve logging for hip_memory
...
Change-Id: Id624b2c91e6b701bc0ee561a0c193f2c66654890
2024-12-12 14:42:00 -05:00
28cbf2bc4f
SWDEV-469422 - Refacor childgraph node
...
Remove static functions in graph
Change-Id: I4df94915f81f250acaea60398aea32ef0ed658e2
2024-12-12 12:38:24 -05:00
c8afd7109d
SWDEV-496544 - Sync with stream if it is different than srcMemory stream.
...
Change-Id: I9c0f94a9531555278a51202ec7203961e1344c2e
2024-12-12 06:17:39 -05:00
072f94c204
Revert "SWDEV-491314 - enable _sync() functions with 64-bit mask argument"
...
This reverts commit 4e2fd192eb
2024-12-11 11:16:48 -05:00
98b33886cd
SWDEV-503299 - Do not use operator to check for nan
...
Some libs use __HIP_NO_HALF_OPERATORS__ and __HIP_NO_HALF_CONVERSIONS__
which results in operators being hidden and can cause errors.
Change-Id: I83c194d7d727cba30b46d7c296f7d396549f5fca
2024-12-11 00:33:44 -05:00
def369a010
SWDEV-489099 - Deprecate AMDGPU_TARGETS in lieu of supporting GPU_TARGETS
...
Change-Id: I184cd18e47b1618bcad0fadc8984de54d2a00a9b
2024-12-10 12:38:37 -05:00
89dfdc4dbe
SWDEV-490860 - Do signal_is_required detection post graph schedule
...
Change-Id: Iaf1067a811aeac3d16c08de954036e219b545e07
2024-12-09 03:57:44 -05:00
0d4823ff88
SWDEV-502532 - Exit graph launch in case of empty graph.
...
Change-Id: Ifb6ab14ca6810cbc1c9e38c59d1d9e7d367358d9
2024-12-07 12:27:53 -05:00
e80442fdbf
SWDEV-497759 - Fix memObj offset computation for hipHostRegister on Windows mgpu
...
On Windows, hipHostRegister may add a single object in the MemObjMap
that maps to memory that is allocated on different devices.
This change ensures that the offset that is returned from
getMemoryObject() is computed relative to the memory that is allocated
on the current device.
Change-Id: I5fd3af200bf6f4926fdeaea12dcb9d0154d3a843
2024-12-05 16:18:10 -05:00
78f62d3230
SWDEV-495609 - Change include path for rocclr/utils
...
- Header files inside rocclr/utils when included from hipamd or opencl should be included as #include "rocclr/utils/xxx.h" instead of "utils/xxx.h"
Change-Id: Ic0760c33b9d091f5620dec67e5482c9698d22093
2024-12-05 11:44:20 -05:00
5122b8c999
SWDEV-501779 - add correct function qualifier for fp16 functions
...
Some functions were __device__ only, but should be __host__ and
__device__, changed them to __HOST_DEVICE__.
Some functions were __HOST_DEVICE__ but were using ockl functions,
changed them to __device__ only.
Change-Id: Ife9e7abe60415bda68f5f9a101e6e7c39ad51064
2024-12-05 10:17:18 -05:00
f2dba978f5
SWDEV-490860 - Include signal_is_required in dot file dumps
...
Change-Id: Iec4b433b11fbecb71a4ce68beb7d6f681d25b8e6
2024-12-05 04:51:59 -05:00
231b2410a0
SWDEV-492049 - Remove the handle of Phy Mem from Memobj
...
The hipGraph will use VMM by default when allocating memory.
However, the handle of Phy mem has been added to Memobj by default.
Since the Memobj will track the whole address range from handle to
handle + size, this needs the system to reserve the whole address
range. If the system range have not reserved by the system, then it
will have the potential issue that clr finds the Memobj incorrectly.
This patch removes the handle from the Memobj to fix this potential
issue.
Change-Id: I2da38e6b2d11d0d48e1afe66c46899500c290624
2024-12-04 19:39:52 -05:00
efd3ea4b30
SWDEV-501403 - Switch to std::shared_mutex for streamSetLock
...
Shared mutex allows to have access to the list of streams from
multiple threads at the same time.
Change-Id: Ibee64b846cde03321d5b17dbee2829c0bab7e7d6
2024-12-04 12:06:51 -05:00
b89977d518
SWDEV-469422 - Always schedule graph nodes
...
Change-Id: Icc636527fa19e7bf3eb111bc4b1bb9a5f9acff73
2024-12-03 23:44:23 -05:00
6611cc015d
SWDEV-494149 - Improve hipGet/Set Device
...
Change-Id: If8975687a3ba9caadafc48a0066f19a4ebaab9e2
2024-12-03 13:36:38 -05:00
2ca644cf22
Revert "SWDEV-440866 - [hip-roclr] Adds support to batch memory operations APIs"
...
This reverts commit bd5d8e9baf
2024-12-02 16:46:12 -05:00
08aee16573
SWDEV-499794 - Update AQL packet after updating GraphNode
...
Change-Id: I332d70bdf42a276894a548a02d636e370c2ca08c
2024-12-02 12:29:35 -05:00
4e2fd192eb
SWDEV-491314 - enable _sync() functions with 64-bit mask argument
...
Change-Id: Ieb13a9e1b2fc49ff225a05a51056d1212d95ae57
2024-12-01 10:16:59 -05:00
bd5d8e9baf
SWDEV-440866 - [hip-roclr] Adds support to batch memory operations APIs
...
Change-Id: I449ffca44bbb04d13348d112e896d603c70fd485
2024-11-30 17:54:32 -05:00
c47f9dda58
SWDEV-469422 - Cleanup graph code remove parallellists and nodewaitlists
...
Change-Id: I00c7b2894333bd13d47b913d3fcdd6e1ffcb741f
2024-11-30 04:40:51 -05:00
Vladana Stojiljkovic
Marko Arandjelovic
Marko Arandjelovic
Ioannis Assiouras
Sourabh Betigeri
Rahul Manocha
Jacob Lambert
Anusha GodavarthySurya
Saleel Kudchadker
German Andryeyev
zichguan-amd
Jaydeep Patel
taosang2
Jatin Chaudhary
Istvan Kiss
Maneesh Gupta
Todd tiantuo Li
Branislav Brzak
Shane Xiao
Sameer Sahasrabuddhe