AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
5,964 Commits 3 Branches 0 Tags
18af8b7754e5fb7ffde66d024a146bea4607abb9
Commit Graph

1365 Commits

Author SHA1 Message Date
kjayapra-amd d3ff861a37 SWDEV-245533 - Implementing Mipmap array APIs 
Change-Id: I222c8d0fcbd50cdefd702462e689463bb36366d2


[ROCm/clr commit: 31d412c292]
 2021-04-30 16:33:43 -04:00
Satyanvesh Dittakavi 9e4b7ff5bb SWDEV-283388 - Fix hipMemRangeGetAttributes on Nvidia Platform 
Change-Id: I5daeacd9dd5c6ce7f914d6e6e45dd41fb2a675a5
hipMemRangeGetAttributes was returning hipErrorInvalidValue due to improper
mapping of the arguments to cudaMemRangeGetAttributes.


[ROCm/clr commit: cc39ceab25]
 2021-04-29 06:06:03 -04:00
Satyanvesh Dittakavi 59c118bb57 SWDEV-281789 - Add missing HMM attributes on CUDA path 
Change-Id: I11167eea006301e01a1f91708bf6d0ac832d8b7f


[ROCm/clr commit: 120436423c]
 2021-04-26 13:54:01 -04:00
Yaxun (Sam) Liu e04783afe7 SWDEV-255234 - remove workaround for warpSize after clang fix is released 
The workaround is no longer needed as the compiler emits the macro itself.

Change-Id: I6a06e73353628bcea71f6bd23503ab6d8e42a29d


[ROCm/clr commit: 37b90c2f64]
 2021-04-26 08:49:15 -04:00
Anusha GodavarthySurya dcad465a22 SWDEV-282361 - HIP support for NVRTC 
Change-Id: I82869af8194b595f9a2fb64ad034630786189335


[ROCm/clr commit: c23586440b]
 2021-04-20 09:28:58 -07:00
Tao Sang fe7d103d56 SWDEV-279657 - Fix hipMallocManaged-N256M failure 
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd


[ROCm/clr commit: 20fd6b8a66]
 2021-04-20 09:07:31 -04:00
Sourabh Betigeri eedde26cc9 SWDEV-256723 - Added group partitioning feature in ROCm CG. 
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9


[ROCm/clr commit: 0a0b026304]
 2021-04-19 18:53:17 -04:00
Julia Jiang e103d4f31d SWDEV-270961 - Update hip_programming_guide.md for event handling 
Change-Id: Ieadac9972e5ee13c05ccb42a679866f494f96f47


[ROCm/clr commit: cb22874ebd]
 2021-04-16 12:14:25 -04:00
Satyanvesh Dittakavi 74cf3b8795 SWDEV-281504 - Rename structure names to use reserved names in HIP headers 
HIP headers use few structure names as X, Y, and Z. This causes
compilation issues when the apps use similar names as macros.
Renamed the struct names to use reserved names such as
__X, __Y and __Z

Change-Id: I59416c3734f274e853c87d4856b7e616f6cee5f5


[ROCm/clr commit: 009543ec7a]
 2021-04-15 09:52:58 -04:00
Tao Sang 73df8d8dd9 SWDEV-273138 - Rearrange device attributes 
Change-Id: Iab5902c9a2702456fbe437fdefc40541c48abb74


[ROCm/clr commit: 2c0b63059b]
 2021-04-12 17:05:27 -04:00
kjayapra-amd 693c5653c5 SWDEV-274276 - Implement system scope atomics to _system builtins. Default atomics will map to agent. 
Change-Id: I63b13063274418e96d4be0159c779127b166bea5
(cherry picked from commit 7c4ae8ca1daac0b75ac36c4e4a45b8d13f219d14)


[ROCm/clr commit: 61d1eaa522]
 2021-04-09 10:23:32 -04:00
Sarbojit Sarkar 9d490550c5 SWDEV-260454 - Fix for idenfying bad streams 
Change-Id: I122ff6f47535c3c76ab56ba49ab1450ef886b15f


[ROCm/clr commit: daf0cbca3c]
 2021-04-07 12:13:30 -04:00
Sarbojit Sarkar 4e5bf6268b SWDEV-280131 - Fix __half2 member access bug 
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/clr commit: 9cbb283771]
 2021-04-07 12:12:02 -04:00
pghafari 4578277e13 SWDEV-245532 - HIP - Vulkan interop 
Change-Id: Iba1ef8112e318b4f099da5a4a4602e0dae7de9e3


[ROCm/clr commit: a9304f6111]
 2021-03-31 10:23:31 -04:00
Sarbojit Sarkar 47a6267c7c SWDEV-277926 - Updated deprecated APIs in Cuda 
Change-Id: I9ff655af227b245067eb760325c395bb562696ee


[ROCm/clr commit: b7a03695c3]
 2021-03-29 01:19:19 -04:00
Satyanvesh Dittakavi 85ca63f256 SWDEV-277152 - Add hipMemcpy2DToArrayAsync API in headers 
Also, address few scenarios for hipMemcpy2DToArray/Async to return
proper error types

Change-Id: Idbadf666a5e7bebc0f3ea8b7048b79208e04cf6b


[ROCm/clr commit: 68abfb4aff]
 2021-03-27 13:50:38 -04:00
jujiang 88c0959afb SWDEV-277423 - Correct hipStreamWaitValue doxygen format 
Change-Id: I8914c14cb7a05d5d0bdfa054af14765c872c70a6


[ROCm/clr commit: cc69e95c1a]
 2021-03-19 14:10:41 -04:00
Tao Sang 2e89139b49 SWDEV-273138 - Update canUseStreamWaitValue retrieving 
Remove canUseStreamWaitValue from hipDeviceProp_t.
Update canUseStreamWaitValue retrieving in hipDeviceGetAttribute().

Change-Id: I275bd42d8b03e141caaf9f1bc6b714e51ca72dfb


[ROCm/clr commit: 08625144b3]
 2021-03-18 22:42:35 -04:00
cjatin 48f0ba9cee SWDEV-272811 - Using OCML functions for conversion of fp to int 
Change-Id: Id0c02bf6a2e0553d522035b078a9db4cd3fad215


[ROCm/clr commit: 06fa63df04]
 2021-03-18 11:43:30 -04:00
Ravi C Akkenapally 212cc49ed6 SWDEV-276827 - Stream Operations: match API with CUDA 
Change-Id: Ia79a950561e97df3b2229f76f5512dede2babf98


[ROCm/clr commit: 397bac37a3]
 2021-03-18 07:52:29 -07:00
Tao Sang e212e1a947 SWDEV-273943 - Enable runtimeApi.event dtest 
Add device_id_ in hip::event to match cuda behaviour in
hipEventQuery() and hipEventRecord().
Enable hipEventElapsedTime test on AMD platform.
Workarround sporadic crash of hipEventIpc test due to
some bug of event ipc.
Add missing hipEventDestroy() in some event tests.
Fix some logic code errors.
Fix typo in comment.

Change-Id: I9ec74c475161b3e31df48d193449023e921f2924


[ROCm/clr commit: 629ea5fe19]
 2021-03-16 17:12:08 -04:00
jujiang 7020872b45 SWDEV-270961 - Add doxygen for Texture APIs 
Change-Id: I4038320a638292440d9ca8c23ffcabffcd9a48c2


[ROCm/clr commit: 3126196cca]
 2021-03-09 16:23:56 -05:00
Satyanvesh Dittakavi c8e84cbf02 SWDEV-275317 - Fix hipMemcpy2DFromArray to return proper error types 
Change-Id: Id722865d81460bfd2fa6ad7a198b6e3c2a08265a


[ROCm/clr commit: daafd303ec]
 2021-03-09 05:22:23 -05:00
Satyanvesh Dittakavi 6531614a23 SWDEV-274404 - Add hipDrvMemcpy3D* and hipMemcpy2DFromArray* APIs on HIP CUDA 
Change-Id: I4aba2bff60a7bae6b01b6e471968227b0df8e192


[ROCm/clr commit: 37d4677aba]
 2021-03-08 13:14:25 -05:00
Arya.Rafii 3d6667ccb7 SWDEV-269246 - Implementation of hipDrvMemcpy2DUnaligned 
Change-Id: I86fdd3b930cbd74c45cd31944f0ea52c0ff65a59


[ROCm/clr commit: 8cb232ddef]
 2021-03-04 14:38:06 -05:00
Arya.Rafii cd4aec747f SWDEV-269246 - Added missing exports for hipArrayDestroy 
Change-Id: I730814720bb618e895efbe2f412e437110bed8bc


[ROCm/clr commit: 9f142f988d]
 2021-03-04 14:29:16 -05:00
Ravi C Akkenapally 4cf7a5799a SWDEV-179105 - Stream Operations: Add swqupport for Wait and Write 
Change-Id: I9d6d0665d12b62fe705ce1569a0e8264a4f23ab7


[ROCm/clr commit: fd0f49503f]
 2021-03-02 12:15:46 -08:00
Vladislav Sytchenko 610611edd1 SWDEV-232428 - Enable device printf for Windows 
Change-Id: Id72cfc34cfcfcbcb459bd8d84979637eaf7947dd


[ROCm/clr commit: 1f8bdcaf20]
 2021-02-26 11:46:38 -05:00
Satyanvesh Dittakavi 936d760a58 SWDEV-271491 - Fix flags for hipSetDeviceFlags on HIP-CUDA path 
Change-Id: I29446d5cc5a26a4b83fa45175ccdf1d8f3a9ea40


[ROCm/clr commit: c2a767a66e]
 2021-02-25 12:06:33 -05:00
Jatin Chaudhary 75e91e9073 SWDEV-272811 - hipCabs returns a double and uses sqrtf, which maps to f32 operation. sqrt should be used instead 
Change-Id: I4f74ee8853113fcebfa508bea9308ae93c7ad13b


[ROCm/clr commit: 474493b929]
 2021-02-25 08:47:19 -05:00
Jatin Chaudhary 3c08aece90 SWDEV-268531 - Fixing shadow variable warning in vector_types 
Change-Id: Ic57e22853529a953582c9194d09133a5aab989aa


[ROCm/clr commit: 3f6bf4c260]
 2021-02-16 06:51:37 -05:00
Maneesh Gupta 60f4dcc336 SWDEV-271416 - Keep HIP_DYNAMIC_SHARED macro for compat with existing HIP apps 
Change-Id: I536e0c65d6e8696cbc369082350834abd710abca


[ROCm/clr commit: 42ab466904]
 2021-02-16 00:09:48 -05:00
Maneesh Gupta 125de2dbe6 SWDEV-269351 - Revert "Implement assert() using the new fprintf_stderr facility" 
This reverts commit 10af608c66.

Reverting since this is dependent on a device libs change which is not yet in mainline.

Change-Id: I094781b868f39995d1eecb41488c1a1a0147b787


[ROCm/clr commit: 18234e1d24]
 2021-02-12 03:46:17 -05:00
cjatin 5fe210011e SWDEV-268531 - Fixing shadow varible warning seen with hip vector usage 
Change-Id: I9e20a41e74e473b328cc173f2c27b06352128c88


[ROCm/clr commit: 9a2e762ccb]
 2021-02-09 13:33:12 -05:00
Julia Jiang 0e20fbfbec SWDEV-271416 - Remove HIP_DYNAMIC_SHARED macro in hip 
Change-Id: I12f39ea8438eb7ce76d8ffb2151b4faa93689048


[ROCm/clr commit: e4fdbfcf5b]
 2021-02-08 13:17:46 -05:00
Sarbojit Sarkar 962dff6a61 SWDEV-265469 - added constexpr constructor for dim3 
Change-Id: I2e23a403f272d1ff0ade24fec11190d2f3244e5f


[ROCm/clr commit: cee3e1aa37]
 2021-01-28 13:23:51 -05:00
Satyanvesh Dittakavi 14be9b54a2 SWDEV-269784 - managed memory support for HIP CUDA 
Change-Id: I01f9fc64573f402031eceab24395e5cbd93007f9


[ROCm/clr commit: 0074429d05]
 2021-01-28 07:51:52 -05:00
Tao Sang 1b1b7bffb6 SWDEV-268757 - Disable deprecation warning 
Disable it as it will fail rocgdb test

Change-Id: Ibf34c780d5bd4278adcedba1d6e057639c258483


[ROCm/clr commit: a0c8c30ae5]
 2021-01-21 15:35:32 -05:00
Satyanvesh Dittakavi fb51766fcb SWDEV-268989 - Modify atomicAdd double to use clang builtin 
Change-Id: If9d40046df2f3f5af7cc1bd6c935fbe7d686e7d8


[ROCm/clr commit: 8da9f4d432]
 2021-01-20 02:39:15 -05:00
Sameer Sahasrabuddhe 10af608c66 Implement assert() using the new fprintf_stderr facility 
The device library now provides functions to specify the host stderr
stream in a hostcall printf message. This change implements an
assert() macro which can construct such a message. The end result is
that assertions on the device are now correctly printed on the host
stderr instead of stdout.

Change-Id: I85ab8f7848bcf28303cb8dbb8a798bc6aece7d75


[ROCm/clr commit: 2cac768a07]
 2021-01-17 23:54:46 -05:00
Satyanvesh Dittakavi 7b8972f41e device property __HIP_ARCH_HAS_SHARED_INT64_ATOMICS__ set to 1 as it has compiler support 
Change-Id: Ic91c4955d4f2d52d844471f81e6f0d19418018f5


[ROCm/clr commit: 84cda7f9c2]
 2021-01-15 11:40:09 -05:00
Tao Sang 52954de0eb Fix building mathlibs failure 
Add back
__HIP_PLATFORM_HCC__
__HIP_PLATFORM_NVCC__

Change-Id: I1ae48678eafd849d6c25bcb204c1724b026be22f


[ROCm/clr commit: 8fc1ff7d4f]
 2021-01-14 14:03:15 -05:00
Tao Sang ef480eb242 Workarround for rocThrust building failure 
Define the following for workarround of rocThrust building failure,
HIP_INCLUDE_HIP_HCC_DETAIL_DRIVER_TYPES_H
HIP_INCLUDE_HIP_HCC_DETAIL_HOST_DEFINES_H

Change-Id: I1ae48677eafd749d6c25bca204c1724b026be22f


[ROCm/clr commit: 149254f7f8]
 2021-01-12 11:31:06 -05:00
Michael LIAO 9211198dcd Remove checking on double. 
- All conversions among floating point types should be allowed.

Change-Id: I6223bece51f5b2a535ab3369c5c4380f18acc74d


[ROCm/clr commit: 6b9c1744e9]
 2021-01-11 11:33:33 -05:00
Sameer Sahasrabuddhe 2df32ebc65 Identifiers with a double underscore "anywhere" are reserved 
This particular cleanup is limited to just two functions defined in
the HIP headers.

Change-Id: Ib529685265f2fda90e009b24e7e756e0cf363012


[ROCm/clr commit: 3558643c64]
 2021-01-11 15:09:53 +05:30
Saleel Kudchadker bced4a5b76 Update documentation for hipEventCreateWithFlags 
Change-Id: I2658bd95df0d3a802cce4ffcb8dfd40e7055b0f7


[ROCm/clr commit: dab9ae32b2]
 2021-01-08 16:32:57 -05:00
Rahul Garg f169546403 Add IPC Events support 
Change-Id: Iac2bf3d5e1d9a993bebbb066c20d300d6f05558b


[ROCm/clr commit: 3829645039]
 2021-01-08 20:09:26 +00:00
Tao Sang eeb275d643 Remove hip-hcc codes: Part four 
Remove __HCC__, __HCC_ONLY__, __HCC_CPP__, __HCC_C__,
__HCC_OR_HIP_CLANG__, __HIP_ROCclr__ and their guarded codes.

Remove Hcc codes from directed_tests and samples.

Remove __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__ from
some files where they are not necessary.

Add deprecation notice.

Change-Id: I1ae467eafd749d6c25bca204c1724b026be21fce


[ROCm/clr commit: d504a761ad]
 2021-01-08 10:53:34 -05:00
Tao Sang 2c1c9f78d6 Remove hip-hcc codes: Part three 
1.Rename include/hip/hcc_detail/ as include/hip/amd_detail/

2.Rename include/hip/nvcc_detail/ as include/hip/nvidia_detail/

3.Create __HIP_PLATFORM_AMD__ to replace __HIP_PLATFORM_HCC__

4.Create __HIP_PLATFORM_NVIDIA__ to replace __HIP_PLATFORM_NVCC__

After hcc_detail, nvcc_detail, __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__
have been removed from upstream, they will be removed from hip runtime.

Change-Id: I1ae457effd739d6c25bca203c1724b026be21fce


[ROCm/clr commit: 8a2b0b7424]
 2021-01-05 10:39:31 -05:00
jujiang c6862ea596 SWDEV-249486-Add doxygeny for API hipExtModuleLaunchKernel 
Change-Id: Id7451ef4f669238a38ed92ec72008326c85afc4a


[ROCm/clr commit: b14bf9e98b]
 2020-12-14 15:34:32 -05:00