fe2d747bcc
SWDEV-401489 - [ABI Break] Removed hipModuleLaunchKernelExt
...
Change-Id: I0b31d9db755f8a89ead203dbd238a93c18b76855
2023-09-21 23:50:16 -04:00
15ba5c0004
SWDEV-422808 - Add E5M2 and E4M3 for nvidia headers
...
Change-Id: Ib40e75c1b2e18d75164607a46e95fc322363c08e
2023-09-21 11:57:04 -04:00
d7d0f11318
SWDEV-395996 - Add HIPRTC support for missing hip headers
...
hip headers such as hip_math_constants.h, library_types.h,
hip_common.h, channel_descriptor.h, device_functions.h, hip_complex.h,
hip_texture_types.h, math_functions.h, surface_types.h
are added in HIPRTC
Change-Id: I4a4c198449ceb609c3ff55e00b43056c1f085431
2023-09-21 03:11:06 -04:00
8fe5100d16
SWDEV-418230 - fix warning seen in HIP headers
...
This PR fixes warning seen on HIP headers due to -Wignored-attributes.
The warning is attributes for a variable must precede definition.
This also fixes a potential issue with C-style header where templates
were declared outside __cplusplus.
Change-Id: I78bfd391717c7891afb442ef79812ea630c0ff49
2023-08-24 08:41:08 -04:00
19afdf719e
SWDEV-414425 - __half2's member variable should be __half instead of unsigned short
...
We currently have __half2 made up of unsigned short instead of __half.
This prevents users to do operation seamlessly when they want to operate on individual components.
Change-Id: I856917db905f68055fdf484f526707fe8ea3117d
2023-08-22 04:25:19 -04:00
051e1005f4
SWDEV-415029 - [ABI Break] Remove hcc symbols
...
Change-Id: Ic0082d3960aadbb7ac559141b6e84bd29a75b5cd
2023-08-10 21:21:01 -04:00
ee3714e916
Github-3225 - Fix hip on cuda build issue with -default-stream=per-thread
...
Change-Id: I0485891c265617c213964f4130e90fbca9d801d4
2023-08-04 06:15:47 -04:00
8c89d16572
Revert "SWDEV-264166 - [ABI Break] goodbye gcnArch, hello gcnArchName"
...
This reverts commit f136a576f5
2023-07-31 21:41:12 -04:00
f136a576f5
SWDEV-264166 - [ABI Break] goodbye gcnArch, hello gcnArchName
...
Change-Id: I4b31284243a801f92f0be9468c25db7d027d9a13
2023-07-25 02:51:29 -04:00
b67d055eb6
SWDEV-412457 - remove unused header, add correct header for cpp
...
Change-Id: I2192daec7c033e94097c26db6177e14558a8728d
2023-07-21 11:30:59 -04:00
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
Ioannis Assiouras
Jatin Chaudhary
Satyanvesh Dittakavi
taosang2
Maneesh Gupta
Sourabh Betigeri
Jaydeep Patel
Ajay
kjayapra-amd
sdashmiz
Julia Jiang
Anusha GodavarthySurya
Sarbojit Sarkar