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

365 Коммитов

Автор SHA1 Сообщение Дата
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
Payam 7e9ece1a25 updated hipcc to include HSA path for clang builds as well
Change-Id: Icaaa68fdbe79fb16e4e9fedd420460f1479d7fe0


[ROCm/hip commit: b95968187b]
2020-02-13 16:48:24 -05:00
mhbliao 63ccc49116 [hip] Cleanup compiler wrapper for HIP-Clang. (#1847)
[ROCm/hip commit: a01b262660]
2020-02-07 13:28:26 -08:00
Michael LIAO b851e564f4 [hipcc] Skip warning on gfx000.
- The known target checking should skip `gfx000` as well as it won't be
  used in real compilation command formation. The avoid generating
  annoying warning on `gfx000`.


[ROCm/hip commit: 66678b0170]
2020-02-06 17:09:14 -05:00
Siu Chi Chan b93eb89b37 Enable code object v3 codgen when compiling with HCC (#1836)
Change-Id: I590c05a418cc37ec247b89124cef17a7fe8b27e2

[ROCm/hip commit: 93e62401c7]
2020-02-05 20:56:33 +05:30
kpyzhov 17ea5021ed hipcc script: Refined device selection; added gfx1011 target. (#1821)
[ROCm/hip commit: af118b98d2]
2020-02-04 08:56:16 +05:30
paulfreddy e47b0a4152 Changes for multiple ROCm installation (#1771)
* FBA-29, FBA-69, multiple rocm support, shared library conflicts
Changes to resolve:
1) Multiple rocm release installation support
2) Multiple rocm shared lib conflicts
3) Add the so versioning also

[ROCm/hip commit: 3bc69394d0]
2020-01-21 14:17:35 +05:30
Evgeny Mankov c688151a89 [HIPIFY] Sync with hipSPARSE
+ Update hipify-perl and doc accordingly


[ROCm/hip commit: d7f8654487]
2020-01-13 18:34:10 +03:00
Rahul Garg 86dbb13897 Fix hipcc warning related to hipVersion (#1767)
* Fix hipcc warning related to hipVersion
* Rename hipVersion.h to hip_version.h
* Remove HIP_VERSION splitting
* Update .gitignore
- Ignore generated include/hip/hip_version.h
- Removed some stale entries
- Added executables from samples/1_Utils/*/ for consistency with bin/ entries.

[ROCm/hip commit: f3cafd5855]
2020-01-06 12:33:23 +05:30
Evgeny Mankov 6ac4d18753 Merge pull request #1759 from emankov/master
[HIP] Unify hipError_t (Step 2)

[ROCm/hip commit: 0dadb23327]
2019-12-30 19:21:09 +03:00
Sarbojit2019 6d2ec032fe Change to generate hipVersion.h (#1726)
HIP_VERSION_MAJOR, HIP_VERSION_MINOR, HIP_VERSION_PATCH and HIP_VERSION pre-processor macros are now defined in hipVersion.h instead of being set by hipcc.

[ROCm/hip commit: aa4aea0754]
2019-12-30 12:44:24 +05:30
Evgeny Mankov 30ae3942dc [HIP] Unify hipError_t (Step 2)
Step 2. Make a few hipError codes deprecated
Update hipify-clang, hipify-perl, docs and samples accordingly


[ROCm/hip commit: dbad4d9b7f]
2019-12-22 02:05:31 +03:00
Maneesh Gupta 78dc660cb6 bump version to 3.1 (#1756)
* Bump version to 3.1

* [ci] Enable tests on ROCm 3.0


[ROCm/hip commit: 18c1003469]
2019-12-20 12:10:25 -08:00
Evgeny Mankov baf7e660a2 [HIPIFY] Revise HIP runtime
+ hipMemAllocHost is deprecated, use hipHostMalloc instead
+ hipMemAllocManaged -> hipMallocManaged
+ hipFreeHost -> hipHostFree
+ cudaMemset3D(Async) -> hipMemset3D(Async)
+ update docs and hipify-perl accordingly


[ROCm/hip commit: 3b00057922]
2019-12-16 20:09:55 +03:00
Evgeny Mankov 9827755cb5 [HIPIFY][BLAS] Sync with cuBlas/rocblas/hipBlas
[ROCm/hip commit: 396a8a7a00]
2019-12-12 19:52:18 +03:00
Evgeny Mankov 970724661d [HIPIFY] CUDA 10.2 (functions only)
+ Both Driver API and RT API are supported and synced with each other
+ Update *.md docs and hipify-perl accordingly
+ Add new conversion type "virtual_memory", introduced in Dirver API


[ROCm/hip commit: ec9b6a95a3]
2019-12-04 18:37:31 +03:00
Evgeny Mankov c9d68c898f [HIPIFY] CUDA 10.2 fp_16 support
[ROCm/hip commit: e3c3c6d86e]
2019-12-04 13:27:46 +03:00
Evgeny Mankov 6a6aa3226d [HIPIFY] CUDA 10.2 support (data types only)
+ Both Driver API and RT API are supported and synced with each other
+ Update *.md docs and hipify-perl accordingly


[ROCm/hip commit: 5a03e8ccb9]
2019-12-04 12:25:20 +03:00
Evgeny Mankov 389263471e [HIPIFY] Sync cudaError/CUresult between CUDA Driver API/CUDA RT API/HIP
+ Update *.md docs and hipify-perl accordingly

[Reason]
Starting with CUDA 10.1 all error codes are merged between Driver and RT APIs

[ToDo]
Do the same merge in HIP API as there is no need in distinguishing return codes by API


[ROCm/hip commit: d33dd71ed3]
2019-11-29 19:29:11 +03:00
Maneesh Gupta 8723218421 Bump version to 3.0 (#1648)
Change-Id: Id1e6eb222080a339af938212e74a52c39c305eab

[ROCm/hip commit: dae8630592]
2019-11-10 20:23:58 -08:00
Evgeny Mankov 07cca5b6bb [HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well
[ROCm/hip commit: c48fdefee8]
2019-11-01 14:34:18 +03:00
Evgeny Mankov 933568681c [HIPIFY] cudaMemcpy2DFromArray(Async) support
[ROCm/hip commit: 315a10a59d]
2019-10-29 19:12:42 +03:00
Evgeny Mankov 9822351686 [HIPIFY][#1569] Fix
[ROCm/hip commit: 6f88c81a78]
2019-10-22 11:08:37 +03:00
Evgeny Mankov f697f14117 [HIPIFY][perl] Support of 'using namespace cub'
[ROCm/hip commit: b08f29a6fa]
2019-10-21 17:15:05 +03:00
Rahul Garg 80ee1cc5a5 Merge pull request #1550 from yxsamliu/new-launch
Add -fhip-new-launch-api to hipcc for HIP/VDI

[ROCm/hip commit: 1fd16d7601]
2019-10-17 19:07:32 -07:00
Rahul Garg d3a40b7b2e Revert "hipcc defaults to code object v3 (#1298)"
This reverts commit 7dbc574a4b.


[ROCm/hip commit: 5f37f3174a]
2019-10-17 13:27:28 -04:00
kpyzhov cba73a44ef [hipcc] Temporary add -D_OPENMP to clang options to workaround cmake issue (#1540)
* Temporary add -D_OPENMP to clang options in hipcc to allow using CMake OpenMP detection with hip-clang (until updated CMake version is available).

[ROCm/hip commit: 596bf4e326]
2019-10-16 10:51:28 +05:30
Yaxun (Sam) Liu 73763f8748 Add -fhip-new-launch-api to hipcc for HIP/VDI
[ROCm/hip commit: 4d5cb8351c]
2019-10-15 21:47:33 -04:00
Evgeny Mankov 3deccebb07 [HIPIFY][CUB] Initial support (hipify-clang only)
+ Add one matcher (will be more)
+ Update Maps and Statistics
+ Add cub_01.cu unit test
+ Update lit harness to support standalone CUB
+ Update README.md
+ Update hipify-perl (only CUB header is supported for now)

[IMPORTANT]
clang (and hipify-clang) works correctly only with official NVLabs version on GitHub.
Compilation of CUB from official CUDA release has conflicts with THRUST.
Thus, to compile CUB sources, option "-I" should be specified to the cloned CUB from NVLAB on GitHub.


[ROCm/hip commit: 277d3b8369]
2019-10-14 11:55:55 +03:00
Evgeny Mankov 20be535ea7 [HIPIFY][perl] Add "important" notice
# IMPORTANT: Do not change this file manually: it is generated by hipify-clang --perl


[ROCm/hip commit: 876af8f381]
2019-10-10 18:25:26 +03:00
srinivamd fe7c030148 remove dependencies on /opt/rocm path (#1379)
* remove hard coded dependencies on /opt/rocm path

[ROCm/hip commit: 908e14d176]
2019-10-10 19:56:55 +05:30
Evgeny Mankov 69ea727e92 [HIPIFY][#1487][fix] Translate correctly kernel names prefixed with namespace
+ Modify CUDA2HIP_perl for the fix
+ Add ns_kernel_launch.cu test
+ Update hipify-perl by hipify-clang -perl


[ROCm/hip commit: 3286ffdfc0]
2019-10-08 15:58:48 +03:00
Evgeny Mankov a05383fc4c [HIPIFY] Sync with HIP
+ Update hipify-perl accordingly


[ROCm/hip commit: 6aa7540be8]
2019-10-07 14:44:05 +03:00
Evgeny Mankov ffee68f4f9 [HIPIFY][SPARSE] sync with hipSPARSE
+ Update doc and hipify-perl accordingly


[ROCm/hip commit: 410f6c4a95]
2019-10-05 15:53:04 +03:00
ansurya 66e94b1b1f Added new Memory API's (#1399)
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.


[ROCm/hip commit: ba9c6e13e4]
2019-10-04 13:36:31 +05:30
Maneesh Gupta 7dbc574a4b hipcc defaults to code object v3 (#1298)
Change-Id: I272ec61090fa504d631fb54371a73dd6fd17a167

[ROCm/hip commit: d39a2a0749]
2019-10-04 13:35:21 +05:30
Evgeny Mankov de6c26040d [HIPIFY] Finishing with generation of hipify-perl
+ hipify-perl script is entirely generated by hipify-clang under an option -perl now
+ hipify-perl still has correctness gaps comparing to hipify-clang: they will be eliminated AMAP further


[ROCm/hip commit: 6badebd963]
2019-10-03 16:00:52 +03:00
Evgeny Mankov eab4a41336 [HIPIFY] Return to wrapping with HIP_KERNEL_NAME(...) macro of a template instantiation kernel launch
[REASON]

1. hip-clang is fine with the templated kernel launch, brackets are unneeded: HIP_KERNEL_NAME(...) __VA_ARGS__
2. HCC is not, thus: HIP_KERNEL_NAME(...) (__VA_ARGS__)

[TODO] Clean-up entirely kernel name wrapping when HCC is finally obsolete.

+ Update perl generation, hipify-perl, and affected tests accordingly.


[ROCm/hip commit: 6bb9913e8a]
2019-10-02 16:01:07 +03:00
Evgeny Mankov 8e6ab7a6c0 Merge pull request #1492 from emankov/master
[HIPIFY][#1490][fix] Populate the list of supported device atomic functions

[ROCm/hip commit: 108992428d]
2019-10-01 14:00:07 +03:00
Evgeny Mankov 3652d77965 [HIPIFY][#1490][fix] Populate the list of supported device atomic functions
+ Update hipify-perl accordingly
+ Add atomics.cu test on all atomics


[ROCm/hip commit: b5f17e8ff0]
2019-10-01 13:57:46 +03:00
Evgeny Mankov 8bfbcc8c51 Merge pull request #1489 from emankov/master
[HIPIFY][perl] Generate transformKernelLaunch

[ROCm/hip commit: 32f2e7b999]
2019-10-01 11:18:41 +03:00
Evgeny Mankov 34e20b8568 [HIPIFY][perl] Generate transformKernelLaunch
+ Update hipify-perl accordingly
+ Minor refactoring


[ROCm/hip commit: c8f73ea491]
2019-10-01 11:17:27 +03:00
Maneesh Gupta 52f126b557 Bump version to 2.10 (#1483)
Change-Id: I22ac0ae723bc537e027306dbb0f1594552fd33a4

[ROCm/hip commit: 96cf31547e]
2019-10-01 12:39:08 +05:30
Evgeny Mankov f738c592c7 [HIPIFY][perl] Generate transformExternShared function
+ Update hipify-perl accordingly


[ROCm/hip commit: 65964db02c]
2019-09-30 17:47:46 +03:00
Evgeny Mankov 14102880b4 [HIPIFY][perl] Generate simpleSubstitutions function
+ Update hipify-perl accordingly


[ROCm/hip commit: 0f19300383]
2019-09-30 16:53:19 +03:00
Evgeny Mankov 042d68e5fb [HIPIFY] Reconcile transformation (statistics) types between hipify-clang and hipify-perl
+ Update hipify-perl accordingly


[ROCm/hip commit: 76a439f4c0]
2019-09-29 17:33:37 +03:00
Evgeny Mankov 8f68e9e035 [HIPIFY][perl] Code clean-up before continuing generation
[ROCm/hip commit: 0c9b661d56]
2019-09-28 20:44:15 +03:00
Evgeny Mankov d265ecac09 [HIPIFY] Generate more hipify-perl (continuation)
+ Minor hipify-perl clean-up
+ Minor CUDA2HIP_Perl refactoring


[ROCm/hip commit: f21e7d8abc]
2019-09-27 19:10:54 +03:00
Evgeny Mankov 3aa9f6bd6e [HIPIFY] Add supported fp16 functions
+ Update hipify-perl accordingly


[ROCm/hip commit: f50852e3a6]
2019-09-26 18:13:20 +03:00
Evgeny Mankov ca15d193e8 [HIPIFY][#1439] Add reinterpret_cast to args of some functions
+ Perl part of [#1458]
+ Affected functions: hipFuncSetCacheConfig, hipFuncGetAttributes
+ Implement function generateHostFunctions() in hipify-clang for that purposes
+ Update hipify-perl accordingly


[ROCm/hip commit: 9d1d4b78e3]
2019-09-25 18:53:17 +03:00