Grafik Komit

4303 Melakukan

Penulis SHA1 Pesan Tanggal
Saleel Kudchadker 2b4b2b2dc9 Merge "Change HIPRTC Version to 9.0" into amd-master-next
[ROCm/hip commit: bcd23335fb]
2020-03-09 22:55:27 -04:00
Vladislav Sytchenko 3082077cc9 Merge "Add hipDrvMemcpy3D." into amd-master-next
[ROCm/hip commit: 7fe7edd77d]
2020-03-09 18:13:16 -04:00
Julia Jiang a4255f8089 Merge "SWDEV-225337-Fix test failure in hipNormalizedFloatValueTex kernel" into amd-master-next
[ROCm/hip commit: 1fa3bf5123]
2020-03-09 16:58:10 -04:00
Vladislav Sytchenko 88ae7337b3 Add hipDrvMemcpy3D.
This is the equivalent of cuMemcpy3D.

Change-Id: Ib2e06dbd6f5093c931cdfd36c87617f32acffc2d


[ROCm/hip commit: ecd7c99b49]
2020-03-09 16:11:25 -04:00
jujiang d745491b17 SWDEV-225337-Fix test failure in hipNormalizedFloatValueTex kernel
Change-Id: I3a4c3b58578703993640a8d28242ec1a0ed5ff60


[ROCm/hip commit: 47cc94b1b4]
2020-03-09 15:21:29 -04:00
Sameer Sahasrabuddhe dd7cad9ed4 enable hostcall tests
Change-Id: Ic6efe71c868defc53be214acd7e0907109ec1410


[ROCm/hip commit: c7d7640d87]
2020-03-09 14:41:37 -04:00
Saleel Kudchadker 0585e40955 Change HIPRTC Version to 9.0
Change-Id: I7e88df61248f0fe6e33c2315805f9e49a493cf29


[ROCm/hip commit: c540a55d21]
2020-03-09 11:28:55 -07:00
Saleel Kudchadker 043b44934a Fix HIPRTC headers to export C style symbols
Change-Id: I3e0d2b19ace4a9096e3e46bd22f420483da51a8a


[ROCm/hip commit: 08c6d941ca]
2020-03-09 14:18:46 -04:00
Vladislav Sytchenko 7affd35b9b Fix Windows build.
extern "C" on Windows implies nothrow. We shouldn't be throwing exceptions either way.

Change-Id: If0ed1f7ec194bf7f65b7cea1a5c250e768a8f190


[ROCm/hip commit: 38004b6ef0]
2020-03-09 11:46:55 -04:00
Saleel Kudchadker cfcf0d025a Merge "Merge branch 'master' into amd-master-next" into amd-master-next
[ROCm/hip commit: a30f9ab2db]
2020-03-06 16:29:16 -05:00
Vladislav Sytchenko 2f8a37880d Add hipMemcpy3DParams -> HIP_MEMCPY3D conversion
Change-Id: I66dd1ae722b8c0d7ddb2562c958b14854e6b86bc


[ROCm/hip commit: 2e9d177304]
2020-03-06 14:33:52 -05:00
Vladislav Sytchenko 42d9576cbe Fix dangling pointer after hipUnbindTexture() call
Change-Id: Ic4b476c62ebfae31e94dd139b20b6aaaa52bb866


[ROCm/hip commit: dbb8f96a8e]
2020-03-06 14:10:56 -05:00
Lad, Aditya 044a1924ba Merge branch 'master' into amd-master-next
Conflicts:
	CMakeLists.txt
	tests/src/texture/simpleTexture2DLayered.cpp
	tests/src/texture/simpleTexture3D.cpp

Change-Id: I4aa4754d391b5f37ddf15fa0bcfc84d9da020119


[ROCm/hip commit: d80edf9541]
2020-03-06 14:10:44 -05:00
Vladislav Sytchenko 8bf13d8d20 Add missing coversion cases.
Handle converting signed int cases of hipResourceViewFormat to number of channels.

Change-Id: Ica8ae6f644edfaa0d4803d0b8e90e320479118e2


[ROCm/hip commit: 90feaf046f]
2020-03-06 14:06:21 -05:00
Tao Sang 9862e33448 Merge "Fix hipExtLaunchMultiKernelMultiDevice compilation issue" into amd-master-next
[ROCm/hip commit: 4b312caca4]
2020-03-06 12:32:55 -05:00
Evgeny Mankov c48bf1b4b0 [HIPIFY][doc] Update README.md: LLVM 10.0.0-rc3 is supported
+ Add -DLLVM_TEMPORARILY_ALLOW_OLD_TOOLCHAIN=ON for LLVM 10.0.0 or newer
+ Supported versions update


[ROCm/hip commit: dd5f3fd282]
2020-03-06 18:17:05 +03:00
jujiang 127e56e482 SWDEV-225338-simpletexture3D failed-Fix bug in test app
Change-Id: I106d1951368e0c7a8ccd6aa462c22f81e8332cdc


[ROCm/hip commit: c5aa54cbd2]
2020-03-05 16:50:27 -05:00
Vladislav Sytchenko 9a62b2ffe7 Correct logic in ihipMemcpyAtoA()
HIP assumes that image width is in bytes, but VDI assumes that image width in pixels. Need to perform byte -> pixel coversion before doing anything.

Change-Id: Ia9fd1f46d05db3fbe8049add10b4d7e5118a2b9a


[ROCm/hip commit: 3fc50731ae]
2020-03-05 15:03:18 -05:00
Vladislav Sytchenko 2f2a2843dc Fix typos in ihipMemcpy3D()
Change-Id: I8720f113642f00bb013cf46284e9b13cc932bf4a


[ROCm/hip commit: f28e2ebb42]
2020-03-05 14:11:55 -05:00
agodavar de0b92948e Enable tests that are passing on hip-vdi
Change-Id: I7de965f7e8bb7e4d0fa61cd584f0cd118c1e212e


[ROCm/hip commit: 65ffaf82d8]
2020-03-05 16:08:51 +05:30
German Andryeyev c503c44b67 Merge "SWDEV-193956 - [hipclang-vdi-rocm][perf]" into amd-master-next
[ROCm/hip commit: 33da3f5c50]
2020-03-04 18:04:52 -05:00
Michael LIAO 2f7869ae2c Fix -Werror=switch.
Change-Id: Ib0850a3f79308efeeecd18bb03ecd82bd355ef85


[ROCm/hip commit: f70a66a7b3]
2020-03-04 17:52:39 -05:00
agodavar 76ee85ff82 Fix hipExtLaunchMultiKernelMultiDevice compilation issue
Fix compilation error on hip-hcc+clang , hip-vdi+clang
Enabled hipExtLaunchMultiKernelMultiDevice test on hip-vdi path
hipExtLaunchMultiKernelMultiDevice common declaration for all paths

Change-Id: I76031840614fce8e12a8e845548fa43a389a741a


[ROCm/hip commit: 6a5d04209c]
2020-03-04 15:38:14 -05:00
Payam 5d57dba9bd reverting part of http://gerrit-git.amd.com/c/compute/ec/hip/+/326145
the test still fails

Change-Id: I2e5968115a717e8482be670d9fb8472e391922d7


[ROCm/hip commit: 3d64a38953]
2020-03-04 13:49:58 -05:00
agodavar 428d4842ae Enable tests hipTestDeviceSymbol,hipTestConstant and p2p_copy_coherency on hip-vdi
SWDEV-225266: [HIP-VDI] HIP-VDI disabled tests (p2p_copy_coherency.cpp)
SWDEV-225388: hipTestDeviceSymbol.cpp & hipTestConstant.cpp failed to build on hip-vdi

For hipTestDeviceSymbol.cpp & hipTestConstant.cpp tests:
Currently "__HIP_VDI__" flag is enabled in CMakeLists.txt, but when application is compiled with hipcc,  
__HIP_VDI__ is not defined to differentiate if compiled for VDI/HCC for headers.

For ./src/runtimeApi/memory/p2p_copy_coherency.cpp:
Fixed compilation issue to include only when compile for HCC runtime "<hc_am.hpp> not found"
Currently test is disabled to run on all platforms. When validated on multi-GPU machine,
memcpy between multiple GPUs via GPU synchronization is not working on hcc and vdi path.
Need to validate on nvidia machine to know if test is valid. Disabled GPU synchronization test for now.

For ./src/runtimeApi/module/hipModuleTexture2dDrv.cpp:
updated test to generate tex2d_kernel.code object in build directory. Currently ctest looks for it in build directory.

Change-Id: I629d395a919c2440d921422716944c7940ed6010


[ROCm/hip commit: 3479847d16]
2020-03-04 10:07:09 -05:00
Saleel Kudchadker 60e9a26fe0 Merge "Add -Wno-ignored-attributes flag to mute warnings" into amd-master-next
[ROCm/hip commit: d97e32d837]
2020-03-03 20:39:16 -05:00
Vladislav Sytchenko 01db2848c4 Fix Windows build.
Calm down warning C4715: not all control paths return a value.

Change-Id: I99d939b84770a499bb6a0edcc3bc0bf12961a711


[ROCm/hip commit: 25f107e2b6]
2020-03-03 16:14:12 -05:00
Vladislav Sytchenko d0db9f5cdf SWDEV-219799
Add missing __hip_pinned_shadow__ attribute to the hipModuleTexture2dDrv test.

Change-Id: I2c213a4108611c1af691388f268cac429b81a313


[ROCm/hip commit: b910a7ff26]
2020-03-03 11:49:00 -05:00
Evgeny Mankov 82710c788a [HIP][cmake] Remove dependency from hipify-clang
[Reason] Upcoming hipify-clang's splitting out into a new repository https://github.com/ROCm-Developer-Tools/HIPIFY.


[ROCm/hip commit: 1561f61642]
2020-03-03 12:07:13 +03:00
German Andryeyev 5af52cba15 SWDEV-193956 - [hipclang-vdi-rocm][perf]
~45% to 50% of Performance drop on rocBLAS_int8 test

Enable cudaSetDeviceFlags() api call. Use active wait by default
for all devices.

Change-Id: Ifc2ebe3dd9b0aa3fdbfbc9cb5c2cd8b3b726124f


[ROCm/hip commit: fe1fad4805]
2020-03-02 18:35:56 -05:00
Vladislav Sytchenko 05c26e5aa7 Fix hipMemcpy3d (partially)
Incoming changes from upstream split the struct hipMemcpy3DParms into two separate ones - hipMemcpy3DParms and HIP_MEMCPY3D, which are cudaMemcpy3DParms and CUDA_MEMCPY3D equivalents respectively.

Note that HIP_MEMCPY3D is missing half the members of CUDA_MEMCPY3D (this should be fixed in PR#1887). Work around this by using a substitute _HIP_MEMCPY3D struct for now.

Change-Id: Ic15134e6deb260189b662b3804d2309a9b8473e9


[ROCm/hip commit: 87178f9456]
2020-03-01 13:52:05 -05:00
Payam e28e857f52 updating hip debug target for VDI
Change-Id: Ia08af89e2ee461e75e888e495984d3b1d9a6a858


[ROCm/hip commit: 5b14ab34f5]
2020-02-28 18:13:50 -05:00
Payam ca490bfe31 updated hip-targets for VDI
Change-Id: I268f1dbf04e3439ca1f3dd1cfbbc2f40667c00f9


[ROCm/hip commit: e638f9afba]
2020-02-28 18:02:02 -05:00
Jatin Chaudhary 1ed7948498 [dtests] __shfl_up and __shfl_down tests (#1899)
[ROCm/hip commit: d29ad50464]
2020-02-28 16:48:15 +05:30
Siu Chi Chan 7a908a9a70 improve code object loading error message (#1889)
[ROCm/hip commit: 57edf48191]
2020-02-28 16:47:40 +05:30
saleelk 3c66b171e1 Fix HIPRTC headers to export C style symbols (#1879)
[ROCm/hip commit: 3e1f41c165]
2020-02-28 16:47:29 +05:30
Rahul Garg c34c9a4b4d Remove deprecated HIP markers (#1876)
[ROCm/hip commit: 6c5fa32815]
2020-02-28 16:47:15 +05:30
Rahul Garg 5229ffff99 Add hipDrvOccupancyMaxActiveBlocksPerMultiprocessor[WithFlags] (#1854)
Equivalent to cuOccupancyMaxActiveBlocksPerMultiprocessor[WithFlags].

[ROCm/hip commit: edc97f3073]
2020-02-28 16:46:55 +05:30
jiabaxie 39fd208ed2 Cleaned up error messages for HipEnvVarDriver test (#1825)
There were several error messages that appeared even if the hipEnvVarDriver.exe test passes and executes successfully. Now it is cleaned up. The following are those instances:

* When popen searches for directed_test directory but does not find it, it outputs an error, then finds the hipEnvVar at the same level. Currently the fix will prompt the test to only output an error if both searches for hipEnvVar fails.
* When assertion is used towards the later half of the test, conditions were set to specifically hide the devices, resulting in No Hip Device detected in the latter half of the test. The fix will make these errors not appear as they are intended to not find any devices. Assertions themselves are untouched.

HipEnvVarDriver.cpp has also been refactored. Reading HipEnvVar will now happen in a helper function for getDeviceNumber and getDevicePCIBusNumRemote, as the code to read HipEnvVar were really similar in them.


[ROCm/hip commit: af90312867]
2020-02-28 16:46:12 +05:30
Saleel Kudchadker 299f117a58 Add -Wno-ignored-attributes flag to mute warnings
Change-Id: Ib9ad75554c0ddfe025e7d500f057830f7ad2ef5b


[ROCm/hip commit: 6f2a872d87]
2020-02-27 10:52:13 -08:00
Alex Voicu a5ad7bc67b Address post-staging issues in #1809 (#1894)
Fixes SWDEV-223910 and SWDEV-223663

[ROCm/hip commit: d830dad3be]
2020-02-27 16:21:12 +05:30
Maneesh Gupta b499822842 bump version to 3.2 (#1898)
- Bump version to 3.2
- [ci] Enable tests on ROCm 3.1

[ROCm/hip commit: 71e1f87f7e]
2020-02-27 16:18:31 +05:30
Christophe Paquot e673e8e0c9 Blocking and default streams' sync:
Add hip::syncStreams(dev) to sync blocking streams on a given device.
hip::syncStreams(void) should only sync streams on the current device.

Change-Id: Ib6b0735215fa0ed12c646ebd029e9763ee3712ce


[ROCm/hip commit: fa6ed89cff]
2020-02-26 08:54:00 -08:00
Nick Curtis 2715d1b036 fix long shuffle implementations for windows (#1895)
Fixes for SWDEV-223694

[ROCm/hip commit: b7dd073d93]
2020-02-26 15:53:56 +05:30
Yaxun (Sam) Liu 3067349909 Fix hipcc for extra -mllvm option (#1885)
[ROCm/hip commit: 69404d8e78]
2020-02-26 15:53:43 +05:30
Payam fa31a1c60d removing 3 tests temporarily to enable hiptests
Change-Id: I8c45791aaf88628850462aff90979c147cb85f64


[ROCm/hip commit: f4401ff2b5]
2020-02-25 19:01:34 -05:00
Payam Ghafari bf2b4f988a Merge "removed excutable permission from source files" into amd-master-next
[ROCm/hip commit: c9b64aa2da]
2020-02-25 17:44:43 -05:00
Vladislav Sytchenko 3d0b66151a Merge "Bump c++ version to 14." into amd-master-next
[ROCm/hip commit: a093814015]
2020-02-25 17:00:27 -05:00
Vladislav Sytchenko 87aa945477 Merge "hipBindTexture() should handle nullptr offset." into amd-master-next
[ROCm/hip commit: 13903baaa5]
2020-02-25 17:00:18 -05:00
Payam 6b7eecb037 removed excutable permission from source files
Change-Id: Iae8639a96c55a098e28de41c5a3f38a07acbe25c


[ROCm/hip commit: 224d41c2f0]
2020-02-25 16:16:47 -05:00