Commit Graph

1354 Commits

Author SHA1 Message Date
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
German Andryeyev bc9b26a59f Update documentation
Add managed memory section for the doxygen documentation.
No code changes.

Change-Id: I2e9db4ec13422159e265193916f0a3cdb721732d


[ROCm/hip commit: 2bf7282bd5]
2020-10-23 18:28:43 -04:00