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
Tao Sang
6227f3fae2
Remove hip-hcc codes: Part one
...
Remove hip-hcc codes from hip code base
Simplify hip CMakeLists.txt to exclude hip-hcc
Simplify cmake cmd for hip-rocclr building
Some minor fixes
Change-Id: I1ae357ecfd638d6c25bca293c1724b026be21ecd
[ROCm/clr commit: 1cba7ec965 ]
2020-12-09 15:49:47 -05:00
Saleel Kudchadker
662d3c2964
Honor hipEventDisableTiming event flag
...
Change-Id: Ia949db96e81b9af467f04ab40d143e8d6faa9394
[ROCm/clr commit: 08a65054ea ]
2020-12-09 15:10:18 -05:00
Jatin Chaudhary
c5feb4d862
Updating the gcnArchName to now have target id
...
Change-Id: Ibd5576e0fb5b46e8f212de4ec57cd96eb1d3c157
[ROCm/clr commit: 24b997119f ]
2020-12-09 01:22:08 -05:00
Satyanvesh Dittakavi
78101c1e6b
Modify atomicAdd float to use clang builtin
...
SWDEV-261229: Change atomicAdd float implementation to use clang builtin
along with deprecating atomicAddNoRet
Change-Id: I5e98034fec54ee1a2b85d5f56273e34945d49ea3
[ROCm/clr commit: 542d3219dc ]
2020-12-03 23:59:10 -05:00
Satyanvesh Dittakavi
37f121bda2
Fix hipLaunchCooperativeKernel failure on nvidia platform
...
SWDEV-262064 - compilation fails when hipLaunchCooperativeKernel C++ routine is invoked
on nvcc path.
Change-Id: Icde35dd1a7008b406401bb3996c06d7acfb27d8d
[ROCm/clr commit: 80cb172fef ]
2020-11-25 01:15:55 -05:00
Michael LIAO
07aeadae82
Add initalize _wassert support.
...
Change-Id: I8922867ec77c975cdb235276fffc3c6272253a11
[ROCm/clr commit: 65f3439a0d ]
2020-11-24 11:24:54 -05:00
Aryan Salmanpour
4376b55b25
Add support for hipExtStreamGetCUMask API
...
Change-Id: I0fa67ad581dd75556f17c7410af2c1d5cb6ae99a
[ROCm/clr commit: 00268eaeed ]
2020-11-20 13:41:38 -05:00
Vladislav Sytchenko
07f463ab3f
Report maxTexture1DLinear property
...
Change-Id: If562bbee80d8b98712806cb8258b5a7482d33bf6
[ROCm/clr commit: 63167e4b70 ]
2020-11-20 10:18:20 -05:00
Julia Jiang
79807462cb
SWDEV-249486-re-organize doxygen HIP API
...
Change-Id: I3d107de526e428ae16c6dffd97d9388bf54a6358
[ROCm/clr commit: eacb30afcd ]
2020-11-11 13:31:56 -05:00