76333 Commits

Autor SHA1 Mensaje Fecha
Ben Sander 2b253a48b6 Use accelerator_scope for create_marker and create_blocking_marker.
As optimization when system-scope is not needed.
2017-05-23 23:15:45 -05:00
Ben Sander 0cde8e5db4 Fix trace category for hipHostMalloc
[ROCm/clr commit: ca07615c37]
2017-05-23 23:15:45 -05:00
Ben Sander ca07615c37 Fix trace category for hipHostMalloc 2017-05-23 23:15:45 -05:00
Ben Sander 1e0046f737 Fix trace category for hipHostMalloc
[ROCm/hip commit: 7cfe07cff4]
2017-05-23 23:15:45 -05:00
Ben Sander 7cfe07cff4 Fix trace category for hipHostMalloc 2017-05-23 23:15:45 -05:00
foreman 29c7a56713 P4 to Git Change 1412538 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/23 03:00:04
SWDEV-2 - Change OpenCL version number from 2425 to 2426.

Affected files ...

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


[ROCm/clr commit: 2e71ba3a73]
2017-05-23 17:24:39 -04:00
foreman 2e71ba3a73 P4 to Git Change 1412538 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/23 03:00:04
SWDEV-2 - Change OpenCL version number from 2425 to 2426.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2173 edit
2017-05-23 17:24:39 -04:00
Evgeny Mankov 9e7a50b1e0 [FIX] [HIPIFY] Matcher for new operator is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/80

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];


[ROCm/clr commit: 21d74f09b9]
2017-05-23 19:45:38 +03:00
Evgeny Mankov 21d74f09b9 [FIX] [HIPIFY] Matcher for new operator is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/80

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];
2017-05-23 19:45:38 +03:00
Evgeny Mankov 0a43773e0d [FIX] [HIPIFY] Matcher for new operator is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/80

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];


[ROCm/hip commit: 3d973dc4da]
2017-05-23 19:45:38 +03:00
Evgeny Mankov 3d973dc4da [FIX] [HIPIFY] Matcher for new operator is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/80

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];
2017-05-23 19:45:38 +03:00
foreman 485dfbc6e2 P4 to Git Change 1412187 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/21 03:00:05
SWDEV-2 - Change OpenCL version number from 2424 to 2425.

Affected files ...

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


[ROCm/clr commit: 421c10fd87]
2017-05-23 10:35:22 -04:00
foreman 421c10fd87 P4 to Git Change 1412187 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/21 03:00:05
SWDEV-2 - Change OpenCL version number from 2424 to 2425.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2172 edit
2017-05-23 10:35:22 -04:00
Aditya Atluri e7813b1933 fixed erfinv build error as it is implemented in hcc
Change-Id: I27a512147c53f658a63fdf3e90f5e9cfac09ada8


[ROCm/clr commit: 490355203b]
2017-05-23 09:32:19 -05:00
Aditya Atluri 490355203b fixed erfinv build error as it is implemented in hcc
Change-Id: I27a512147c53f658a63fdf3e90f5e9cfac09ada8
2017-05-23 09:32:19 -05:00
Aditya Atluri 6e117234bf fixed erfinv build error as it is implemented in hcc
Change-Id: I27a512147c53f658a63fdf3e90f5e9cfac09ada8


[ROCm/hip commit: 0559fc69e9]
2017-05-23 09:32:19 -05:00
Aditya Atluri 0559fc69e9 fixed erfinv build error as it is implemented in hcc
Change-Id: I27a512147c53f658a63fdf3e90f5e9cfac09ada8
2017-05-23 09:32:19 -05:00
foreman 3a0554d5b4 P4 to Git Change 1412181 by yaxunl@yaxunl_stg_win50 on 2017/05/20 20:14:34
SWDEV-121585 - [OCL-LC-ROCm] Merge GitHub pull requests
	- Merged https://github.com/RadeonOpenCompute/ROCm-OpenCL-Runtime/pull/8

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#33 edit


[ROCm/clr commit: 2cea61199a]
2017-05-23 10:30:44 -04:00
foreman 2cea61199a P4 to Git Change 1412181 by yaxunl@yaxunl_stg_win50 on 2017/05/20 20:14:34
SWDEV-121585 - [OCL-LC-ROCm] Merge GitHub pull requests
	- Merged https://github.com/RadeonOpenCompute/ROCm-OpenCL-Runtime/pull/8

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#33 edit
2017-05-23 10:30:44 -04:00
pensun f848e9f117 fix GGL helper header file, reorder for C++17
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213


[ROCm/clr commit: 2523f8a492]
2017-05-22 08:52:43 -05:00
pensun 2523f8a492 fix GGL helper header file, reorder for C++17
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213
2017-05-22 08:52:43 -05:00
pensun b19e862dc4 fix GGL helper header file, reorder for C++17
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213


[ROCm/hip commit: 6d0f58b939]
2017-05-22 08:52:43 -05:00
pensun 6d0f58b939 fix GGL helper header file, reorder for C++17
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213
2017-05-22 08:52:43 -05:00
Evgeny Mankov aebc80c8e0 [HIPIFY] [FIX] [HIPIFY] Matcher for pointer to enum var declaration is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];

[TODO]
1. new CUjit_option -> new hipJitOption.
   Matcher for new operator is missing:
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79
2. Merge matchers cudaEnumDecl and cudaEnumVarPtr.


[ROCm/clr commit: 51b7420359]
2017-05-19 17:39:09 +03:00
Evgeny Mankov 51b7420359 [HIPIFY] [FIX] [HIPIFY] Matcher for pointer to enum var declaration is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];

[TODO]
1. new CUjit_option -> new hipJitOption.
   Matcher for new operator is missing:
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79
2. Merge matchers cudaEnumDecl and cudaEnumVarPtr.
2017-05-19 17:39:09 +03:00
Evgeny Mankov cb7e073c42 [HIPIFY] [FIX] [HIPIFY] Matcher for pointer to enum var declaration is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];

[TODO]
1. new CUjit_option -> new hipJitOption.
   Matcher for new operator is missing:
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79
2. Merge matchers cudaEnumDecl and cudaEnumVarPtr.


[ROCm/hip commit: b5a1d47e68]
2017-05-19 17:39:09 +03:00
Evgeny Mankov b5a1d47e68 [HIPIFY] [FIX] [HIPIFY] Matcher for pointer to enum var declaration is missing.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];

[TODO]
1. new CUjit_option -> new hipJitOption.
   Matcher for new operator is missing:
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79
2. Merge matchers cudaEnumDecl and cudaEnumVarPtr.
2017-05-19 17:39:09 +03:00
Evgeny Mankov 052f630bd3 [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.


[ROCm/clr commit: ae9f14ef9c]
2017-05-19 17:22:14 +03:00
Evgeny Mankov ae9f14ef9c [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.
2017-05-19 17:22:14 +03:00
Evgeny Mankov 042de3e175 [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.


[ROCm/hip commit: 270f643c9c]
2017-05-19 17:22:14 +03:00
Evgeny Mankov 270f643c9c [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.
2017-05-19 17:22:14 +03:00
foreman 25834f08d8 P4 to Git Change 1411633 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/19 03:00:04
SWDEV-2 - Change OpenCL version number from 2423 to 2424.

Affected files ...

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


[ROCm/clr commit: 738528f6f3]
2017-05-19 03:07:36 -04:00
foreman 738528f6f3 P4 to Git Change 1411633 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/19 03:00:04
SWDEV-2 - Change OpenCL version number from 2423 to 2424.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2171 edit
2017-05-19 03:07:36 -04:00
foreman f3b10bbbca P4 to Git Change 1411361 by gandryey@gera-lnx-rcf-lc on 2017/05/18 14:22:45
SWDEV-121873 - [ROCm CQE][Vega10][QR] Observed Aborted (core dumped) while running clinfo due to CL#1410373
	- Fix device handle default initialization

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/pro/prodevice.hpp#2 edit


[ROCm/clr commit: 6d7fb53d4a]
2017-05-18 14:47:03 -04:00
foreman 6d7fb53d4a P4 to Git Change 1411361 by gandryey@gera-lnx-rcf-lc on 2017/05/18 14:22:45
SWDEV-121873 - [ROCm CQE][Vega10][QR] Observed Aborted (core dumped) while running clinfo due to CL#1410373
	- Fix device handle default initialization

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/pro/prodevice.hpp#2 edit
2017-05-18 14:47:03 -04:00
Aditya Atluri 905ab9a689 fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd


[ROCm/clr commit: 0433a2e608]
2017-05-18 10:51:07 -05:00
Aditya Atluri 0433a2e608 fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd
2017-05-18 10:51:07 -05:00
Aditya Atluri 721cb0f7db fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd


[ROCm/hip commit: bdc08fcf10]
2017-05-18 10:51:07 -05:00
Aditya Atluri bdc08fcf10 fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd
2017-05-18 10:51:07 -05:00
foreman 0bbe6a74da P4 to Git Change 1411057 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/18 03:00:04
SWDEV-2 - Change OpenCL version number from 2422 to 2423.

Affected files ...

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


[ROCm/clr commit: fabcd11161]
2017-05-18 03:04:34 -04:00
foreman fabcd11161 P4 to Git Change 1411057 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/18 03:00:04
SWDEV-2 - Change OpenCL version number from 2422 to 2423.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2170 edit
2017-05-18 03:04:34 -04:00
foreman 6b2cb94b84 P4 to Git Change 1410993 by lmoriche@lmoriche_opencl_dev2 on 2017/05/17 22:25:50
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Make it possible to use cl2.hpp

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl2.0/CL/cl2.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/clinfo.cpp#3 edit


[ROCm/clr commit: 842f311464]
2017-05-17 22:31:48 -04:00
foreman 842f311464 P4 to Git Change 1410993 by lmoriche@lmoriche_opencl_dev2 on 2017/05/17 22:25:50
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Make it possible to use cl2.hpp

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl2.0/CL/cl2.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/clinfo.cpp#3 edit
2017-05-17 22:31:48 -04:00
Sean Keely e38ff18990 Unmap GPUs when allow_access removes them from system pools.
Change-Id: Ib9eb88622fded43ebd9eddbf78ad6771a5b91e77
2017-05-17 20:58:05 -04:00
Sean Keely 754935ee65 Unmap GPUs when allow_access removes them from system pools.
Change-Id: Ib9eb88622fded43ebd9eddbf78ad6771a5b91e77


[ROCm/ROCR-Runtime commit: e38ff18990]
2017-05-17 20:58:05 -04:00
foreman fceec81e95 P4 to Git Change 1410861 by gandryey@gera-lnx-rcf-lc on 2017/05/17 17:03:55
SWDEV-120180 - [amdgpu-pro] OpenCL support for SSG
	Correct define name

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_lqdflash_amd.cpp#20 edit


[ROCm/clr commit: 757432840f]
2017-05-17 18:52:41 -04:00
foreman 757432840f P4 to Git Change 1410861 by gandryey@gera-lnx-rcf-lc on 2017/05/17 17:03:55
SWDEV-120180 - [amdgpu-pro] OpenCL support for SSG
	Correct define name

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_lqdflash_amd.cpp#20 edit
2017-05-17 18:52:41 -04:00
foreman 95ab416aa0 P4 to Git Change 1410787 by gandryey@gera-w8 on 2017/05/17 15:15:22
SWDEV-120180 - [amdgpu-pro] OpenCL support for SSG
	- Protect amdgpu-pro headers with the define for easier open source integration

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#21 edit


[ROCm/clr commit: 94759e212e]
2017-05-17 15:49:02 -04:00
foreman 94759e212e P4 to Git Change 1410787 by gandryey@gera-w8 on 2017/05/17 15:15:22
SWDEV-120180 - [amdgpu-pro] OpenCL support for SSG
	- Protect amdgpu-pro headers with the define for easier open source integration

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#21 edit
2017-05-17 15:49:02 -04:00
foreman 70dc638015 P4 to Git Change 1410684 by gandryey@gera-w8 on 2017/05/17 13:00:21
SWDEV-120180 - [amdgpu-pro] OpenCL support for SSG
	Fix open source build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_lqdflash_amd.cpp#19 edit


[ROCm/clr commit: 928d2bcf66]
2017-05-17 13:09:07 -04:00