kjayapra-amd
f3af2709b4
SWDEV-274276 - Implement system scope atomics to _system builtins. Default atomics will map to agent.
...
Change-Id: I63b13063274418e96d4be0159c779127b166bea5
(cherry picked from commit 7c4ae8ca1daac0b75ac36c4e4a45b8d13f219d14)
[ROCm/hip commit: dfaf6140cf ]
2021-04-09 10:23:32 -04:00
Sarbojit Sarkar
225d149818
SWDEV-260454 - Fix for idenfying bad streams
...
Change-Id: I122ff6f47535c3c76ab56ba49ab1450ef886b15f
[ROCm/hip commit: 492ccc3281 ]
2021-04-07 12:13:30 -04:00
Sarbojit Sarkar
47c83726a4
SWDEV-280131 - Fix __half2 member access bug
...
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783
[ROCm/hip commit: 83a25eb5b5 ]
2021-04-07 12:12:02 -04:00
pghafari
5242decbc0
SWDEV-245532 - HIP - Vulkan interop
...
Change-Id: Iba1ef8112e318b4f099da5a4a4602e0dae7de9e3
[ROCm/hip commit: a1b321bba4 ]
2021-03-31 10:23:31 -04:00
Sarbojit Sarkar
04849fca63
SWDEV-277926 - Updated deprecated APIs in Cuda
...
Change-Id: I9ff655af227b245067eb760325c395bb562696ee
[ROCm/hip commit: d4f347747b ]
2021-03-29 01:19:19 -04:00
Satyanvesh Dittakavi
70445b1f7e
SWDEV-277152 - Add hipMemcpy2DToArrayAsync API in headers
...
Also, address few scenarios for hipMemcpy2DToArray/Async to return
proper error types
Change-Id: Idbadf666a5e7bebc0f3ea8b7048b79208e04cf6b
[ROCm/hip commit: 39f4d0d244 ]
2021-03-27 13:50:38 -04:00
jujiang
59acce2b79
SWDEV-277423 - Correct hipStreamWaitValue doxygen format
...
Change-Id: I8914c14cb7a05d5d0bdfa054af14765c872c70a6
[ROCm/hip commit: d279bd99bb ]
2021-03-19 14:10:41 -04:00
Tao Sang
f962ea4cc1
SWDEV-273138 - Update canUseStreamWaitValue retrieving
...
Remove canUseStreamWaitValue from hipDeviceProp_t.
Update canUseStreamWaitValue retrieving in hipDeviceGetAttribute().
Change-Id: I275bd42d8b03e141caaf9f1bc6b714e51ca72dfb
[ROCm/hip commit: ca0cc36ef4 ]
2021-03-18 22:42:35 -04:00
cjatin
3ecbc923db
SWDEV-272811 - Using OCML functions for conversion of fp to int
...
Change-Id: Id0c02bf6a2e0553d522035b078a9db4cd3fad215
[ROCm/hip commit: 2afa40873a ]
2021-03-18 11:43:30 -04:00
Ravi C Akkenapally
276d9ce2cb
SWDEV-276827 - Stream Operations: match API with CUDA
...
Change-Id: Ia79a950561e97df3b2229f76f5512dede2babf98
[ROCm/hip commit: 475d928be8 ]
2021-03-18 07:52:29 -07:00
Tao Sang
15519dd555
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/hip commit: 38b0c952a6 ]
2021-03-16 17:12:08 -04:00
jujiang
f9b7d37bea
SWDEV-270961 - Add doxygen for Texture APIs
...
Change-Id: I4038320a638292440d9ca8c23ffcabffcd9a48c2
[ROCm/hip commit: 3498f3600a ]
2021-03-09 16:23:56 -05:00
Satyanvesh Dittakavi
d988defe00
SWDEV-275317 - Fix hipMemcpy2DFromArray to return proper error types
...
Change-Id: Id722865d81460bfd2fa6ad7a198b6e3c2a08265a
[ROCm/hip commit: 0303084b0e ]
2021-03-09 05:22:23 -05:00
Satyanvesh Dittakavi
8b8e7636cd
SWDEV-274404 - Add hipDrvMemcpy3D* and hipMemcpy2DFromArray* APIs on HIP CUDA
...
Change-Id: I4aba2bff60a7bae6b01b6e471968227b0df8e192
[ROCm/hip commit: fba442fe36 ]
2021-03-08 13:14:25 -05:00
Arya.Rafii
335decd182
SWDEV-269246 - Implementation of hipDrvMemcpy2DUnaligned
...
Change-Id: I86fdd3b930cbd74c45cd31944f0ea52c0ff65a59
[ROCm/hip commit: 24837c1afc ]
2021-03-04 14:38:06 -05:00
Arya.Rafii
20c981abd3
SWDEV-269246 - Added missing exports for hipArrayDestroy
...
Change-Id: I730814720bb618e895efbe2f412e437110bed8bc
[ROCm/hip commit: 6f1a09b47f ]
2021-03-04 14:29:16 -05:00
Ravi C Akkenapally
3d9b4cc2c2
SWDEV-179105 - Stream Operations: Add swqupport for Wait and Write
...
Change-Id: I9d6d0665d12b62fe705ce1569a0e8264a4f23ab7
[ROCm/hip commit: e89b228eac ]
2021-03-02 12:15:46 -08:00
Vladislav Sytchenko
a523f75554
SWDEV-232428 - Enable device printf for Windows
...
Change-Id: Id72cfc34cfcfcbcb459bd8d84979637eaf7947dd
[ROCm/hip commit: 084d25010b ]
2021-02-26 11:46:38 -05:00
Satyanvesh Dittakavi
08828176e7
SWDEV-271491 - Fix flags for hipSetDeviceFlags on HIP-CUDA path
...
Change-Id: I29446d5cc5a26a4b83fa45175ccdf1d8f3a9ea40
[ROCm/hip commit: d134c05699 ]
2021-02-25 12:06:33 -05:00
Jatin Chaudhary
31983c00f5
SWDEV-272811 - hipCabs returns a double and uses sqrtf, which maps to f32 operation. sqrt should be used instead
...
Change-Id: I4f74ee8853113fcebfa508bea9308ae93c7ad13b
[ROCm/hip commit: 4d0383df0c ]
2021-02-25 08:47:19 -05:00
Jatin Chaudhary
4f4340f4af
SWDEV-268531 - Fixing shadow variable warning in vector_types
...
Change-Id: Ic57e22853529a953582c9194d09133a5aab989aa
[ROCm/hip commit: 22164ebc3f ]
2021-02-16 06:51:37 -05:00
Maneesh Gupta
e1802c292c
SWDEV-271416 - Keep HIP_DYNAMIC_SHARED macro for compat with existing HIP apps
...
Change-Id: I536e0c65d6e8696cbc369082350834abd710abca
[ROCm/hip commit: debceab2a8 ]
2021-02-16 00:09:48 -05:00
Maneesh Gupta
800652cef7
SWDEV-269351 - Revert "Implement assert() using the new fprintf_stderr facility"
...
This reverts commit f0a9c129a0 .
Reverting since this is dependent on a device libs change which is not yet in mainline.
Change-Id: I094781b868f39995d1eecb41488c1a1a0147b787
[ROCm/hip commit: 7998429c21 ]
2021-02-12 03:46:17 -05:00
cjatin
cb46badf20
SWDEV-268531 - Fixing shadow varible warning seen with hip vector usage
...
Change-Id: I9e20a41e74e473b328cc173f2c27b06352128c88
[ROCm/hip commit: a12163b4e5 ]
2021-02-09 13:33:12 -05:00
Julia Jiang
ef396373ec
SWDEV-271416 - Remove HIP_DYNAMIC_SHARED macro in hip
...
Change-Id: I12f39ea8438eb7ce76d8ffb2151b4faa93689048
[ROCm/hip commit: 090b2829b9 ]
2021-02-08 13:17:46 -05:00
Sarbojit Sarkar
3fa56865cc
SWDEV-265469 - added constexpr constructor for dim3
...
Change-Id: I2e23a403f272d1ff0ade24fec11190d2f3244e5f
[ROCm/hip commit: 09b1eb8c9f ]
2021-01-28 13:23:51 -05:00
Satyanvesh Dittakavi
89fec911e8
SWDEV-269784 - managed memory support for HIP CUDA
...
Change-Id: I01f9fc64573f402031eceab24395e5cbd93007f9
[ROCm/hip commit: 25cccbb60d ]
2021-01-28 07:51:52 -05:00
Tao Sang
8679ca98aa
SWDEV-268757 - Disable deprecation warning
...
Disable it as it will fail rocgdb test
Change-Id: Ibf34c780d5bd4278adcedba1d6e057639c258483
[ROCm/hip commit: 30820b131e ]
2021-01-21 15:35:32 -05:00
Satyanvesh Dittakavi
8a803a1592
SWDEV-268989 - Modify atomicAdd double to use clang builtin
...
Change-Id: If9d40046df2f3f5af7cc1bd6c935fbe7d686e7d8
[ROCm/hip commit: ecdbaf73cf ]
2021-01-20 02:39:15 -05:00
Sameer Sahasrabuddhe
f0a9c129a0
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/hip commit: 96be8a7b73 ]
2021-01-17 23:54:46 -05:00
Satyanvesh Dittakavi
5c60465932
device property __HIP_ARCH_HAS_SHARED_INT64_ATOMICS__ set to 1 as it has compiler support
...
Change-Id: Ic91c4955d4f2d52d844471f81e6f0d19418018f5
[ROCm/hip commit: aaa15a7455 ]
2021-01-15 11:40:09 -05:00
Tao Sang
118c6ba23e
Fix building mathlibs failure
...
Add back
__HIP_PLATFORM_HCC__
__HIP_PLATFORM_NVCC__
Change-Id: I1ae48678eafd849d6c25bcb204c1724b026be22f
[ROCm/hip commit: 59ef7dc9e2 ]
2021-01-14 14:03:15 -05:00
Tao Sang
2d1dc3949d
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/hip commit: ef8110da22 ]
2021-01-12 11:31:06 -05:00
Michael LIAO
ab8ad19eda
Remove checking on double.
...
- All conversions among floating point types should be allowed.
Change-Id: I6223bece51f5b2a535ab3369c5c4380f18acc74d
[ROCm/hip commit: 094ff5431e ]
2021-01-11 11:33:33 -05:00
Sameer Sahasrabuddhe
26e35374ff
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/hip commit: 05cc647684 ]
2021-01-11 15:09:53 +05:30
Saleel Kudchadker
c9cc6fbd65
Update documentation for hipEventCreateWithFlags
...
Change-Id: I2658bd95df0d3a802cce4ffcb8dfd40e7055b0f7
[ROCm/hip commit: f24b2e075a ]
2021-01-08 16:32:57 -05:00
Rahul Garg
8c0ea0d8a3
Add IPC Events support
...
Change-Id: Iac2bf3d5e1d9a993bebbb066c20d300d6f05558b
[ROCm/hip commit: c307baf3da ]
2021-01-08 20:09:26 +00:00
Tao Sang
2820f91c90
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/hip commit: b34dd95124 ]
2021-01-08 10:53:34 -05:00
Tao Sang
c618b6aeff
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/hip commit: c2adc70d4d ]
2021-01-05 10:39:31 -05:00
jujiang
07aa78a19b
SWDEV-249486-Add doxygeny for API hipExtModuleLaunchKernel
...
Change-Id: Id7451ef4f669238a38ed92ec72008326c85afc4a
[ROCm/hip commit: 942419f217 ]
2020-12-14 15:34:32 -05:00
Tao Sang
5d94d2ee98
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/hip commit: 186f95ea30 ]
2020-12-09 15:49:47 -05:00
Saleel Kudchadker
8c78939796
Honor hipEventDisableTiming event flag
...
Change-Id: Ia949db96e81b9af467f04ab40d143e8d6faa9394
[ROCm/hip commit: 6da16e90d2 ]
2020-12-09 15:10:18 -05:00
Jatin Chaudhary
be29ce8cbb
Updating the gcnArchName to now have target id
...
Change-Id: Ibd5576e0fb5b46e8f212de4ec57cd96eb1d3c157
[ROCm/hip commit: d056171a20 ]
2020-12-09 01:22:08 -05:00
Satyanvesh Dittakavi
9eb0c2d999
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/hip commit: 019c556c7d ]
2020-12-03 23:59:10 -05:00
Satyanvesh Dittakavi
47b1005aac
Fix hipLaunchCooperativeKernel failure on nvidia platform
...
SWDEV-262064 - compilation fails when hipLaunchCooperativeKernel C++ routine is invoked
on nvcc path.
Change-Id: Icde35dd1a7008b406401bb3996c06d7acfb27d8d
[ROCm/hip commit: 44d6914ef3 ]
2020-11-25 01:15:55 -05:00
Michael LIAO
6d79e8473b
Add initalize _wassert support.
...
Change-Id: I8922867ec77c975cdb235276fffc3c6272253a11
[ROCm/hip commit: 4ac8346383 ]
2020-11-24 11:24:54 -05:00
Aryan Salmanpour
bfbf9c7929
Add support for hipExtStreamGetCUMask API
...
Change-Id: I0fa67ad581dd75556f17c7410af2c1d5cb6ae99a
[ROCm/hip commit: d9a335bccf ]
2020-11-20 13:41:38 -05:00
Vladislav Sytchenko
e0dfaf51e9
Report maxTexture1DLinear property
...
Change-Id: If562bbee80d8b98712806cb8258b5a7482d33bf6
[ROCm/hip commit: fb04bdc4f2 ]
2020-11-20 10:18:20 -05:00
Julia Jiang
24e1e855fc
SWDEV-249486-re-organize doxygen HIP API
...
Change-Id: I3d107de526e428ae16c6dffd97d9388bf54a6358
[ROCm/hip commit: 3ccce6a642 ]
2020-11-11 13:31:56 -05:00
Sourabh Betigeri
35e394cab1
SWDEV-255694: Include attributes - hipFuncAttributePreferredSharedMemoryCarveout and hipFuncAttributeMaxDynamicSharedMemorySize
...
Change-Id: I3569859e6db0c59a10a76c8ea356d4bc0a0bb906
[ROCm/hip commit: 81ca27783b ]
2020-11-02 19:39:39 -05:00