295963fe7a
SWDEV-411156 - Use _Float16 instead of unsigned short values
...
Change-Id: I23387bf27b2bd70fb47a3a36ffaf114e6c03e0bc
2023-07-20 01:03:32 +01:00
3a8e0dd1cb
SWDEV-398472 - Added new include file for openGL interop APIs for AMD backend
...
Change-Id: I255030b9e70e777c1ede998d5dcf554a266492c5
2023-07-17 11:57:36 -04:00
c46adc9b56
SWDEV-396657 - Using abort() instead of trap instruction to fix a compilation error
...
Change-Id: Ia6a3f58ca5891c5700dd7853e088c51fef1a1e09
2023-07-13 18:48:05 -04:00
5a68556c9b
SWDEV-407692 - Add def values to match non spt API declaration and match HIP_SYMBOL with nvidia_hip_runtime.h.
...
Change-Id: I8d87aa1b14fec6ca73544c78a47e7ad385b99e21
2023-07-01 01:05:46 -04:00
a77fb5a1dd
SWDEV-396656 - Adds meta_group_rank and meta_group_size APIs in ROCm CG
...
Change-Id: I2ded1a97379dfa736219cffe28fe051c58ea1260
2023-06-27 12:24:10 -04:00
7bea186750
SWDEV-407139 - Update __hipMapVector
...
Update __hipMapVector to fix surface test
failure
Change-Id: I6179d9f3b2ddd4e42b9a6f7f3912322cfca22cff
2023-06-26 23:56:05 -04:00
d9955b6707
SWDEV-407139 - Update __hipMapVector
...
Update __hipMapVector for C++11
Change-Id: I6179d9f3b2ddf4e42b9a6f7f3912322cfca02cfe
2023-06-25 23:15:21 -04:00
e9e69f4c07
SWDEV-368553 - Fix C build failure
...
Change-Id: I56d760fa6cf8544100e3bcf3d35129bd16d8a42f
2023-06-23 18:47:53 -04:00
f03c11491b
SWDEV-368553 – Add missing mipmap Apis
...
Add missing mipmap Apis’ implementation.
Fix some bugs of mimpmap apis.
Use hipmipmappedArray to differentiate cuda
and driver apis on Nvidia.
Change-Id: I6079d9f3b2ddf4e42b9a6f7f3902322cfca02cfd
2023-06-22 17:24:21 -04:00
422d3ea035
SWDEV-402274 - Adds CG API group_dim() in class thread_block
...
Change-Id: I1c2569fffbc6fc730df9ba80786459c71140d327
2023-06-21 20:10:19 -04:00
be02e1e524
SWDEV-399522 - Fix the issue #2 raised on github clr repo. Adds signed long long atomics
...
Change-Id: I09c386d45e219e472d2da1449f678b9d17fe3e2e
2023-06-16 08:53:45 -04:00
f7f70a0880
SWDEV-400136 - change make_complex function name to make_hipComplex
...
Change-Id: Ia276610286df80ec35fe11f303eb9919eeda87dd
2023-06-15 09:02:38 -04:00
4f5dfa77bd
SWDEV-401852 - Do not define hipCreateChannelDesc for long types in LP64
...
Change-Id: I56881a229ea666269d575c6bdfde5081562ec009
2023-06-06 14:28:15 -04:00
9daf8e3177
SWDEV-404118 - Change to uint.
...
Change-Id: Ib9ced171a4330e868a584bfb86d7ee5418e784ed
2023-06-06 13:17:56 -04:00
16c6b365c2
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
2023-06-06 12:11:41 -04:00
287f607d2b
SWDEV-395996 - Add double precision constants to math constants header
...
Fixes a typo and adds missing constants matching cuda
Change-Id: Iebf47d107af361cbd356c2a3b9cd6ef121d01363
2023-06-05 03:31:27 -04:00
d576356505
SWDEV-401847 - Update atomicMin/Max for float and double.
...
Change-Id: Ib5be459b8a24f0739e299ed12c9f877f8baa02b1
2023-05-29 14:27:16 -04:00
586731c2cc
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
2023-05-25 04:36:24 -04:00
feb22250f3
SWDEV-393910 - Adding CAS expanders under gfx941 tag.
...
Change-Id: I2c4bcf56be419d1f037b8555ad254a2dc49d0c5b
2023-05-22 09:59:05 -04:00
23e99dbb07
SWDEV-396533 - correct _shfl function to match cuda
...
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: I311419fd25c055339f25fe0c7a132ec9ee225600
2023-05-17 14:19:46 -04:00
15bafc9a93
SWDEV-395773 - Fix unordered compare functions in fp16 header
...
Change-Id: I9158420e37cd3151159182223c6645ed84c4fddd
2023-05-11 10:42:13 -04:00
6c793ea206
SWDEV-367537 - Add __hip_bfloat16 and vector definitions to match __nv_bfloat16
...
Change-Id: I1c0f9f5f278c2c3b4e175d9f08831ba458ed856e
2023-05-11 04:45:13 -04:00
a7041d15a7
SWDEV-399203 - Use clang pragma only with clang
...
Change-Id: I21d84ccde07e243b6bc06f1980c24b399e74d1c3
2023-05-10 04:19:51 -04:00
f14e8a2dba
SWDEV-393910 - Port gfx94x changes to mainline.
...
Change-Id: Ibf727223bbe5230b132b47c39e0fc1d87cbd3b9c
2023-05-05 15:16:23 -04:00
0aa70ee0e1
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
2023-05-05 10:10:07 -04:00
a167abefe5
SWDEV-396277 - Offset and bit size correction, Considaration of SA ID for Navi.
...
Correct sm id formula for GFX10 and GFX11.
Change-Id: I2883c139b8e684e0334ccc81f703a09e3ddec588
2023-05-05 01:04:42 -04:00
633e720da4
SWDEV-393199 - Added new include file for opengl interop mappings for nvidia
...
Change-Id: I2e955a9dd06539939188a5f2e1dde4f173af1202
2023-05-03 19:43:24 -04:00
381e6520d0
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
2023-05-02 10:01:13 -04:00
cbd91bdc19
SWDEV-395559 - Move unsigned short up.
...
Change-Id: I3373a7bc22e632dc10b94b93ff023444d456b2b7
2023-05-02 00:43:36 -04:00
2f2d02649f
SWDEV-396574 – Refactor device mapping functions
...
Refactor mapFrom(), mapTo(), mapElem(),
__hip_is_surf_channel_type() and
__hip_is_itex_channel_type()
Change-Id: I1692b92d407bad742d562678f218ebf8ca532e91
2023-05-01 13:57:10 -04:00
a67f354cec
SWDEV-395413 - Fix fp16 header errors with -Werror in hiprtc
...
Change-Id: I7875b91758e826b439c67ac9f211a20f9b6133f0
2023-04-26 13:05:20 -04:00
650b6767c4
SWDEV-390626 - Fix wrong mapping functions
...
Remove wrong functions
__hipMapFromNativeFloat4()
__hipMapToNativeFloat4()
Replace them with mapFrom() and mapTo()
Change-Id: I1692b92d397bfd732d562778f918ebf8ca532e93
2023-04-25 13:19:00 -04:00
9ca5e71127
SWDEV-390170 - guard deprecated runtime apis on CUDA 12.0
...
Change-Id: I4ab967c276dfa98f75d508b9484e8d1324b4e4a7
2023-04-05 16:36:53 +00:00
0442501849
SWDEV-389033 - Update header for cooperate group
...
Change-Id: Ica8f99c644a32835bf480b52a6a2af861f1526c0
2023-04-05 10:58:04 +00:00
1d6c40b569
SWDEV-387173 - Added cuda mappings for hipGraphMemAttr* enums
...
Change-Id: Ie5485ec518c6d107901a429ac3614e22caa9196b
2023-03-09 08:08:06 -05:00
b689c56107
SWDEV-330658 - Added flag hipHostRegisterReadOnly
...
Change-Id: Idb59dc6187e99512546dfeafde44c08ae85f6057
2023-03-09 00:20:24 -05:00
a8c2375fe1
SWDEV-384714 - Add hipRTC support for amd_hip_fp16
...
Change-Id: Ib6e2b46908d740909dfc15253965590f496a7068
2023-03-01 06:57:57 -05:00
a7049bf7a0
SWDEV-372153 - Add hipStreamGetDevice Implementation
...
Change-Id: Ifd1f13e311e8221ca6d94cf27f9131eb97678067
2023-03-01 04:35:49 -05:00
d0920c5959
SWDEV-293749 - Fix for operator mixup
...
Change-Id: I61d1fea5a6ed2176dd92050c6d96cee1af3a39fb
2023-02-23 04:45:23 -05:00
32a9249d3e
SWDEV-345571 - Added support for half/half2 data types for warp shuffle functions
...
Change-Id: I276a55129d6527b73292d75eb18403acd2623c8a
2023-02-22 22:40:01 -05:00
0ad47eb3e5
SWDEV-319526 - SE ID size incresed.
...
Change-Id: Ia7df94d172102b321f12c8caa821e3a7e4447a21
2023-02-21 22:13:57 -05:00
aaf1c19609
SWDEV-384362 - Added explicit cast from __fp16 to _Float16 in rcph
...
Change-Id: Ibbb11e928a80126ed7a8c7cd8bddebc74c38986d
2023-02-21 17:32:59 -05:00
fc6a77a09f
SWDEV-384100 - HIP support for CUDA 12.0
...
Apps are failing to build due to undefined deprecated texture APIs
Change-Id: I1fb64adc4bc0ba6ee6ecaa65d54b34da0327e6a3
2023-02-21 12:23:48 -05:00
287d07ccd4
SWDEV-338733 - Implement hipArrayGet* APIs
...
- Add implementation for hipArrayGetInfo, hipArrayGetDescriptor &
hipArray3DGetDescriptor APIs
Change-Id: I181a472066006bc3bd0d987408ea67e218310983
2023-02-16 23:04:29 -05:00
eacf63673b
SWDEV-1 - Use proper __builtin_amdgcn_rcph builtin
...
Change-Id: Ic0b1b25a5ab7d132cb51425f2a17bc779c762668
2023-02-07 10:58:48 -05:00
bebbf3c4ec
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
2023-02-07 10:58:31 -05:00
6704f3d0f0
SWDEV-380687 - Fixed typo in safe atomicAdd for gfx90a
...
Change-Id: I87bc6d9e0ef1f564d679c6280c71c4633d3aa619
2023-02-07 10:14:34 -05:00
24d3d8216b
SWDEV-380466 - Fixed typo in unsafe atomicAdd for doubles and gfx940
...
Change-Id: I3b9ea4773f94bf6a9b9dfb655062f42aeb3b5eba
2023-02-07 10:06:17 -05:00
8c7391398a
SWDEV-1 - Reapply "SWDEV-1 - Directly call __builtin_amdgcn_fence"
...
This reverts commit 5b39c346adhttps://github.com/ROCmSoftwarePlatform/rocPRIM/commit/ba8a86166ec9c4cf3a40ecde7017feeb1484e7f6
Change-Id: I194559484a5a0d7f4443381fe77218ea73d2def9
2023-02-03 10:54:27 -05:00
14477c24d0
SWDEV-1 - Use proper builtins for math intrinsics
...
Change-Id: If0e420332c718abe0e9f6316c467b6b29b80b183
2023-02-01 07:19:45 -05:00
Jatin Chaudhary
Ioannis Assiouras
Sourabh Betigeri
Jaydeep Patel
taosang2
Ajay
Satyanvesh Dittakavi
kjayapra-amd
sdashmiz
Julia Jiang
Anusha GodavarthySurya
Sarbojit Sarkar
Rakesh Roy
Matt Arsenault