720e209366
Fix gcc build issues for host code
2018-04-25 12:30:11 +05:30
894f01c206
P4 to Git Change 1545859 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/24 16:44:17
...
SWDEV-145570 - [HIP] Get hipCtx_simple to pass
Implemented hipCtxGetDevice
hipCtxCreate must push the created context onto the context stack
hipCtxDestroy must check if the top of the stack is the context being destroy
and not just pop the top of the stack w/o checking.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#8 edit
2018-04-24 16:49:38 -04:00
56734306ed
Add host and device targets
2018-04-24 14:04:24 -05:00
bfee03f95b
[HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)
...
Execution Control [deprecated since 7.0]:
cudaConfigureCall -> hipConfigureCall
cudaLaunch -> hipLaunchByPtr
cudaSetupArgument -> hipSetupArgument
Surfaces (partially):
cudaSurfaceObject_t -> hipSurfaceObject_t
cudaSurfaceBoundaryMode -> hipSurfaceBoundaryMode
cudaCreateSurfaceObject -> hipCreateSurfaceObject
cudaDestroySurfaceObject -> hipDestroySurfaceObject
Memory Management:
cudaMemset2DAsync -> hipMemset2DAsync
2018-04-24 22:04:04 +03:00
65a90c55e7
Checkin to fix bugs in math functions.
...
This change fixes the following bugs that were discovered while debuggnig TF unit test failures (cwise_ops_test)
1. __hisinf and __hisnan routines
Both had incorrect implementations.
2. abs
A "long long" (64bit int) version was missing, resulting in the 32bit version being used for 64bit ints (which resulted in incorrect results, when the value passed in was outside the 32bit int range)
3. lgamma
We seemed to have a custom version for the 'double' datatype (which was giving incorrect results). Replaced it with a call to the 'double' version of the underlying 'hc::precision_math::lgamma'
2018-04-24 18:10:07 +00:00
5eace16718
P4 to Git Change 1545750 by skudchad@skudchad_test2_win_opencl on 2018/04/24 13:55:57
...
SWDEV-145570 - [HIP] - Add some hip_mem* APIs. Part 2.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14681/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#11 edit
2018-04-24 14:05:20 -04:00
1149f88413
Remove unsupported targets gfx801 and gfx802
...
These architectures are no longer supported. Should not compile for them.
2018-04-23 15:25:35 -04:00
14a95fc231
Merge pull request #413 from emankov/master
...
[HIPIFY] undo apply .clangformat to HIPIFY source files
2018-04-23 20:29:43 +03:00
ad28f72ca9
[HIPIFY] undo apply .clangformat to HIPIFY source files
2018-04-23 20:22:15 +03:00
db522a2fbc
P4 to Git Change 1544858 by skudchad@skudchad_rocm on 2018/04/22 21:07:25
...
SWDEV-144570 - [HIP] - Fix a few APIs and typos.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#6 edit
2018-04-22 21:17:27 -04:00
a68b9b6bf6
Added deprecation note in cuCtx section
2018-04-20 22:43:58 +05:30
bc61260168
Moved deprecated macro to the end
2018-04-20 21:57:23 +05:30
74faa61d52
SWDEV-141024
2018-04-20 17:40:00 +05:30
89674c54a7
Mark hipCtx APIs as deprecated
2018-04-20 17:34:48 +05:30
22439e8644
P4 to Git Change 1544061 by skudchad@skudchad_test2_win_opencl on 2018/04/19 18:24:45
...
SWDEV-145570 - [HIP] - Add some hip_mem* APIs
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14647/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#10 edit
2018-04-19 18:35:00 -04:00
d532cc2b66
P4 to Git Change 1543751 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/19 11:17:02
...
SWDEV-145570 - [HIP] Implemented a bunch of texture APIs
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#5 edit
2018-04-19 12:27:09 -04:00
4770abf00e
Merge pull request #404 from gargrahul/hipMemset2DAsync_support
...
Added hipMemset2DAsync support
2018-04-18 14:19:41 +05:30
a898ccfb3f
Resolve tex1D float to int conversion issue
2018-04-18 14:15:18 +05:30
fcc0866681
Added hipMemset2DAsync support
2018-04-17 18:27:27 +05:30
9226f981ab
Merge 'master' into 'amd-master'
...
Change-Id: I599b0d1176a11c635c8b16c395d15677bd431fb5
2018-04-17 04:09:48 -05:00
72ff4c5cc4
Merge pull request #400 from gargrahul/hipModule_cleanup
...
hip_module code cleanup
2018-04-17 09:00:15 +05:30
a004c8dfa2
Clean up triple_to_hsa_isa naming ( #403 )
2018-04-17 06:47:55 +05:30
17d153a162
P4 to Git Change 1541938 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/16 18:27:17
...
SWDEV-145570 - [HIP] Set/GetDevice and Create/DestroyTextureObject
Implemented Set/GetDevice relying on g_context (current context)
Implemented create linear/2D texture object function
Implemented hipDestroyTextureObject
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#4 edit
2018-04-16 18:37:17 -04:00
c23898f49b
hip_module code cleanup
...
-Fixed missing ihipLogStatus in hipModuleLoad()
-Fixed some ihipXXX functions
2018-04-16 15:35:04 +05:30
21382e361c
Fix bug when using older rocr naming ( #399 )
2018-04-14 15:47:46 +05:30
aec786cfdb
P4 to Git Change 1541197 by skudchad@skudchad_test2_win_opencl on 2018/04/13 17:49:07
...
SWDEV-145570 - [HIP] - Add missing HIP APIs and fill sym table references. The HIP tests can now build if we do a symlink to libhip_hcc.so that we build with VDI in the install folder in github HIP.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14619/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_profile.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#3 edit
2018-04-13 18:19:28 -04:00
199cff2365
Fix new gfx target naming convention ( #397 )
...
This was introduced in recent xnack changes naming changes which affected our offload bundler. This patch will fix issues in HIP samples, ROCR tests, and others.
2018-04-13 16:24:39 +05:30
36173d50bb
Merge 'master' into 'amd-master'
...
Change-Id: I68d26834a9e5e651e1be4e4219a7521f6da97415
2018-04-13 04:10:05 -05:00
2ab05a2069
Merge pull request #395 from lmoriche/master
...
Add missing __device__ function attributes.
2018-04-12 14:51:32 +05:30
de8eae68e9
Merge pull request #393 from mangupta/cmake_update_deps
...
[cmake] Update target build dependencies
2018-04-12 14:36:49 +05:30
234488eba2
Merge pull request #394 from gargrahul/hipMemset_refactoring
...
hipMemset refactoring
2018-04-12 14:01:49 +05:30
2ee80397f2
Correct missed ihipMemsetCopyDataType change
2018-04-12 10:27:19 +05:30
2658963f5b
Changed ihipMemsetCopyDataType to ihipMemsetDataType
2018-04-12 09:29:22 +05:30
8dcfbf5bee
Add missing __device__ function attributes.
2018-04-11 09:29:37 -07:00
88073a17c1
Fix hipMemset stream resolution
2018-04-11 19:01:53 +05:30
40846f6f8e
hipMemset refactoring
2018-04-11 15:58:48 +05:30
ebc52e5bc0
[cmake] Update target build dependencies
...
Change-Id: Ib1c34135c0d04f88daa695e7a90272225d7e64b0
2018-04-11 15:30:13 +05:30
c516409a4b
Merge 'master' into 'amd-master'
...
Change-Id: Icea2117281aa6f24d85bc5ceea1db8c5d737caf3
2018-04-11 04:10:08 -05:00
a39a96dcc9
Merge pull request #391 from lmoriche/master
...
Create one hipModule_t per device
2018-04-11 13:06:58 +05:30
e19802c5c9
P4 to Git Change 1539198 by skudchad@skudchad_test2_win_opencl on 2018/04/10 17:32:14
...
SWDEV-145570 - [HIP] - Add HIP API skeletons for Peer and memory
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14596/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_peer.cpp#1 add
2018-04-10 17:41:24 -04:00
f4cde23be3
Create one hipModule_t per device
2018-04-10 08:57:34 -07:00
f61ca7be5c
Merge 'master' into 'amd-master'
...
Change-Id: I2bb8d2d98bb90185d663d0dc3bad1803acd857cc
2018-04-09 04:10:14 -05:00
2d1d79cb22
Merge pull request #390 from mangupta/hipmemcpy_fix
...
hipMemcpyAsync returns success when trying to copy 0 bytes
2018-04-09 14:02:36 +05:30
d945c85fa7
Merge pull request #388 from lmoriche/master
...
Add support for clang offload bundles and <<<>>> kernel launch.
2018-04-09 12:40:28 +05:30
445de66560
hipMemcpyAsync returns success when trying to copy 0 bytes
...
Change-Id: I4c0ee7ccc7563e2df657b50356cdd7fec9a1ef15
2018-04-09 12:39:44 +05:30
04f116a9e8
[ci] Disable nvcc CI builds
2018-04-09 12:23:56 +05:30
e5b14cd918
Merge pull request #389 from scchan/adjust_texture_hcc_workweek
...
adjust the hcc work week for the texture fix
2018-04-09 10:54:16 +05:30
03a6601214
P4 to Git Change 1537729 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/06 17:59:29
...
SWDEV-145570 - [HIP] Use Svm path for both hipMalloc and hipHostMalloc
Make sure hipMemCpy uses SvmBuffer to fetch the cl_mem
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#8 edit
2018-04-06 18:08:18 -04:00
5df923cdfa
adjust the hcc work week for the texture fix
2018-04-06 15:46:55 -04:00
7f03ff1012
Don't include __clang_cuda_builtin_vars.h
2018-04-05 16:27:05 -07:00
Rahul Garg
foreman
Paul
Evgeny Mankov
Deven Desai
Aaron Enye Shi
Evgeny Mankov
Lakhan Singh
Maneesh Gupta
Jenkins
Laurent Morichetti
Siu Chi Chan