Граф коммитов

5018 Коммитов

Автор SHA1 Сообщение Дата
Vladislav Sytchenko 0c7735ad28 Merge "Enable simpleTexture3D test for VDI" into amd-master-next
[ROCm/clr commit: 7da159bac2]
2020-03-17 11:41:05 -04:00
Sameer Sahasrabuddhe f12c0f1dbb SWDEV-204784: separate printf declaration for vdi/clang
There are now two implementations of printf in HIP:

1. The implemenation for HCC is controlled by the HC_FEATURE_PRINTF
   macro, and it works only with the HCC compiler used in combination
   with the HCC runtime.

2. The implementation for hip-clang requires the VDI runtime, and is
   always enabled with that combination.

Change-Id: Ibaeda7900ffe2ce602ca0094aafed0f1147ac2b6


[ROCm/clr commit: d48738856c]
2020-03-16 04:00:39 -04:00
Vladislav Sytchenko 303e04fa55 Enable simpleTexture3D test for VDI
Change-Id: Ida65de6e1cae64ac97b624eaab1340877a6fba73


[ROCm/clr commit: dafed1a009]
2020-03-13 18:34:39 -04:00
Saleel Kudchadker 80c688d9f5 Merge "Fix P4 linux make builds" into amd-master-next
[ROCm/clr commit: 7d86f10c3c]
2020-03-11 16:17:18 -04:00
Jiabao Xie 9bfc5ba7a9 Merge "Structs expanded to print struct information than address. Moved to hip_formatting.hpp. Reformatted to follow Google standards" into amd-master-next
[ROCm/clr commit: 214c07a5b8]
2020-03-10 15:56:49 -04:00
Yaxun Liu 4042bf151b Merge "Let hipcc not pass -mllvm option to HIP-Clang on Windows" into amd-master-next
[ROCm/clr commit: 3fbd8e0dc2]
2020-03-10 14:12:06 -04:00
Vladislav Sytchenko 98761c5721 Fix typo in device __shfl_xor function
Change-Id: I8bcdd53ced00c596a0af013a0c34e37aa67c93ae


[ROCm/clr commit: caea3f9b32]
2020-03-10 13:23:08 -04:00
Jiabao Xie 3f843860d0 Structs expanded to print struct information than address. Moved to hip_formatting.hpp. Reformatted to follow Google standards
Change-Id: I08695058c11db51b9f3cbe1deb4af944ebf9e64d


[ROCm/clr commit: 10d90ab2ad]
2020-03-10 13:12:28 -04:00
Yaxun (Sam) Liu 23a8dfc8f3 Let hipcc not pass -mllvm option to HIP-Clang on Windows
Currently there is a clang bug on Windows causing duplicate -mllvm options in clang -cc1.

Tempoarily disable -mllvm options for HIP-Clang on Windows until the bug is fixed.

Change-Id: I3a4393ba7745989398dc6c6001722837dad18704


[ROCm/clr commit: e796a1ed78]
2020-03-10 13:07:26 -04:00
Saleel Kudchadker 049340f08e Fix P4 linux make builds
Change-Id: I6cc4e69a914389b53bc3b52535eb6faf24897a09


[ROCm/clr commit: 7bba326ed1]
2020-03-10 00:02:10 -07:00
Saleel Kudchadker 82a836eb22 Merge "Change HIPRTC Version to 9.0" into amd-master-next
[ROCm/clr commit: 8d05d06dce]
2020-03-09 22:55:27 -04:00
Vladislav Sytchenko 426e3ecb06 Merge "Add hipDrvMemcpy3D." into amd-master-next
[ROCm/clr commit: 305e4eedcf]
2020-03-09 18:13:16 -04:00
Julia Jiang cf35a2a1de Merge "SWDEV-225337-Fix test failure in hipNormalizedFloatValueTex kernel" into amd-master-next
[ROCm/clr commit: 9b436779e4]
2020-03-09 16:58:10 -04:00
Vladislav Sytchenko 952502e2ed Add hipDrvMemcpy3D.
This is the equivalent of cuMemcpy3D.

Change-Id: Ib2e06dbd6f5093c931cdfd36c87617f32acffc2d


[ROCm/clr commit: cd76eb7486]
2020-03-09 16:11:25 -04:00
jujiang 0279f1d89e SWDEV-225337-Fix test failure in hipNormalizedFloatValueTex kernel
Change-Id: I3a4c3b58578703993640a8d28242ec1a0ed5ff60


[ROCm/clr commit: 09d442d7c3]
2020-03-09 15:21:29 -04:00
Sameer Sahasrabuddhe 7973b6d45d enable hostcall tests
Change-Id: Ic6efe71c868defc53be214acd7e0907109ec1410


[ROCm/clr commit: 5fc32755b7]
2020-03-09 14:41:37 -04:00
Saleel Kudchadker 1834fb4c5e Change HIPRTC Version to 9.0
Change-Id: I7e88df61248f0fe6e33c2315805f9e49a493cf29


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


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

Change-Id: If0ed1f7ec194bf7f65b7cea1a5c250e768a8f190


[ROCm/clr commit: a15e895cfd]
2020-03-09 11:46:55 -04:00
Saleel Kudchadker cba02a6305 Merge "Merge branch 'master' into amd-master-next" into amd-master-next
[ROCm/clr commit: af88b3f18f]
2020-03-06 16:29:16 -05:00
Vladislav Sytchenko 468ede4cc1 Add hipMemcpy3DParams -> HIP_MEMCPY3D conversion
Change-Id: I66dd1ae722b8c0d7ddb2562c958b14854e6b86bc


[ROCm/clr commit: 59fb85f94d]
2020-03-06 14:33:52 -05:00
Vladislav Sytchenko d65e730457 Fix dangling pointer after hipUnbindTexture() call
Change-Id: Ic4b476c62ebfae31e94dd139b20b6aaaa52bb866


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

Change-Id: I4aa4754d391b5f37ddf15fa0bcfc84d9da020119


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

Change-Id: Ica8ae6f644edfaa0d4803d0b8e90e320479118e2


[ROCm/clr commit: e746584d24]
2020-03-06 14:06:21 -05:00
Tao Sang 8eb086a967 Merge "Fix hipExtLaunchMultiKernelMultiDevice compilation issue" into amd-master-next
[ROCm/clr commit: 1216153c66]
2020-03-06 12:32:55 -05:00
Evgeny Mankov 0d9efef77b Merge pull request #1914 from emankov/hipify-clang
[HIPIFY][doc] Update README.md: LLVM 10.0.0-rc3 is supported

[ROCm/clr commit: cf61ad2830]
2020-03-06 18:20:36 +03:00
Evgeny Mankov 47e249093d [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/clr commit: 278eff4c96]
2020-03-06 18:17:05 +03:00
jujiang 3296a1c526 SWDEV-225338-simpletexture3D failed-Fix bug in test app
Change-Id: I106d1951368e0c7a8ccd6aa462c22f81e8332cdc


[ROCm/clr commit: 75c90a4bf1]
2020-03-05 16:50:27 -05:00
Vladislav Sytchenko 53ab95f3f8 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/clr commit: 801c70279f]
2020-03-05 15:03:18 -05:00
Vladislav Sytchenko a4b38979b6 Fix typos in ihipMemcpy3D()
Change-Id: I8720f113642f00bb013cf46284e9b13cc932bf4a


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


[ROCm/clr commit: f360ff6479]
2020-03-05 16:08:51 +05:30
German Andryeyev 28fb4e50bb Merge "SWDEV-193956 - [hipclang-vdi-rocm][perf]" into amd-master-next
[ROCm/clr commit: a083dc8547]
2020-03-04 18:04:52 -05:00
Michael LIAO 6ea8286d14 Fix -Werror=switch.
Change-Id: Ib0850a3f79308efeeecd18bb03ecd82bd355ef85


[ROCm/clr commit: d2d0225c2e]
2020-03-04 17:52:39 -05:00
agodavar 1c828b7575 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/clr commit: 5a6c605730]
2020-03-04 15:38:14 -05:00
Payam 64638a230f reverting part of http://gerrit-git.amd.com/c/compute/ec/hip/+/326145
the test still fails

Change-Id: I2e5968115a717e8482be670d9fb8472e391922d7


[ROCm/clr commit: a52975bc03]
2020-03-04 13:49:58 -05:00
agodavar ac317d0029 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/clr commit: ae465bc338]
2020-03-04 10:07:09 -05:00
Evgeny Mankov fbf9b7429d Merge pull request #1905 from emankov/hipify-clang
[HIP][cmake] Remove dependency from hipify-clang

[ROCm/clr commit: 3be5375bde]
2020-03-04 07:42:48 +03:00
Saleel Kudchadker c69a3ecd25 Merge "Add -Wno-ignored-attributes flag to mute warnings" into amd-master-next
[ROCm/clr commit: f4caaeb308]
2020-03-03 20:39:16 -05:00
Vladislav Sytchenko 30d22b1ea8 Fix Windows build.
Calm down warning C4715: not all control paths return a value.

Change-Id: I99d939b84770a499bb6a0edcc3bc0bf12961a711


[ROCm/clr commit: 14810044f7]
2020-03-03 16:14:12 -05:00
Vladislav Sytchenko 7d51c87f76 SWDEV-219799
Add missing __hip_pinned_shadow__ attribute to the hipModuleTexture2dDrv test.

Change-Id: I2c213a4108611c1af691388f268cac429b81a313


[ROCm/clr commit: 818a65ff66]
2020-03-03 11:49:00 -05:00
Evgeny Mankov 464af0b28e [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/clr commit: ff7165a73c]
2020-03-03 12:07:13 +03:00
German Andryeyev 597bf599ad 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/clr commit: b93d997fb7]
2020-03-02 18:35:56 -05:00
Vladislav Sytchenko 9347d89f8d 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/clr commit: d28b77bf23]
2020-03-01 13:52:05 -05:00
Payam 8b814bf404 updating hip debug target for VDI
Change-Id: Ia08af89e2ee461e75e888e495984d3b1d9a6a858


[ROCm/clr commit: 93aa3ca565]
2020-02-28 18:13:50 -05:00
Payam 51df58c2d2 updated hip-targets for VDI
Change-Id: I268f1dbf04e3439ca1f3dd1cfbbc2f40667c00f9


[ROCm/clr commit: 727219eb0a]
2020-02-28 18:02:02 -05:00
Jatin Chaudhary ee8cee7d35 [dtests] __shfl_up and __shfl_down tests (#1899)
[ROCm/clr commit: dacc90f415]
2020-02-28 16:48:15 +05:30
Siu Chi Chan e1b10796da improve code object loading error message (#1889)
[ROCm/clr commit: eebba4799c]
2020-02-28 16:47:40 +05:30
saleelk 21712e6fb8 Fix HIPRTC headers to export C style symbols (#1879)
[ROCm/clr commit: 40a28e767e]
2020-02-28 16:47:29 +05:30
Rahul Garg 7395bf9ba9 Remove deprecated HIP markers (#1876)
[ROCm/clr commit: 6be7537cf9]
2020-02-28 16:47:15 +05:30
Rahul Garg ff421fb2d2 Add hipDrvOccupancyMaxActiveBlocksPerMultiprocessor[WithFlags] (#1854)
Equivalent to cuOccupancyMaxActiveBlocksPerMultiprocessor[WithFlags].

[ROCm/clr commit: 1c794045e0]
2020-02-28 16:46:55 +05:30