AI/rocm-systems
2
0
Bifurcation 0
Code Tickets Demandes d'ajout Actions Paquets Projets Publications Wiki Activité
12 413 Révisions 3 Branches 0 Étiquette
d418e686cee42cdd16769ff8cdc8f20aed5b01bb
Graphe des révisions

1596 Révisions

Auteur SHA1 Message Date
Satyanvesh Dittakavi 54c3576dd1 Github-3225 - Fix hip on cuda build issue with -default-stream=per-thread 
Change-Id: I0485891c265617c213964f4130e90fbca9d801d4


[ROCm/clr commit: ee3714e916]
 2023-08-04 06:15:47 -04:00
Maneesh Gupta 045ec1919e Revert "SWDEV-264166 - [ABI Break] goodbye gcnArch, hello gcnArchName" 
This reverts commit 20add33513.

Change-Id: Ia7b9ca115be4f9591b195194eed967fc6c330012


[ROCm/clr commit: 8c89d16572]
 2023-07-31 21:41:12 -04:00
Jatin Chaudhary 20add33513 SWDEV-264166 - [ABI Break] goodbye gcnArch, hello gcnArchName 
Change-Id: I4b31284243a801f92f0be9468c25db7d027d9a13


[ROCm/clr commit: f136a576f5]
 2023-07-25 02:51:29 -04:00
Jatin Chaudhary dfc4d60ec4 SWDEV-412457 - remove unused header, add correct header for cpp 
Change-Id: I2192daec7c033e94097c26db6177e14558a8728d


[ROCm/clr commit: b67d055eb6]
 2023-07-21 11:30:59 -04:00
Jatin Chaudhary 9c28f156e4 SWDEV-411156 - Use _Float16 instead of unsigned short values 
Change-Id: I23387bf27b2bd70fb47a3a36ffaf114e6c03e0bc


[ROCm/clr commit: 295963fe7a]
 2023-07-20 01:03:32 +01:00
Ioannis Assiouras 2b1e2a860b SWDEV-398472 - Added new include file for openGL interop APIs for AMD backend 
Change-Id: I255030b9e70e777c1ede998d5dcf554a266492c5


[ROCm/clr commit: 3a8e0dd1cb]
 2023-07-17 11:57:36 -04:00
Sourabh Betigeri 178b3faa70 SWDEV-396657 - Using abort() instead of trap instruction to fix a compilation error 
Change-Id: Ia6a3f58ca5891c5700dd7853e088c51fef1a1e09


[ROCm/clr commit: c46adc9b56]
 2023-07-13 18:48:05 -04:00
Jaydeep Patel c2b7aa6b73 SWDEV-407692 - Add def values to match non spt API declaration and match HIP_SYMBOL with nvidia_hip_runtime.h. 
Change-Id: I8d87aa1b14fec6ca73544c78a47e7ad385b99e21


[ROCm/clr commit: 5a68556c9b]
 2023-07-01 01:05:46 -04:00
Sourabh Betigeri 4ed9d80104 SWDEV-396656 - Adds meta_group_rank and meta_group_size APIs in ROCm CG 
Change-Id: I2ded1a97379dfa736219cffe28fe051c58ea1260


[ROCm/clr commit: a77fb5a1dd]
 2023-06-27 12:24:10 -04:00
taosang2 3de5e3bba3 SWDEV-407139 - Update __hipMapVector 
Update __hipMapVector to fix surface test
failure

Change-Id: I6179d9f3b2ddd4e42b9a6f7f3912322cfca22cff


[ROCm/clr commit: 7bea186750]
 2023-06-26 23:56:05 -04:00
taosang2 b005d758b9 SWDEV-407139 - Update __hipMapVector 
Update __hipMapVector for C++11

Change-Id: I6179d9f3b2ddf4e42b9a6f7f3912322cfca02cfe


[ROCm/clr commit: d9955b6707]
 2023-06-25 23:15:21 -04:00
taosang2 0d9cc9efd2 SWDEV-368553 - Fix C build failure 
Change-Id: I56d760fa6cf8544100e3bcf3d35129bd16d8a42f


[ROCm/clr commit: e9e69f4c07]
 2023-06-23 18:47:53 -04:00
taosang2 9aa3a87b66 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


[ROCm/clr commit: f03c11491b]
 2023-06-22 17:24:21 -04:00
Sourabh Betigeri c00cd118d3 SWDEV-402274 - Adds CG API group_dim() in class thread_block 
Change-Id: I1c2569fffbc6fc730df9ba80786459c71140d327


[ROCm/clr commit: 422d3ea035]
 2023-06-21 20:10:19 -04:00
Jatin Chaudhary 0cd45b8cc7 SWDEV-399522 - Fix the issue #2 raised on github clr repo. Adds signed long long atomics 
Change-Id: I09c386d45e219e472d2da1449f678b9d17fe3e2e


[ROCm/clr commit: be02e1e524]
 2023-06-16 08:53:45 -04:00
Jatin Chaudhary 8913c4de4f SWDEV-400136 - change make_complex function name to make_hipComplex 
Change-Id: Ia276610286df80ec35fe11f303eb9919eeda87dd


[ROCm/clr commit: f7f70a0880]
 2023-06-15 09:02:38 -04:00
Ioannis Assiouras 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
Jaydeep Patel 7be6ca6306 SWDEV-404118 - Change to uint. 
Change-Id: Ib9ced171a4330e868a584bfb86d7ee5418e784ed


[ROCm/clr commit: 9daf8e3177]
 2023-06-06 13:17:56 -04:00
Ajay 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
Satyanvesh Dittakavi 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
Jaydeep Patel 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
Satyanvesh Dittakavi 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
kjayapra-amd 62302ac4fa SWDEV-393910 - Adding CAS expanders under gfx941 tag. 
Change-Id: I2c4bcf56be419d1f037b8555ad254a2dc49d0c5b


[ROCm/clr commit: feb22250f3]
 2023-05-22 09:59:05 -04:00
sdashmiz 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
Jatin Chaudhary 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
Jatin Chaudhary 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
Satyanvesh Dittakavi 130f9c5117 SWDEV-399203 - Use clang pragma only with clang 
Change-Id: I21d84ccde07e243b6bc06f1980c24b399e74d1c3


[ROCm/clr commit: a7041d15a7]
 2023-05-10 04:19:51 -04:00
kjayapra-amd 23584feba4 SWDEV-393910 - Port gfx94x changes to mainline. 
Change-Id: Ibf727223bbe5230b132b47c39e0fc1d87cbd3b9c


[ROCm/clr commit: f14e8a2dba]
 2023-05-05 15:16:23 -04:00
Ajay 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
Jaydeep Patel 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
Ioannis Assiouras 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
taosang2 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
Jaydeep Patel fa88970f6a SWDEV-395559 - Move unsigned short up. 
Change-Id: I3373a7bc22e632dc10b94b93ff023444d456b2b7


[ROCm/clr commit: cbd91bdc19]
 2023-05-02 00:43:36 -04:00
taosang2 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
Satyanvesh Dittakavi 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
taosang2 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
Ajay 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
Julia Jiang b7a0456cfb SWDEV-389033 - Update header for cooperate group 
Change-Id: Ica8f99c644a32835bf480b52a6a2af861f1526c0


[ROCm/clr commit: 0442501849]
 2023-04-05 10:58:04 +00:00
Ioannis Assiouras 55c387ca23 SWDEV-387173 - Added cuda mappings for hipGraphMemAttr* enums 
Change-Id: Ie5485ec518c6d107901a429ac3614e22caa9196b


[ROCm/clr commit: 1d6c40b569]
 2023-03-09 08:08:06 -05:00
Anusha GodavarthySurya cfcc0aede9 SWDEV-330658 - Added flag hipHostRegisterReadOnly 
Change-Id: Idb59dc6187e99512546dfeafde44c08ae85f6057


[ROCm/clr commit: b689c56107]
 2023-03-09 00:20:24 -05:00
Satyanvesh Dittakavi 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
Jatin Chaudhary 2bcde46b12 SWDEV-372153 - Add hipStreamGetDevice Implementation 
Change-Id: Ifd1f13e311e8221ca6d94cf27f9131eb97678067


[ROCm/clr commit: a7049bf7a0]
 2023-03-01 04:35:49 -05:00
Sarbojit Sarkar cd6c8fc2fb SWDEV-293749 - Fix for operator mixup 
Change-Id: I61d1fea5a6ed2176dd92050c6d96cee1af3a39fb


[ROCm/clr commit: d0920c5959]
 2023-02-23 04:45:23 -05:00
Anusha GodavarthySurya 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
Jaydeep Patel 013905b593 SWDEV-319526 - SE ID size incresed. 
Change-Id: Ia7df94d172102b321f12c8caa821e3a7e4447a21


[ROCm/clr commit: 0ad47eb3e5]
 2023-02-21 22:13:57 -05:00
Ioannis Assiouras 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
Ajay 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
Rakesh Roy 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
Matt Arsenault 5e61121d88 SWDEV-1 - Use proper __builtin_amdgcn_rcph builtin 
Change-Id: Ic0b1b25a5ab7d132cb51425f2a17bc779c762668


[ROCm/clr commit: eacf63673b]
 2023-02-07 10:58:48 -05:00
Matt Arsenault 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