917dc7ee82
SWDEV-401852 - Do not define hipCreateChannelDesc for long types in LP64
...
Change-Id: I56881a229ea666269d575c6bdfde5081562ec009
[ROCm/clr commit: 4f5dfa77bd
2023-06-06 14:28:15 -04:00
7be6ca6306
SWDEV-404118 - Change to uint.
...
Change-Id: Ib9ced171a4330e868a584bfb86d7ee5418e784ed
[ROCm/clr commit: 9daf8e3177
2023-06-06 13:17:56 -04:00
06213e3b4b
SWDEV-400515 - populate __HIP_NO_IMAGE_SUPPORT flag
...
MI300 does not support image APIs.
Apps to use __HIP_NO_IMAGE_SUPPORT instead of arch
Change-Id: I91178bfd27ea7b7188e7a958a876c0264f4469aa
[ROCm/clr commit: 16c6b365c2
2023-06-06 12:11:41 -04:00
d7b529ff6e
SWDEV-395996 - Add double precision constants to math constants header
...
Fixes a typo and adds missing constants matching cuda
Change-Id: Iebf47d107af361cbd356c2a3b9cd6ef121d01363
[ROCm/clr commit: 287f607d2b
2023-06-05 03:31:27 -04:00
6ab03957bb
SWDEV-401847 - Update atomicMin/Max for float and double.
...
Change-Id: Ib5be459b8a24f0739e299ed12c9f877f8baa02b1
[ROCm/clr commit: d576356505
2023-05-29 14:27:16 -04:00
094b2bfa9e
SWDEV-401850 - Fix hipCreateChannelDescHalf APIs
...
- Address ChannelDescHalf1 and ChannelDescHalf2 APIs not returning
correct Channel Descriptors in amd headers
- Add missing hipCreateChannelDescHalf APIs in nvidia headers
Change-Id: I558847425c2459d3cde329ca2e926d882bb0a9dd
[ROCm/clr commit: 586731c2cc
2023-05-25 04:36:24 -04:00
62302ac4fa
SWDEV-393910 - Adding CAS expanders under gfx941 tag.
...
Change-Id: I2c4bcf56be419d1f037b8555ad254a2dc49d0c5b
[ROCm/clr commit: feb22250f3
2023-05-22 09:59:05 -04:00
915677e9a0
SWDEV-396533 - correct _shfl function to match cuda
...
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: I311419fd25c055339f25fe0c7a132ec9ee225600
[ROCm/clr commit: 23e99dbb07
2023-05-17 14:19:46 -04:00
8d0b25334b
SWDEV-395773 - Fix unordered compare functions in fp16 header
...
Change-Id: I9158420e37cd3151159182223c6645ed84c4fddd
[ROCm/clr commit: 15bafc9a93
2023-05-11 10:42:13 -04:00
69d6e8873d
SWDEV-367537 - Add __hip_bfloat16 and vector definitions to match __nv_bfloat16
...
Change-Id: I1c0f9f5f278c2c3b4e175d9f08831ba458ed856e
[ROCm/clr commit: 6c793ea206
2023-05-11 04:45:13 -04:00
130f9c5117
SWDEV-399203 - Use clang pragma only with clang
...
Change-Id: I21d84ccde07e243b6bc06f1980c24b399e74d1c3
[ROCm/clr commit: a7041d15a7
2023-05-10 04:19:51 -04:00
23584feba4
SWDEV-393910 - Port gfx94x changes to mainline.
...
Change-Id: Ibf727223bbe5230b132b47c39e0fc1d87cbd3b9c
[ROCm/clr commit: f14e8a2dba
2023-05-05 15:16:23 -04:00
2e9767d073
SWDEV-394488 - cudaStreamGetCaptureInfo_v2 is undefined in CUDA 12.0
...
hipStreamPerThrdCompilerOptn.cc test fails to build with cudaStreamGetCaptureInfo_v2
in CUDA 12.0.
fix was to change runtime API cudaStreamGetCaptureInfo_v2
to Driver cuStreamGetCaptureInfo_v2
Change-Id: I44a0110770d3246f5345092acae301c9a2f6d520
[ROCm/clr commit: 0aa70ee0e1
2023-05-05 10:10:07 -04:00
d43e7a2db1
SWDEV-396277 - Offset and bit size correction, Considaration of SA ID for Navi.
...
Correct sm id formula for GFX10 and GFX11.
Change-Id: I2883c139b8e684e0334ccc81f703a09e3ddec588
[ROCm/clr commit: a167abefe5
2023-05-05 01:04:42 -04:00
91f676904b
SWDEV-393199 - Added new include file for opengl interop mappings for nvidia
...
Change-Id: I2e955a9dd06539939188a5f2e1dde4f173af1202
[ROCm/clr commit: 633e720da4
2023-05-03 19:43:24 -04:00
ebc60d68a8
SWDEV-396574 – Refactor texture channel type checking
...
Create __hip_is_tex_surf_channel_type to replace
__hip_is_tex_channel_type
__hip_is_itex_channel_type
__hip_is_surf_channel_type .
Change-Id: I1692b92d417bad742d562679f218ebf8ca532e31
[ROCm/clr commit: 381e6520d0
2023-05-02 10:01:13 -04:00
fa88970f6a
SWDEV-395559 - Move unsigned short up.
...
Change-Id: I3373a7bc22e632dc10b94b93ff023444d456b2b7
[ROCm/clr commit: cbd91bdc19
2023-05-02 00:43:36 -04:00
3a37f33e4e
SWDEV-396574 – Refactor device mapping functions
...
Refactor mapFrom(), mapTo(), mapElem(),
__hip_is_surf_channel_type() and
__hip_is_itex_channel_type()
Change-Id: I1692b92d407bad742d562678f218ebf8ca532e91
[ROCm/clr commit: 2f2d02649f
2023-05-01 13:57:10 -04:00
a00b618051
SWDEV-395413 - Fix fp16 header errors with -Werror in hiprtc
...
Change-Id: I7875b91758e826b439c67ac9f211a20f9b6133f0
[ROCm/clr commit: a67f354cec
2023-04-26 13:05:20 -04:00
44c74a77d2
SWDEV-390626 - Fix wrong mapping functions
...
Remove wrong functions
__hipMapFromNativeFloat4()
__hipMapToNativeFloat4()
Replace them with mapFrom() and mapTo()
Change-Id: I1692b92d397bfd732d562778f918ebf8ca532e93
[ROCm/clr commit: 650b6767c4
2023-04-25 13:19:00 -04:00
42dda1e6f4
SWDEV-390170 - guard deprecated runtime apis on CUDA 12.0
...
Change-Id: I4ab967c276dfa98f75d508b9484e8d1324b4e4a7
[ROCm/clr commit: 9ca5e71127
2023-04-05 16:36:53 +00:00
b7a0456cfb
SWDEV-389033 - Update header for cooperate group
...
Change-Id: Ica8f99c644a32835bf480b52a6a2af861f1526c0
[ROCm/clr commit: 0442501849
2023-04-05 10:58:04 +00:00
55c387ca23
SWDEV-387173 - Added cuda mappings for hipGraphMemAttr* enums
...
Change-Id: Ie5485ec518c6d107901a429ac3614e22caa9196b
[ROCm/clr commit: 1d6c40b569
2023-03-09 08:08:06 -05:00
cfcc0aede9
SWDEV-330658 - Added flag hipHostRegisterReadOnly
...
Change-Id: Idb59dc6187e99512546dfeafde44c08ae85f6057
[ROCm/clr commit: b689c56107
2023-03-09 00:20:24 -05:00
8947306ffd
SWDEV-384714 - Add hipRTC support for amd_hip_fp16
...
Change-Id: Ib6e2b46908d740909dfc15253965590f496a7068
[ROCm/clr commit: a8c2375fe1
2023-03-01 06:57:57 -05:00
2bcde46b12
SWDEV-372153 - Add hipStreamGetDevice Implementation
...
Change-Id: Ifd1f13e311e8221ca6d94cf27f9131eb97678067
[ROCm/clr commit: a7049bf7a0
2023-03-01 04:35:49 -05:00
cd6c8fc2fb
SWDEV-293749 - Fix for operator mixup
...
Change-Id: I61d1fea5a6ed2176dd92050c6d96cee1af3a39fb
[ROCm/clr commit: d0920c5959
2023-02-23 04:45:23 -05:00
d650f7a50c
SWDEV-345571 - Added support for half/half2 data types for warp shuffle functions
...
Change-Id: I276a55129d6527b73292d75eb18403acd2623c8a
[ROCm/clr commit: 32a9249d3e
2023-02-22 22:40:01 -05:00
013905b593
SWDEV-319526 - SE ID size incresed.
...
Change-Id: Ia7df94d172102b321f12c8caa821e3a7e4447a21
[ROCm/clr commit: 0ad47eb3e5
2023-02-21 22:13:57 -05:00
b91c27aef1
SWDEV-384362 - Added explicit cast from __fp16 to _Float16 in rcph
...
Change-Id: Ibbb11e928a80126ed7a8c7cd8bddebc74c38986d
[ROCm/clr commit: aaf1c19609
2023-02-21 17:32:59 -05:00
a9675e0faa
SWDEV-384100 - HIP support for CUDA 12.0
...
Apps are failing to build due to undefined deprecated texture APIs
Change-Id: I1fb64adc4bc0ba6ee6ecaa65d54b34da0327e6a3
[ROCm/clr commit: fc6a77a09f
2023-02-21 12:23:48 -05:00
9c51780b13
SWDEV-338733 - Implement hipArrayGet* APIs
...
- Add implementation for hipArrayGetInfo, hipArrayGetDescriptor &
hipArray3DGetDescriptor APIs
Change-Id: I181a472066006bc3bd0d987408ea67e218310983
[ROCm/clr commit: 287d07ccd4
2023-02-16 23:04:29 -05:00
5e61121d88
SWDEV-1 - Use proper __builtin_amdgcn_rcph builtin
...
Change-Id: Ic0b1b25a5ab7d132cb51425f2a17bc779c762668
[ROCm/clr commit: eacf63673b
2023-02-07 10:58:48 -05:00
6035907648
SWDEV-1 - Eliminate rcp_2f16 pseudo intrinsic
...
No such wrapper or intrinsic would ever exist because there is no such
underlying instruction.
Change-Id: I6c3f64cd2df2a58edf32037da8f5712868f296ea
[ROCm/clr commit: bebbf3c4ec
2023-02-07 10:58:31 -05:00
d2904ffe47
SWDEV-380687 - Fixed typo in safe atomicAdd for gfx90a
...
Change-Id: I87bc6d9e0ef1f564d679c6280c71c4633d3aa619
[ROCm/clr commit: 6704f3d0f0
2023-02-07 10:14:34 -05:00
a6a6f744ee
SWDEV-380466 - Fixed typo in unsafe atomicAdd for doubles and gfx940
...
Change-Id: I3b9ea4773f94bf6a9b9dfb655062f42aeb3b5eba
[ROCm/clr commit: 24d3d8216b
2023-02-07 10:06:17 -05:00
716ddd1d98
SWDEV-1 - Reapply "SWDEV-1 - Directly call __builtin_amdgcn_fence"
...
This reverts commit 7b3cf2e9d7https://github.com/ROCmSoftwarePlatform/rocPRIM/commit/ba8a86166ec9c4cf3a40ecde7017feeb1484e7f6
Change-Id: I194559484a5a0d7f4443381fe77218ea73d2def9
[ROCm/clr commit: 8c7391398a
2023-02-03 10:54:27 -05:00
c77979a365
SWDEV-1 - Use proper builtins for math intrinsics
...
Change-Id: If0e420332c718abe0e9f6316c467b6b29b80b183
[ROCm/clr commit: 14477c24d0
2023-02-01 07:19:45 -05:00
e8b7717abb
SWDEV-375004 - Fix rocprim test failure
...
- For !__HIPCC_RTC__ case, operator<<(std::ostream& os, const hip_bfloat16& bf16) calls itself in endless recursion
- Convert hip_bfloat16 to float to fix this
Change-Id: I252a656817550caf43c587cebf461474f12b8c0c
[ROCm/clr commit: 8b00f56577
2023-01-25 00:01:02 -05:00
d96114fd22
SWDEV-372396 - Address the errors in hiprtc headers with -Werror
...
Change-Id: Ied553216dfc2ff8b5c72de617cb47b6ca8f52063
[ROCm/clr commit: 0ccd41050b
2023-01-23 17:25:42 +00:00
7b3cf2e9d7
SWDEV-378321 - Revert "SWDEV-1 - Directly call __builtin_amdgcn_fence"
...
This reverts commit 1de57c06b35b39c346ad
2023-01-19 13:01:27 -05:00
f94a34e128
SWDEV-373231 - Support hip atomics header with HIPRTC
...
Change-Id: Ic500dfb66ed5ef0c4b672dfd0595409d0e8caaf5
[ROCm/clr commit: 842b9d0b56
2023-01-17 00:31:07 -05:00
c9fa0aad8b
SWDEV-369961 - Add mappings for enum hipGraphInstantiateFlags and types.
...
Change-Id: I03fa8221684b08a0c44e12aaf2eb7ce5281be629
[ROCm/clr commit: 8bd45ae5da
2023-01-15 12:17:21 +00:00
967ad97993
SWDEV-1 - Use proper builtin for groupstaticsize
...
Remove the now empty header for asm intrinsic wrappers.
Change-Id: I63495dc6ed899b1ea823062f2be2fb064af8d4f9
[ROCm/clr commit: 8615a89f24
2023-01-13 13:14:10 -05:00
9c811dc241
SWDEV-353281 - Initial support of memalloc in graph
...
Add memory allocation support in graph. Current implementation uses
cache from mempool to hold the allocations which belong to the graph.
Also the resource tracking is disabled at this moment because mempool
operates with hip::Stream objects, but graph has execution with
amd::HostQueue objects.
Change-Id: I54fe3250126d24f5a26ada975f37d429bb4ef17b
[ROCm/clr commit: eef47ca24a
2023-01-13 13:06:59 -05:00
6035b0e214
SWDEV-376386 - Support __hip_move_dpp with hipRTC
...
Change-Id: If9a6fe23d6df143a7f522823fca7183416048c6a
[ROCm/clr commit: c193503722
2023-01-13 00:05:31 -05:00
1de57c06b3
SWDEV-1 - Directly call __builtin_amdgcn_fence
...
The device libraries provide hip.bc, which only contains
__atomic_work_item_fence. This is identical to OpenCL's
atomic_work_item_fence, except prefixed with __. This only existed to
switch over the unknown values the OpenCL function provides. There's
no need to go through the wrapper here since it's using constant
values, and without it we can drop one of the bitcode libraries. I'm
guessing this was a holdover from before the fence builtin existed.
Change-Id: I8b04614f96194eafddeba295215c12c3856e6c42
[ROCm/clr commit: 3e54bad5b3
2023-01-12 12:04:09 -05:00
ac1201f598
SWDEV-1 - Remove unused intrinsic declaration
...
The uses have moved to using the proper __builtin_amdgcn_ds_swizzle.
Change-Id: I82159ebf41fb91ac6a9d07b33311e569dce5e754
[ROCm/clr commit: 91b851fad7
2023-01-12 12:04:09 -05:00
bfa0b9f844
SWDEV-374405 - Added OpenGL interoperability APIs for nvidia
...
Change-Id: I1d6ad5c610ab6ee805bd07dacea316b3242ed129
[ROCm/clr commit: e97dcfbe48
2023-01-12 05:22:14 -05:00
87db95fad7
SWDEV-368881 - Implement hipModuleLaunchCooperative* APIs
...
- Add implementation for hipModuleLaunchCooperativeKernel, hipModuleLaunchCooperativeKernelMultiDevice APIs
Change-Id: I2a80264e458549211c34b413397a08b57d021147
[ROCm/clr commit: b321e2afc6
2023-01-10 13:50:20 -05:00
Ioannis Assiouras
Jaydeep Patel
Ajay
Satyanvesh Dittakavi
kjayapra-amd
sdashmiz
Jatin Chaudhary
taosang2
Julia Jiang
Anusha GodavarthySurya
Sarbojit Sarkar
Rakesh Roy
Matt Arsenault
Maneesh Gupta
German Andryeyev