c73cd64f5b
Add HIP Compute Mode
2018-06-22 14:37:19 +00:00
0e0d43bfe1
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_native_vector_types
2018-06-22 12:19:32 +01:00
f0286b57c2
P4 to Git Change 1571566 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/22 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2679 to 2680.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2427 edit
2018-06-22 03:21:18 -04:00
dc850cc3e7
HIPCC - Use clang if clang++ is not compiled
2018-06-21 18:12:55 +00:00
c184b88692
P4 to Git Change 1571066 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/21 03:00:20
...
SWDEV-2 - Change OpenCL version number from 2678 to 2679.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2426 edit
2018-06-21 03:17:42 -04:00
5d4986d470
Replace __hip_hc_ir_ inline asm with __ockl_* functions
2018-06-20 20:40:14 +00:00
9a295a732d
Implement __ballot, __any, __all into HIP headers
2018-06-20 17:39:39 +00:00
175c87f2bf
Implement hip_hc.ll into HIP headers
...
Move all __hip_hc_ir_* functions from hip_hc.ll into HIP header as inline asm. Remove hip_hc.ll and build dependencies from HIP.
2018-06-20 17:39:31 +00:00
ad5f1dcbf2
Implement device_functions.cpp into HIP headers
...
Move all Integer Intrinsics, device_functions.cpp definitions and HIP specific device functions into HIP headers. Implement the device functions using llvm_intrinsics and device-libs functions instead of calling hc::__* functions. Remove device_functions.cpp since everything is now defined in header.
2018-06-20 17:39:23 +00:00
e8a18a5473
Move hipclang funcs into corresponding headers
2018-06-20 17:39:15 +00:00
366207f8af
Split __llvm and device lib funcs into new headers
2018-06-20 17:39:06 +00:00
0694d0300a
Add get_dynamicgroupbaseptr def and remove hc_
2018-06-20 17:38:59 +00:00
7cade79d98
Add prefix __ to memory scope and order
2018-06-20 17:38:52 +00:00
4298ed308e
Add __llvm_fence funcs and __ prefixes
2018-06-20 17:38:45 +00:00
f4399d57a3
Add hipclang amdgcn functions
...
These are moving from hipclang in device library to hip headers. These are required for the functionality of HIPclang project.
2018-06-20 17:38:37 +00:00
8b4feff6e2
Merge 'master' into 'amd-master'
...
Change-Id: Ia897c694ffbbce2ab01493d3ea60e42701ce021e
2018-06-20 04:09:40 -05:00
272c16d34e
Merge pull request #507 from ROCm-Developer-Tools/fix-forward
...
Add __device__ to device functions in hip_fp16_math_fwd.h
2018-06-20 14:21:46 +05:30
29aa297899
Merge pull request #504 from ROCm-Developer-Tools/fix-vector3
...
Fix channel_descriptor.h about vector 3 for gcc
2018-06-20 14:20:29 +05:30
d27991e1c8
Merge pull request #490 from ROCm-Developer-Tools/feature_decouple_atomics_from_hc
...
Switch the atomic implementation to use Clang builtins.
2018-06-20 14:16:43 +05:30
e7b38959a2
P4 to Git Change 1570469 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/20 03:00:04
...
SWDEV-2 - Change OpenCL version number from 2677 to 2678.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2425 edit
2018-06-20 03:11:11 -04:00
8ff33a83b1
Merge pull request #457 from whchung/hip-reinit
...
HIP program state re-initialization logic
2018-06-20 09:37:27 +05:30
64fd3e50a0
P4 to Git Change 1570202 by gandryey@gera-w8 on 2018/06/19 13:58:38
...
SWDEV-155436 - Write dispatch dimensions to COMPUTE registers for OpenCL support for RGP
- Add the dispatch dimensions to the RGP trace
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#111 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#290 edit
2018-06-19 14:06:00 -04:00
f67ed6630e
P4 to Git Change 1570186 by gandryey@gera-w8 on 2018/06/19 13:20:24
...
SWDEV-150518 - [IQE][DG2018][I+eA][SSG] System hangs when trying to preview cache video to AMD SSG
- Disable optimization for "disabled deferred allocations" in SSG path. There is an extra logic to support double copy transfers with allocations in the invisible heap. It's not an official requirement for the SSG extension and hasn't been tested, but Adobe utilizes that path.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#89 edit
2018-06-19 13:28:44 -04:00
454d45e5bb
Let hipcc handle library with extension lo for hip-clang
2018-06-19 10:51:08 -04:00
2b5242b2c3
Add conj, operator-,==,!= for hipFloatComplex/hipDoubleComplex
2018-06-19 10:49:59 -04:00
8d82c5e97b
P4 to Git Change 1570053 by jatang@jatang-opencl-hsa-stg5 on 2018/06/19 09:47:32
...
SWDEV-155306 - Restore ClockMode when the last queue is destroyed.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#110 edit
2018-06-19 09:53:09 -04:00
2ee0f5310b
Merge 'master' into 'amd-master'
...
Change-Id: I539a79195161876b0a6eae952f64af85d4c47b28
2018-06-19 04:09:57 -05:00
bdfd6957aa
added option HIP_BUILD_VERBOSE to enable verbosity in HIP build
2018-06-19 13:50:24 +05:30
956ec86f42
P4 to Git Change 1569929 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/19 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2676 to 2677.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2424 edit
2018-06-19 03:15:24 -04:00
6bdb5f3541
added changes to FindHIP.cmake which would allow us to build using ninja #467
2018-06-19 12:26:18 +05:30
cae3aeb923
Merge pull request #516 from bddppq/empty-generator-expression
...
Properly handle (empty) cmake generator expression
2018-06-19 09:38:21 +05:30
a24f1d7353
Merge pull request #520 from ntrost57/master
...
added missing hipCmul() to nvcc_detail/hip_complex.h
2018-06-19 09:37:50 +05:30
8f521edff1
Keep the map which tracks GPU kernel symbols to grow monotonically
2018-06-18 16:54:18 -05:00
1e1aa59aed
P4 to Git Change 1569647 by gandryey@gera-lnx-rcf-lc on 2018/06/18 14:04:00
...
SWDEV-79445 - OCL generic changes and code clean-up
-Following CL#1568521. Correct LDS size look-up.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#57 edit
2018-06-18 14:15:59 -04:00
0de3ef7b32
Add abs/real/imag functions for hipFloatComplex/hipDoubleComplex
2018-06-18 11:57:57 -04:00
d30f3f0c88
Merge pull request #521 from gargrahul/temp_fixmemcpy2dasync_trsmissue
...
Use memcpy kernel for all pinned memory cases in hipMemcpy2DAsync
2018-06-18 09:34:02 +05:30
40d2d8a0bd
Add missing __device__ __host__ to complex constructor
...
Also add missing typedef value_type
2018-06-17 20:20:32 -04:00
5d0d2ea455
Includes <cmath> or <math.h> by __cplusplus in hip_complex.h
2018-06-17 20:20:32 -04:00
cc44a3d234
Include cmath instead of math.h in hip_complex.h
2018-06-17 20:20:32 -04:00
8ddadf835d
Add missing macro MAKE_COMPONENT_CONSTRUCTOR_TWO_COMPONENT to hip_complex.h
2018-06-17 20:20:32 -04:00
fd03c8fc18
Fix handling of static library in hipcc for hip-clang
2018-06-17 20:11:10 -04:00
d442a57002
Let hipcc handle static library for hip-clang only if it contains bundles
2018-06-17 20:11:10 -04:00
e9aafc3e93
P4 to Git Change 1569377 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/17 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2675 to 2676.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2423 edit
2018-06-17 03:10:08 -04:00
fa370fcf19
Revert "Revert "Switch over to using native vector types, for better codegen. Remove noise.""
...
This reverts commit d137271083
2018-06-16 22:59:36 +01:00
b883ea759d
Improve performance of re-initialization logic
...
Keep track of shared libaries already discovered. Do not build HSA executables
for them.
2018-06-15 18:07:33 -05:00
007e2a4b5f
TEMP- fix memcpy2dAsync for trsm issue
2018-06-15 16:08:29 +05:30
ccd4fe1653
P4 to Git Change 1568675 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/15 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2674 to 2675.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2422 edit
2018-06-15 03:11:00 -04:00
936b878d72
Made changes as suggested.
2018-06-15 11:30:02 +05:30
d2b85cc118
P4 to Git Change 1568521 by gandryey@gera-w8 on 2018/06/14 17:43:52
...
SWDEV-79445 - OCL generic changes and code clean-up
- Change LDS setup to account the size, since LC forces 4 bytes for LDS offsets always
http://ocltc.amd.com/reviews/r/15197/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_execute.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#49 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpublit.cpp#130 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#327 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#56 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#109 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#38 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#25 edit
2018-06-14 17:51:35 -04:00
f6d8feabeb
P4 to Git Change 1568521 by gandryey@gera-w8 on 2018/06/14 17:43:52
...
SWDEV-79445 - OCL generic changes and code clean-up
- Change LDS setup to account the size, since LC forces 4 bytes for LDS offsets always
http://ocltc.amd.com/reviews/r/15197/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_execute.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#49 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpublit.cpp#130 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#327 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#56 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#109 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#38 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#25 edit
2018-06-14 17:51:35 -04:00
Aaron Enye Shi
Alex Voicu
foreman
Jenkins
Maneesh Gupta
Yaxun (Sam) Liu
pradeepisro
Wen-Heng (Jack) Chung
Rahul Garg
Lakhan Singh