Commit Graph

429 Commits

Author SHA1 Message Date
Evgeny Mankov 65dd13c677 [HIPIFY][doc] Update Readme.md: versioning 2019-12-20 20:55:19 +03:00
Evgeny Mankov 08f1c8edf3 Merge pull request #1739 from emankov/hipify-clang
[HIP] Unify hipError_t (Step 1)
2019-12-19 07:57:02 +03:00
Evgeny Mankov 1108ef06e1 [HIPIFY] Revise HIP runtime
+ hipMemAllocHost is deprecated, use hipHostMalloc instead
+ hipMemAllocManaged -> hipMallocManaged
+ hipFreeHost -> hipHostFree
+ cudaMemset3D(Async) -> hipMemset3D(Async)
+ update docs and hipify-perl accordingly
2019-12-16 20:09:55 +03:00
Evgeny Mankov 21b0f64f3a [HIP] Unify hipError_t (Step 1)
Step 1. Set the same values for RT error codes as for analogous Driver's

[Reason] RT's and Driver's error codes unification in CUDA 10.2
2019-12-13 19:40:16 +03:00
Evgeny Mankov 1377db639f [HIPIFY][build] Fix building with LLVM trunk 2019-12-13 15:42:27 +03:00
Evgeny Mankov c7bea1f865 [HIPIFY][BLAS] Sync with cuBlas/rocblas/hipBlas 2019-12-12 19:52:18 +03:00
Evgeny Mankov 486ec185e7 [HIPIFY] Add cleanupHipifyOptions functionality
Needed for sorting input files to avoid clang errors on unsupported options
2019-12-08 15:13:28 +03:00
Evgeny Mankov 72b1d16115 [HIPIFY] main source file refactoring 2019-12-07 13:50:13 +03:00
Evgeny Mankov ef405daaee [HIPIFY][fix][#1246][#1655] Sort input files based on their dependency graph
+ Implemented by using clang Driver infrastructure

[ToDo] Add tests for in-place hipification of multiple files
2019-12-07 11:20:17 +03:00
Evgeny Mankov 43441eb99c [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
2019-12-04 18:37:31 +03:00
Evgeny Mankov 721a8540c0 [HIPIFY] CUDA 10.2 fp_16 support 2019-12-04 13:27:46 +03:00
Evgeny Mankov 33f81effb1 [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
2019-12-04 12:25:20 +03:00
Evgeny Mankov 636108aaa9 [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
2019-11-29 19:29:11 +03:00
Shyam Saladi 562336e733 [HIPIFY] fix typo (#1681) 2019-11-22 07:54:37 +05:30
Evgeny Mankov bb6f1648ec [HIPIFY][doc] A few words about LLVM's FileCheck in README.md 2019-11-12 16:04:28 +03:00
Evgeny Mankov 7f143585f6 [HIPIFY] Clang style formatting 2019-11-07 12:48:05 +03:00
Evgeny Mankov 4d2424ad36 [HIPIFY][fix] Delete canCompileHostAndDeviceInOneJob declaration as well 2019-11-07 11:32:53 +03:00
Evgeny Mankov 21c3d25403 [HIPIFY][fix] Abandon canCompileHostAndDeviceInOneJob check for --cuda-compile-host-device option
[Reason] It turned out that it is not so: 2 jobs are always
2019-11-07 11:30:40 +03:00
Evgeny Mankov f18e63b8a9 [HIPIFY] Reorder options propagation to clang
[Reason] Leave overriding opportunity for -D, -std=c++XX, etc.
2019-11-07 11:21:06 +03:00
Evgeny Mankov 97a0670d29 [HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10 2019-11-06 19:25:42 +03:00
Evgeny Mankov 3f737625ee [HIPIFY][doc] Update README.md
+ Supported versions, testing
2019-11-06 19:18:13 +03:00
Evgeny Mankov 4cad5fab78 [HIPIFY][format] Apply clang style formatting in LLVMCompat 2019-11-06 14:43:22 +03:00
Evgeny Mankov 3dcae8760d [HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7 2019-11-06 14:30:39 +03:00
Evgeny Mankov cf5d1caab3 Merge pull request #1624 from emankov/hipify
[HIPIFY][#1409] Fix for kernel launch macro expansion
2019-11-05 14:04:51 +03:00
Evgeny Mankov a1c380f38d [HIPIFY][#1409] Fix for kernel launch macro expansion
+ Add a corresponding test kernel_launch_01.cu
+ Add isBefore() check to avoid crash on Replacement with negative length

TODO:
+ Compatibility with former LLVM versions
+ More complicated kernel launch tests
2019-11-05 14:00:13 +03:00
Evgeny Mankov 7142b884ab [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
+ Pass it to clang if specified
2019-11-02 14:19:31 +03:00
Evgeny Mankov c5a2a2daf2 [HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well 2019-11-01 14:34:18 +03:00
Evgeny Mankov e79fd55d01 [HIPIFY][cmake][#1572] Fix: Do not override CMAKE_INSTALL_PREFIX
Affects building with HIP, standalone building is not changed
2019-10-31 16:55:06 +03:00
Evgeny Mankov 050fdad7b7 [HIPIFY][#1603] Fix 2019-10-29 22:10:36 +03:00
Evgeny Mankov dd2243f2fa [HIPIFY][Linux] Rollback --cuda-compile-host-device on Linux
[Reason] It doesn't work with LLVM 9 and higher; Windows is fine
2019-10-29 20:53:54 +03:00
Evgeny Mankov 411b18a124 [HIPIFY] Introduce --cuda-compile-host-device for LLVM >= 9
* LLVM < 9 continues using --cuda-host-only
2019-10-29 19:42:53 +03:00
Evgeny Mankov 5dd00bdf52 [HIPIFY] cudaMemcpy2DFromArray(Async) support 2019-10-29 19:12:42 +03:00
Evgeny Mankov 2435567e70 [HIPIFY][cmake][#1571] Take into account building hipify-clang as a part of building HIP while installing
[Algorithm]
  [Release]
    If CMAKE_INSTALL_PREFIX is set by the user:
       If BIN_INSTALL_DIR is set by HIP, use it as CMAKE_INSTALL_PREFIX, otherwise CMAKE_INSTALL_PREFIX is used unchanged.
    If the user does not set CMAKE_INSTALL_PREFIX (CMAKE_INSTALL_PREFIX_INITIALIZED_TO_DEFAULT):
       If BIN_INSTALL_DIR is set by HIP, use it as CMAKE_INSTALL_PREFIX, otherwise use PROJECT_BINARY_DIR/bin for installation.
  [Debug]
    If CMAKE_INSTALL_PREFIX is set by the user:
       CMAKE_INSTALL_PREFIX is used unchanged.
    If the user does not set CMAKE_INSTALL_PREFIX (CMAKE_INSTALL_PREFIX_INITIALIZED_TO_DEFAULT):
       use CMAKE_CURRENT_SOURCE_DIR/bin for installation.

Standalone build left unchanged: CMAKE_INSTALL_PREFIX is used if set.
2019-10-23 18:54:45 +03:00
Evgeny Mankov 7ab06b3892 [HIPIFY] Disable delayed template parsing
By implicit unconditional passing -fno-delayed-template-parsing option (which appeared in LLVM 3.8.0, thus doesn't need compatibility wrapping) to hipify-clang.

[Reason] To parse uncalled template functions otherwise they are not parsed without calling, thus not hipified.

Affects cub_03.cu test, which has uncalled global template function.
2019-10-22 19:07:37 +03:00
Evgeny Mankov e2191e23e6 [HIPIFY][#1569] Fix 2019-10-22 11:08:37 +03:00
Evgeny Mankov 9633cdbd8a [HIPIFY][perl] Support of 'using namespace cub' 2019-10-21 17:15:05 +03:00
Evgeny Mankov 86f6756b02 [HIPIFY][CUB][#1460] Add "using namespace cub" translation support
+ Add cub_03.cu
2019-10-18 18:51:40 +03:00
Aaron Enye Shi b3ea58abe7 [HIPIFY][cmake] Make CMakeLists use default 3.5.1 for Ubuntu 16.04 2019-10-17 21:21:24 +00:00
Evgeny Mankov 1165e6bd71 [HIPIFY][doc] Update README.md
+ Versions, testing
2019-10-17 22:26:48 +03:00
Evgeny Mankov 8c3dff7ab9 [HIPIFY][cmake] Add install rule for clang-resource-headers
+ Fix: set destination for all installing files to ${CMAKE_INSTALL_PREFIX}
2019-10-17 15:05:55 +03:00
Evgeny Mankov e557563947 [HIPIFY][CUB][#1460] Add cub:: namespace support in TemplateInstantiation of cudaLaunchKernel
+ Update cub_02.cu test accordingly
2019-10-16 19:02:13 +03:00
Evgeny Mankov 0a20048759 [HIPIFY] Refactor a couple of matcher functions
+ Separate out GetSubstrLocation function for finding substr SourceLocation in a given SourceRange
2019-10-16 13:43:56 +03:00
Evgeny Mankov 5555d46e66 [HIPIFY][CUB][#1460] Implement cubFunctionTemplateDecl matcher
+ Add cub_02.cu test
+ Partial fixes #1460
2019-10-16 13:08:11 +03:00
Evgeny Mankov 5dae577d67 [HIPIFY][cmake] Make CMakeLists.txt compatible with default cmake 3.5.2 for Ubuntu 16.04
+ Update README.md accordingly
2019-10-15 11:26:03 +03:00
Evgeny Mankov 0025c24fe9 [HIPIFY] HipifyAction code clean-up 2019-10-14 18:08:29 +03:00
Evgeny Mankov 01ae988fab [HIPIFY][build fix] Add missing new source file 2019-10-14 16:32:57 +03:00
Evgeny Mankov 97df38903a [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.
2019-10-14 11:55:55 +03:00
Evgeny Mankov 0ee069bad7 [HIPIFY][perl] Add "important" notice
# IMPORTANT: Do not change this file manually: it is generated by hipify-clang --perl
2019-10-10 18:25:26 +03:00
Evgeny Mankov 7c3f5a387d Merge pull request #1513 from emankov/hipify-clang
[HIPIFY][doc] Add a few words about hipify-perl
2019-10-08 22:30:25 +03:00
Evgeny Mankov eaffbb10b8 [HIPIFY][doc] Add a few words about hipify-perl
+ Update testing and versions
2019-10-08 22:27:48 +03:00