76333 Коммитов

Автор SHA1 Сообщение Дата
pensun 33c38de407 Initial integration with Alex' Generic Grid Launch
Change-Id: I559afb80e9e39ec0d119bb3bf3b85ef9e448caf6
2017-03-17 14:59:34 -05:00
Aditya Atluri 1ec7582820 Added default module launch api functionality
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868


[ROCm/hip-tests commit: 219343027f]
2017-03-17 13:11:34 -05:00
Aditya Atluri 219343027f Added default module launch api functionality
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868
2017-03-17 13:11:34 -05:00
Aditya Atluri b4b87b8786 Added default module launch api functionality
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868


[ROCm/clr commit: 9645b0e0dc]
2017-03-17 13:11:34 -05:00
Aditya Atluri 9645b0e0dc Added default module launch api functionality
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868
2017-03-17 13:11:34 -05:00
Aditya Atluri 95c7942f5c Added default module launch api functionality
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868


[ROCm/hip commit: 99432cc12c]
2017-03-17 13:11:34 -05:00
Aditya Atluri 99432cc12c Added default module launch api functionality
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868
2017-03-17 13:11:34 -05:00
Ben Sander 7466b4005b Move USE_PROMOTE_FREE_HCC
[ROCm/clr commit: 20ea5e179f]
2017-03-17 12:04:13 -05:00
Ben Sander 20ea5e179f Move USE_PROMOTE_FREE_HCC 2017-03-17 12:04:13 -05:00
Ben Sander e10e2bd267 Move USE_PROMOTE_FREE_HCC
[ROCm/hip commit: 8cbe310870]
2017-03-17 12:04:13 -05:00
Ben Sander 8cbe310870 Move USE_PROMOTE_FREE_HCC 2017-03-17 12:04:13 -05:00
Ben Sander e0171505b4 Add __device__ to needful functions for promote-free.
[ROCm/clr commit: 92fd4c8f10]
2017-03-17 11:19:48 -05:00
Ben Sander 92fd4c8f10 Add __device__ to needful functions for promote-free. 2017-03-17 11:19:48 -05:00
Ben Sander 8d5c39fd52 Add __device__ to needful functions for promote-free.
[ROCm/hip commit: 29232ff283]
2017-03-17 11:19:48 -05:00
Ben Sander 29232ff283 Add __device__ to needful functions for promote-free. 2017-03-17 11:19:48 -05:00
Ben Sander 572be5449d Add USE_PROMOTE_FREE_HCC for smooth transition to new HCC caps.
ADDRESS_SPACE_1 defines


[ROCm/clr commit: f4256cb57c]
2017-03-17 11:04:39 -05:00
Ben Sander f4256cb57c Add USE_PROMOTE_FREE_HCC for smooth transition to new HCC caps.
ADDRESS_SPACE_1 defines
2017-03-17 11:04:39 -05:00
Ben Sander a9ec705ee4 Add USE_PROMOTE_FREE_HCC for smooth transition to new HCC caps.
ADDRESS_SPACE_1 defines


[ROCm/hip commit: e85c167171]
2017-03-17 11:04:39 -05:00
Ben Sander e85c167171 Add USE_PROMOTE_FREE_HCC for smooth transition to new HCC caps.
ADDRESS_SPACE_1 defines
2017-03-17 11:04:39 -05:00
Ben Sander c81fb24611 Add simple device-side assert macro
Currently swallows asserts but will compile.


[ROCm/clr commit: c9f64bbd2d]
2017-03-17 10:25:56 -05:00
Ben Sander c9f64bbd2d Add simple device-side assert macro
Currently swallows asserts but will compile.
2017-03-17 10:25:56 -05:00
Ben Sander 25e4ace28b Add simple device-side assert macro
Currently swallows asserts but will compile.


[ROCm/hip commit: ecd8179a71]
2017-03-17 10:25:56 -05:00
Ben Sander ecd8179a71 Add simple device-side assert macro
Currently swallows asserts but will compile.
2017-03-17 10:25:56 -05:00
foreman 96ab410afb P4 to Git Change 1386940 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/17 03:00:05
SWDEV-2 - Change OpenCL version number from 2383 to 2384.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2130 edit


[ROCm/clr commit: 1e561f40e5]
2017-03-17 03:13:06 -04:00
foreman 1e561f40e5 P4 to Git Change 1386940 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/17 03:00:05
SWDEV-2 - Change OpenCL version number from 2383 to 2384.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2130 edit
2017-03-17 03:13:06 -04:00
foreman 6d775d0419 P4 to Git Change 1386753 by gandryey@gera-w8 on 2017/03/16 18:08:37
SWDEV-115529 - Interoperability DX11/OGL/OCL
	- Make sure displayable tiling property is passed to the aliased memory object

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDeviceGL.cpp#28 edit


[ROCm/clr commit: 3f0f26193f]
2017-03-16 18:14:01 -04:00
foreman 3f0f26193f P4 to Git Change 1386753 by gandryey@gera-w8 on 2017/03/16 18:08:37
SWDEV-115529 - Interoperability DX11/OGL/OCL
	- Make sure displayable tiling property is passed to the aliased memory object

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDeviceGL.cpp#28 edit
2017-03-16 18:14:01 -04:00
Evgeny Mankov 151612e184 [HIP] [DOC] Update hip_porting_driver_api.md
+ Fix typos, formatting, update CUDA Driver API support.


[ROCm/clr commit: c6de5b92b5]
2017-03-16 14:39:28 +03:00
Evgeny Mankov c6de5b92b5 [HIP] [DOC] Update hip_porting_driver_api.md
+ Fix typos, formatting, update CUDA Driver API support.
2017-03-16 14:39:28 +03:00
Evgeny Mankov e4af25d292 [HIP] [DOC] Update hip_porting_driver_api.md
+ Fix typos, formatting, update CUDA Driver API support.


[ROCm/hip commit: 76820409a8]
2017-03-16 14:39:28 +03:00
Evgeny Mankov 76820409a8 [HIP] [DOC] Update hip_porting_driver_api.md
+ Fix typos, formatting, update CUDA Driver API support.
2017-03-16 14:39:28 +03:00
Ilya Biryukov fa9d609d5d Fix compilation error when compiling with 'clang -x cuda'.
Functions vFetch and vStore are not found by ADL with clang,
so they need to be declared before usage in ReduceCopy.


[ROCm/rccl commit: 8241cd7b6e]
2017-03-16 12:01:11 +01:00
Ilya Biryukov 8241cd7b6e Fix compilation error when compiling with 'clang -x cuda'.
Functions vFetch and vStore are not found by ADL with clang,
so they need to be declared before usage in ReduceCopy.
2017-03-16 12:01:11 +01:00
foreman 86d9e0ee94 P4 to Git Change 1386335 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/16 03:00:05
SWDEV-2 - Change OpenCL version number from 2382 to 2383.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2129 edit


[ROCm/clr commit: 3da0a50292]
2017-03-16 03:11:07 -04:00
foreman 3da0a50292 P4 to Git Change 1386335 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/16 03:00:05
SWDEV-2 - Change OpenCL version number from 2382 to 2383.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2129 edit
2017-03-16 03:11:07 -04:00
Siu Chi Chan ff4621af4e replace code names with gfx names
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b


[ROCm/clr commit: c6efbc1f25]
2017-03-15 12:26:13 -04:00
Siu Chi Chan c6efbc1f25 replace code names with gfx names
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b
2017-03-15 12:26:13 -04:00
Siu Chi Chan d17073a995 replace code names with gfx names
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b


[ROCm/hip commit: a96821871f]
2017-03-15 12:26:13 -04:00
Siu Chi Chan a96821871f replace code names with gfx names
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b
2017-03-15 12:26:13 -04:00
Maneesh Gupta f1bfcb634c Merge branch 'amd-develop' into amd-master
Change-Id: Ifc503b382fc93491b7d72ba2f5bb3511ceeb8e3d


[ROCm/clr commit: 516866a410]
2017-03-15 14:10:43 +05:30
Maneesh Gupta 516866a410 Merge branch 'amd-develop' into amd-master
Change-Id: Ifc503b382fc93491b7d72ba2f5bb3511ceeb8e3d
2017-03-15 14:10:43 +05:30
Maneesh Gupta 2578d1b310 Merge branch 'amd-develop' into amd-master
Change-Id: Ifc503b382fc93491b7d72ba2f5bb3511ceeb8e3d


[ROCm/hip commit: f4e19a3ff6]
2017-03-15 14:10:43 +05:30
Maneesh Gupta f4e19a3ff6 Merge branch 'amd-develop' into amd-master
Change-Id: Ifc503b382fc93491b7d72ba2f5bb3511ceeb8e3d
2017-03-15 14:10:43 +05:30
foreman 3d9131ba30 P4 to Git Change 1385795 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/15 03:00:06
SWDEV-2 - Change OpenCL version number from 2381 to 2382.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2128 edit


[ROCm/clr commit: 4506b41314]
2017-03-15 03:06:32 -04:00
foreman 4506b41314 P4 to Git Change 1385795 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/15 03:00:06
SWDEV-2 - Change OpenCL version number from 2381 to 2382.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2128 edit
2017-03-15 03:06:32 -04:00
Maneesh Gupta da5548303e Disable broken tests on hcc path
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823


[ROCm/clr commit: 8536af7b71]
2017-03-15 12:03:44 +05:30
Maneesh Gupta 8536af7b71 Disable broken tests on hcc path
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823
2017-03-15 12:03:44 +05:30
Maneesh Gupta 86e2a5d11d Disable broken tests on hcc path
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823


[ROCm/hip commit: 65bb22eefc]
2017-03-15 12:03:44 +05:30
Maneesh Gupta 65bb22eefc Disable broken tests on hcc path
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823
2017-03-15 12:03:44 +05:30
Maneesh Gupta fe01aec686 hipcc: Fix warning when HCC_AMDGPU_TARGET is not defined
Change-Id: I5cc6b0e9fb23ec78152d8bcfe9e7511e2fe91055


[ROCm/clr commit: 42faa4a4fe]
2017-03-15 12:03:05 +05:30