7aae33951b
SWDEV-508966 - hipGetTextureAlignmentOffset return hipErrorInvalidTexture ( #389 )
2025-05-22 23:19:45 +05:30
51dd60a64f
SWDEV-508977 - return error in global capture mode for hipEventQuery ( #388 )
2025-05-22 23:17:57 +05:30
a0e946c2cc
Match hipStreamAddCallback capture behavior with nvidia ( #386 )
...
Co-authored-by: Anusha GodavarthySurya <Anusha.GodavarthySurya@amd.com >
2025-05-22 20:54:04 +05:30
63c4020e49
Match hipLaunchCooperativeKernelMultiDevice behavior with nvidia ( #385 )
...
Co-authored-by: Anusha GodavarthySurya <Anusha.GodavarthySurya@amd.com >
2025-05-22 20:52:37 +05:30
2ddfe40de0
Allow hipMemAdvise capturing only in relaxed mode ( #384 )
...
Co-authored-by: Anusha GodavarthySurya <Anusha.GodavarthySurya@amd.com >
2025-05-22 20:52:00 +05:30
69112331ac
Allow hipMallocManaged capturing only in relaxed mode ( #383 )
...
Co-authored-by: Anusha GodavarthySurya <Anusha.GodavarthySurya@amd.com >
2025-05-22 20:51:30 +05:30
9ef5602453
Match cuda behaviour for VMM APIs ( #382 )
2025-05-22 20:49:08 +05:30
ad44dd527f
[CLR ABI] step runtime api version hip memset node params ( #373 )
...
* increase hip api table version for HIP_MEMSET_NODE_PARAMS removed.
* update version in static_assert.
---------
Co-authored-by: Venkateshwar Reddy Kandula <vkandula@amd.com >
2025-05-22 15:09:31 +05:30
e5f7519e64
SWDEV-433031 - Match the signature of HIPRTC APIs with NVRTC ( #378 )
...
Change-Id: I5eb175b15a65a9f1c2db3ae30da6803179520dbe
2025-05-22 13:30:33 +05:30
2c173c6da4
SWDEV-512756 - SWDEV-510954 - Add appropriate checks during active stream capture ( #375 )
...
- hipStreamAddCallback is not permitted during stream capture for all modes
- hipModuleUnload is permitted only for relaxed mode during stream capture
Change-Id: I79ca5d2f6b61bd2e169fee7c13da4cd46e472a10
2025-05-22 13:24:49 +05:30
5cc172c99c
SWDEV-533074 - Expose hipDeviceAttributeNumberOfXccs attribute ( #336 )
2025-05-21 22:35:42 +05:30
664bf232dd
SWDEV-438790 - Remove DEBUG_HIP_7_PREVIEW env var keeping the hipGetLastError changes by default ( #337 )
2025-05-21 22:12:45 +05:30
88f15877f6
SWDEV-508964 - Match hip launch kernel retuns with cuda ( #357 )
2025-05-21 21:59:11 +05:30
e9dbd7c99d
SWDEV-418904 - Remove hiprtc symbols from hip library ( #370 )
2025-05-21 21:22:47 +05:30
0b64eec921
SWDEV-508962 - [6.4 Preview] Update hipPointerGetAttributes to match CUDA > 11.0 behavior ( #120 ) ( #363 )
2025-05-21 21:18:05 +05:30
968f5599a8
SWDEV-508965 - [6.4 Preview] Remove HIP_MEMSET_NODE_PARAMS struct ( #121 ) ( #364 )
2025-05-21 21:16:42 +05:30
58df22546b
SWDEV-532868 - Disable implicit wait in hipFree for async allocations ( #323 )
...
* SWDEV-532868 - Disable implicit wait in hipFree for async allocations
* Fix compilation error
2025-05-21 21:14:38 +05:30
7a357800dd
SWDEV-508979 - Match hipModuleLoad negative return with Cuda ( #326 )
2025-05-21 21:09:07 +05:30
a46ed60e2e
SWDEV-508970 - Match hipBindTextureToArray negative return with Cuda ( #325 )
2025-05-21 20:57:09 +05:30
12131de4a9
SWDEV-529929 - hipMemGetHandleForAddressRange implementation. ( #245 )
2025-05-20 15:56:04 -04:00
f5b8db33f1
SWDEV-531711 - Report correct error code based on device failure. ( #286 )
2025-05-17 06:33:13 -04:00
32eb6a5d89
SWDEV-530803 - User current device id while cloning graph node. ( #313 )
2025-05-15 09:06:15 +05:30
0457b634f8
SWDEV-527781 - Remove Stream Validation in HIP APIs
2025-05-13 13:45:27 -07:00
f7482ef0a6
SWDEV-529449 - Bug fix when retrieving a memobj from the IPC mem handle
2025-05-13 19:18:22 +01:00
acb1f7e8d5
SWDEV-526855 - Modify the SIMDPerCU calculation for gfx1250/1. ( #275 )
2025-05-12 11:09:03 -04:00
c5ced8c3a2
SWDEV-512344 - Unmap all subbuffers ( #214 )
2025-05-12 16:56:10 +02:00
a7492c516d
SWDEV-511204 - Mapped virtual memory should use device instead of host context ( #213 )
...
Since the sub-buffer(virtual memory that is mapped to device memory) is associated with device memory, it should utilize the device context instead of the host context. The original implementation caused hipMemcpyPeer to not take the P2P path, as the memory object was treated as host memory.
2025-05-12 16:55:25 +02:00
b434fbe2bd
SWDEV-527299 - Support HIP_POINTER_ATTRIBUTE_CONTEXT ( #180 )
...
* SWDEV-527299 - Support HIP_POINTER_ATTRIBUTE_CONTEXT
As HIP enables UVA by default, it seems we can simply expose the context to support this feature.
2025-05-09 17:34:16 +08:00
fa55557f46
SWDEV-493805 - Cleaning up launch parameters arguments. ( #241 )
2025-05-06 15:06:13 -04:00
607f8f26fd
SWDEV-529831 - Return error if the program is empty ( #257 )
2025-05-06 15:12:12 +05:30
2538d7f02b
SWDEV-522841 - Graph nodes must be created/launched on device where they are captured/created ( #108 )
2025-04-29 22:20:39 +05:30
eb62fe9f62
SWDEV-522634 - Fix device properties in hipInfo ( #203 )
2025-04-29 11:29:47 -04:00
96cadbc9e9
SWDEV-520352 - Remove HostThread and legacy monitor ( #230 )
...
* SWDEV-520352 - Remove HostThread and legacy monitor
Remove HostThread, semaphore and legacy monitor.
Make original logics of thread and command queue stricker.
Add more comments to make logics clearer.
Some other minor improvement.
Also part of SWDEV-458943.
2025-04-29 09:55:24 -04:00
b2388dfb88
SWDEV-506467 - Skip Abort in case of crash from the device. ( #60 )
...
Change-Id: I964b2f2647d068202e9c38fcddb1337da754df8d
2025-04-29 11:19:02 +05:30
9cf3f1e461
SWDEV-528351 - Removes unused code and asserts to improve coverage ( #219 )
2025-04-28 14:40:35 -07:00
fb92683d86
SWDEV-469422 - Avoid using of hipStream_t in internal methods ( #69 )
...
Change-Id: Ifd5362f371c846a88241927383cb95cf046548ef
2025-04-28 15:09:11 +05:30
bbcb1f9c70
SWDEV-469422 - hipGraphNodeDOTAttribute change std::string members to const char* ( #70 )
...
Compiler creates global variables for every unique string
Change-Id: I4cf8dd3e763d16740096e345da67a7ef72f61515
2025-04-28 14:57:36 +05:30
1099e0a131
SWDEV-526188 - Fix race condition in StatCO::getStatFunc()
...
Make sure that a newly created FatBinaryInfo is assigned to modules only after extractFatBinary has been called for the object.
2025-04-27 21:14:01 +01:00
1113eff3f9
SWDEV-493275 - Support scratch limit ( #20 )
...
Support programmatic query and change of scratch limit on
AMD devices.
Change-Id: Id5da355a77366f97868e462847f3916e87fd2af6
2025-04-24 17:15:25 -04:00
e5ce544c45
SWDEV-469423 - hipStreamEndCapture graph* can be nullptr ( #170 )
2025-04-24 13:57:09 +05:30
27aad09bd4
SWDEV-518831 - fix streams' sync issue in mthreads ( #123 )
...
* SWDEV-518831 - fix streams' sync issue in mthreads
1. Fix sync issue of null stream and non-null streams in
multithreads.
2. Remove assert(GetSubmissionBatch() == nullptr) as it
is invalid in multithreads.
3. Update getActiveQueues() to deal with the state of
being terminated.
2025-04-23 15:08:07 -04:00
64d6f5714a
SWDEV-523281 - CHANGELOG.md and negative test return values : hipLaunchKernelEx, hipLaunchKernelExC, hipDrvLaunchKernelEx ( #155 )
2025-04-22 21:47:37 +05:30
bf28bbd9ab
SWDEV-508538 - Optimize mem access and pack structure ( #71 )
...
Change-Id: Ib05b8891a6d228fc3266918a000d332fddc7438b
2025-04-21 13:43:25 +05:30
d00b2a0953
SWDEV-525423 - In COMGR Loader don't open file if image is already mapped ( #193 )
2025-04-16 11:00:54 +02:00
5fe080fd67
SWDEV-523137 - function ptrs should match across all devices ( #171 )
2025-04-16 10:35:48 +02:00
e92ea151b2
SWDEV-518317 - Remove Redundant Error Message in removeFatBinary ( #164 )
2025-04-15 09:00:39 -07:00
fcaefe97b8
SWDEV-509213 - make cmake_minimum_required consistent across clr ( #51 )
...
Change-Id: Ib0b1df7af8984a37d6bf7ca68ec99597d5978821
2025-04-15 15:23:41 +05:30
07e57a1f0d
SWDEV-517941 - use device bitcode before spirv ( #95 )
...
Also add flag: HIP_FORCE_SPIRV_CODEOBJECT to allow override to force use
SPIRV.
* use cache for already compiled code objects
* address review comments and use the two spirv isa names
2025-04-14 23:40:52 +01:00
66496258b4
SWDEV-521920 - Fix compilation issues introduced by the reduce sync operations - 2 ( #167 )
...
Fix pytorch 2.5 issues, by defining reduce sync operations for type __half in amd_hip_fp16.h and not in
amd_warp_sync_functions.h which is problematic in case __half does not get included before that header.
Only define types not supported by cuda if HIP_ENABLE_EXTRA_WARP_SYNC_TYPES is defined, to avoid portability issues
2025-04-11 17:00:59 +05:30
199b0f1086
Report null stream creation failure ( #152 )
...
Explicitly nulling the pointer causes us to report the error below
instead of keeping a dangling pointer around that will most likely lead
to a subsequent segfault.
2025-04-10 11:40:05 -07:00
Belton-Schure, Aidan
Stojiljkovic, Vladana
Arandjelovic, Marko
Kandula, Venkateshwar reddy
Dittakavi, Satyanvesh
Andryeyev, German
Brzak, Branislav
Assiouras, Ioannis
Jayaprakash, Karthik
Patel, Jaydeepkumar
Xie, Pengda
Huang, AnZhong
Godavarthy Surya, Anusha
Jiang, Julia
Sang, Tao
Betigeri, Sourabh
GunaShekar, Ajay
Chaudhary, Jatin Jaikishan
Hernandez, Gerardo
Haehnle, Nicolai