Commit Graph

653 Commits

Author SHA1 Message Date
Maneesh Gupta b272e57c33 Merge pull request #410 from gargrahul/hipCtx_deprecation_warning
Mark hipCtx APIs as deprecated

[ROCm/hip commit: caa13f98ed]
2018-05-01 12:23:22 +05:30
Maneesh Gupta 93fc0a8312 Merge pull request #406 from gargrahul/fix_tex1D_coordinate_type
Resolve tex1D float to int conversion issue

[ROCm/hip commit: 365d155774]
2018-05-01 09:18:11 +05:30
Rahul Garg c4df5688c4 Moved deprecated macro to the end
[ROCm/hip commit: 19cb6c61ab]
2018-04-20 21:57:23 +05:30
Rahul Garg 3b4875ba77 Mark hipCtx APIs as deprecated
[ROCm/hip commit: a039dbf2dd]
2018-04-20 17:34:48 +05:30
Rahul Garg 80d7e34418 Resolve tex1D float to int conversion issue
[ROCm/hip commit: ffe18d1505]
2018-04-18 14:15:18 +05:30
Rahul Garg e1e88f3bff Added hipMemset2DAsync support
[ROCm/hip commit: 3cfb9c0d40]
2018-04-17 18:27:27 +05:30
Maneesh Gupta 29c54aa96a Merge pull request #395 from lmoriche/master
Add missing __device__ function attributes.

[ROCm/hip commit: bda18af06d]
2018-04-12 14:51:32 +05:30
Laurent Morichetti 3d9e3019d0 Add missing __device__ function attributes.
[ROCm/hip commit: 211c18e674]
2018-04-11 09:29:37 -07:00
Maneesh Gupta 9d80544e28 Merge pull request #388 from lmoriche/master
Add support for clang offload bundles and <<<>>> kernel launch.

[ROCm/hip commit: ac7c5dfd0b]
2018-04-09 12:40:28 +05:30
Siu Chi Chan 83343a2bba adjust the hcc work week for the texture fix
[ROCm/hip commit: f48e471dd4]
2018-04-06 15:46:55 -04:00
Laurent Morichetti de2f2a87ff Don't include __clang_cuda_builtin_vars.h
[ROCm/hip commit: bc6fa2bc62]
2018-04-05 16:27:05 -07:00
Laurent Morichetti 9e1d2064c9 Add support for clang offload bundles and <<<>>> kernel launch.
[ROCm/hip commit: 0c1893ea62]
2018-04-04 13:32:33 -07:00
Rahul Garg e5e0efe002 Fix texture driver api TRFS flags
[ROCm/hip commit: 62fc6c85e0]
2018-04-02 21:47:20 +05:30
Siu Chi Chan 3f0fa73342 Change constant address space to 4
when compiling with a newer hcc.  This is
due to a recent change to address space
mapping in the amdgpu compiler backend.


[ROCm/hip commit: 0d8b97274a]
2018-03-26 18:13:59 -04:00
Laurent Morichetti e2fc87d3c6 Merge remote-tracking branch 'upstream/master'
[ROCm/hip commit: a5e04c9706]
2018-03-21 11:17:52 -07:00
Laurent Morichetti 2208bf6cbc Add HIP_KERNEL_NAME/HIP_SYMBOL definitions for HIP-clang, and rename hipLaunch->hipLaunchByPtr.
[ROCm/hip commit: a06b21c500]
2018-03-21 11:07:21 -07:00
Maneesh Gupta 4f42ee762d Apply .clangformat to all repo source files
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344


[ROCm/hip commit: 1ba06f63c4]
2018-03-12 11:29:03 +05:30
Maneesh Gupta 52506ef382 Merge pull request #363 from gargrahul/surface_object_api
Added surface object support

[ROCm/hip commit: 18e70b1e6b]
2018-03-09 11:50:30 +05:30
Maneesh Gupta d08f7dccbd Merge pull request #288 from AlexVlx/feature_purge_genco
Purge hsagenco.sh

[ROCm/hip commit: 1e13ebd992]
2018-03-05 09:59:56 +05:30
Rahul Garg 413c9ac9cb Fixed byte offset issue
Added HIP/NVCC support


[ROCm/hip commit: d697739d57]
2018-03-04 19:05:37 +05:30
Laurent Morichetti f18bee421c __CUDA__ and __HIP__ are both defined when compiling with 'clang -x hip', so make sure __HIP__ is not defined in the case of __HIP_PLATFORM_NVCC__.
[ROCm/hip commit: 0d45c1d2d3]
2018-03-02 06:51:51 -08:00
Laurent Morichetti 12e8f48181 Use __HIP__ instead of __HIPCC__, and __CUDA__ instead of __CUDACC__
[ROCm/hip commit: 6536164914]
2018-02-28 14:20:55 -08:00
Laurent Morichetti b32680706c Fixes a build error with hcc
[ROCm/hip commit: 2bc7adfa62]
2018-02-28 14:12:09 -08:00
Laurent Morichetti 69f5dc0883 Add initial support for clang
[ROCm/hip commit: f8b0c96462]
2018-02-28 12:31:26 -08:00
Rahul Garg ff74aadd87 Added surface object support
[ROCm/hip commit: 5c3b91a0a1]
2018-02-26 11:59:03 +05:30
Alex Voicu 64fc905d32 Missing merge.
[ROCm/hip commit: 9526e05732]
2018-02-12 20:21:37 +00:00
Alex Voicu 3afca75a71 Re-sync with upstream.
[ROCm/hip commit: baf50a5311]
2018-02-12 20:20:24 +00:00
Maneesh Gupta d4a4a8a1c1 Merge pull request #321 from gargrahul/hipMemcpyArray_Functions
Added support for hipMemcpy Array functions-

[ROCm/hip commit: 4b8ae78891]
2018-02-12 10:36:38 +05:30
Rahul Garg e2ade308cf Fixed host allocated globals address lookup for host usage
Fixed texture driver APIs failure


[ROCm/hip commit: 24ab820a11]
2018-01-30 18:06:31 +05:30
Maneesh Gupta 254f8aeed1 Merge branch 'master' into feature_purge_genco
[ROCm/hip commit: 72d3e679e4]
2018-01-29 16:02:03 +05:30
Maneesh Gupta e98b8a56ba Merge pull request #346 from scchan/fix_rhel_build
use assign rather than insert

[ROCm/hip commit: 44de3f8309]
2018-01-26 06:59:25 +05:30
Siu Chi Chan 6e53c6d37a use assign rather than insert
[ROCm/hip commit: 8acc8365fa]
2018-01-25 16:51:29 +00:00
Kent Knox cc15f73add Fixing rocblas build failure
with ::Bundled_code_header constructor

Disabling hipPrintfKernel test from CI


[ROCm/hip commit: 0497424978]
2018-01-25 10:29:40 -06:00
Alex Voicu abb22cc7f2 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_purge_genco
[ROCm/hip commit: ed75522ba5]
2018-01-17 14:02:19 +00:00
Rahul Garg 5da7dcbd3b Added support for -
- hipMemcpyFromArray
- hipMemcpyAtoH
- hipMemcpyHtoA


[ROCm/hip commit: 487a430b5a]
2018-01-16 11:44:19 +05:30
Maneesh Gupta a90f8a7fb2 Merge pull request #282 from gargrahul/texture_driver_3d_support
Added support for 3D texture driver apis

[ROCm/hip commit: 814d55f046]
2017-12-18 15:39:26 +05:30
Alex Voicu 044ae14b92 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_purge_genco
[ROCm/hip commit: e14ac87474]
2017-12-14 13:50:49 +00:00
Maneesh Gupta 4b2066d4dc Merge pull request #286 from gargrahul/fix_hipDeviceGetAttribute_nvcc
Fix hipGetDeviceAttribute dtest for HIP/NVCC

[ROCm/hip commit: 6cb5e92d75]
2017-12-12 12:49:23 +05:30
Maneesh Gupta 39f2afa9e3 Merge pull request #285 from aaronenyeshi/fix-ilogb-unreachable
Fix ilogb/ilogbf functions to return int

[ROCm/hip commit: 6293d3f887]
2017-12-12 10:47:33 +05:30
Alex Voicu 56fd7f129a This introduces LipoProteinLipase (lpl), a simple tool for creating fat binaries. It represents a direct replacement of the creaky hccgenco.sh script, which had various issues. The format it uses is that of a code object bundle, generated by the Clang Offload Bundler. The output is always suffixed with the ".adipose" extension. It is shared with HCC. The hipcc script and associated tests are modified to use lpl. Help can be obtained by invoking lpl --help. A more computer-sciency / corporate friendly name is likely to be beneficial, which is a reason for choosing easily searchable/replaceable names such as lpl or adipose.
[ROCm/hip commit: b842394957]
2017-12-08 04:22:57 +00:00
Rahul Garg 89d9f8ae1c Fix hipGetDeviceAttribute dtest for HIP/NVCC
[ROCm/hip commit: 0782c52271]
2017-12-06 15:49:06 +05:30
Aaron En Ye Shi 58c6892f4b Fix ilogb/ilogbf functions to return int
This patch will fix hipDoublePrecisionMathDevice test on ThinLTO, which uncovered that hip math_function's ilogb/ilogbf should return type int instead of double. This will match rocdl.


[ROCm/hip commit: 707aaef99d]
2017-12-05 23:14:10 +00:00
Rahul Garg 299c873e1a Added support for
- 3D texture driver APIs
- hipMalloc3D
- hipMemcpy3D for destination other than array


[ROCm/hip commit: 115c7f2b79]
2017-12-05 14:11:13 +05:30
Alex Voicu abe3c22cf1 This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
[ROCm/hip commit: 5127ce67e8]
2017-12-03 23:09:06 +00:00
Alex Voicu 08a0d96448 Fix legacy mode detection of the address of an agent allocated variable. In this mode, there exist two executables per each code object, one created by HCC and one created by HIP. Since we dispatch through HCC in legacy mode, we should obtain the address for an agent allocated variable from the latter's executable. Also add two omitted validity checks, whose absence could lead to segfaults when the current process had no .kernel section and / or when an invalid or empty blob was extracted from the latter.
[ROCm/hip commit: 7c0b9a005b]
2017-11-30 03:29:04 +00:00
Alex Voicu b70bcb5f60 Add missing space (the final frontier).
[ROCm/hip commit: 20fc68c9a1]
2017-11-29 21:50:43 +00:00
Alex Voicu 8d51eaafb6 Revert "Revert adoption of CUDA indexing in general - this can only work with later versions of the compiler, just like module based dispatch, and thus must be guarded against usage in earlier (e.g. 1.6) versions."
This reverts commit 1c50968


[ROCm/hip commit: 32e11e7dc6]
2017-11-29 21:49:10 +00:00
Alex Voicu cd61d38118 Use a much simpler guard for version 1.6, which allows for direct CUDA indexing to be used.
[ROCm/hip commit: 7acb1e6ff6]
2017-11-29 21:47:04 +00:00
Alex Voicu 1c50968051 Revert adoption of CUDA indexing in general - this can only work with later versions of the compiler, just like module based dispatch, and thus must be guarded against usage in earlier (e.g. 1.6) versions.
[ROCm/hip commit: d2fd1f5544]
2017-11-29 21:01:28 +00:00
Alex Voicu c58a083e96 Fix compiler version check.
[ROCm/hip commit: b881cf713c]
2017-11-29 03:05:53 +00:00