AI/rocm-systems
2
0
Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
76 333 коммитов 3 Ветки 0 Теги
develop
Граф коммитов

76333 Коммитов

This Branch
This Branch
Все ветки
Автор SHA1 Сообщение Дата
foreman 8854784f49 P4 to Git Change 1414965 by gandryey@gera-w8 on 2017/05/26 15:51:24 
SWDEV-79445 - OCL generic changes and code clean-up
	- use getBackendDevice() for HSA agent look-up for persistent memory allocation

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#23 edit
 2017-05-26 16:08:36 -04:00
Ben Sander d9587ae2f0 Add isDefaultStream() accessor. 
Fix code that checked for stream==nullptr after stream had been
resolved to a "true stream".


[ROCm/clr commit: b2b620c12b]
 2017-05-26 13:46:48 -05:00
Ben Sander b2b620c12b Add isDefaultStream() accessor. 
Fix code that checked for stream==nullptr after stream had been
resolved to a "true stream".
 2017-05-26 13:46:48 -05:00
Ben Sander 715aeef97c Add isDefaultStream() accessor. 
Fix code that checked for stream==nullptr after stream had been
resolved to a "true stream".


[ROCm/hip commit: b251d72917]
 2017-05-26 13:46:48 -05:00
Ben Sander b251d72917 Add isDefaultStream() accessor. 
Fix code that checked for stream==nullptr after stream had been
resolved to a "true stream".
 2017-05-26 13:46:48 -05:00
foreman 0d55a0a397 P4 to Git Change 1414821 by lmoriche@lmoriche_palamida on 2017/05/26 13:04:04 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Update from git.

Affected files ...

... //depot/stg/opencl/drivers/opencl/.gitignore#1 add
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#10 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/CMakeLists.txt#5 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#1 add


[ROCm/clr commit: 595192b942]
 2017-05-26 13:12:30 -04:00
foreman 595192b942 P4 to Git Change 1414821 by lmoriche@lmoriche_palamida on 2017/05/26 13:04:04 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Update from git.

Affected files ...

... //depot/stg/opencl/drivers/opencl/.gitignore#1 add
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#10 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/CMakeLists.txt#5 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#1 add
 2017-05-26 13:12:30 -04:00
foreman 385e747cb2 P4 to Git Change 1414821 by lmoriche@lmoriche_palamida on 2017/05/26 13:04:04 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Update from git.

Affected files ...

... //depot/stg/opencl/drivers/opencl/.gitignore#1 add
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#10 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/CMakeLists.txt#5 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#1 add


[ROCm/clr commit: 700577fee9]
 2017-05-26 13:12:30 -04:00
foreman 700577fee9 P4 to Git Change 1414821 by lmoriche@lmoriche_palamida on 2017/05/26 13:04:04 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Update from git.

Affected files ...

... //depot/stg/opencl/drivers/opencl/.gitignore#1 add
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#10 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/CMakeLists.txt#5 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#1 add
 2017-05-26 13:12:30 -04:00
foreman d610b81968 P4 to Git Change 1414775 by asalmanp@asalmanp-ocl-stg on 2017/05/26 11:34:07 
SWDEV-120065 - [Vega10] Multi 4k60 Hyrid VP9 Chrome Decode Causes System Hang
	- The hang happens because runtime was overwriting an incomplete IB due to incorrect result for OS event wait.
	- To fix this issue force to wait for fences if ibReuse is enabled.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/12862/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#23 edit


[ROCm/clr commit: 600b7c365c]
 2017-05-26 11:43:05 -04:00
foreman 600b7c365c P4 to Git Change 1414775 by asalmanp@asalmanp-ocl-stg on 2017/05/26 11:34:07 
SWDEV-120065 - [Vega10] Multi 4k60 Hyrid VP9 Chrome Decode Causes System Hang
	- The hang happens because runtime was overwriting an incomplete IB due to incorrect result for OS event wait.
	- To fix this issue force to wait for fences if ibReuse is enabled.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/12862/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#23 edit
 2017-05-26 11:43:05 -04:00
foreman c5ffb841a4 P4 to Git Change 1414622 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/26 03:00:05 
SWDEV-2 - Change OpenCL version number from 2428 to 2429.

Affected files ...

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


[ROCm/clr commit: 88f304df7d]
 2017-05-26 03:06:00 -04:00
foreman 88f304df7d P4 to Git Change 1414622 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/26 03:00:05 
SWDEV-2 - Change OpenCL version number from 2428 to 2429.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2176 edit
 2017-05-26 03:06:00 -04:00
Siu Chi Chan 6c3a05ac5b fix hip_fast_dsqrt* to call a double fp sqrt function 
[ROCm/clr commit: a3595d2e8c]
 2017-05-25 23:15:30 -04:00
Siu Chi Chan a3595d2e8c fix hip_fast_dsqrt* to call a double fp sqrt function 2017-05-25 23:15:30 -04:00
Siu Chi Chan ef1a8c2788 fix hip_fast_dsqrt* to call a double fp sqrt function 
[ROCm/hip commit: 1dce01f9bb]
 2017-05-25 23:15:30 -04:00
Siu Chi Chan 1dce01f9bb fix hip_fast_dsqrt* to call a double fp sqrt function 2017-05-25 23:15:30 -04:00
foreman be45f9068f P4 to Git Change 1414382 by cpaquot@cpaquot-ocl-lc-lnx on 2017/05/25 15:55:25 
SWDEV-121486 - Create a metadata structure
	This is needed for UGL/CL interop because in UGL, they do not pass the metadata
	to KMD/KFD via amdgpu_bo_set_metadata. UGL instead will pass the SRD info
	via the mesa_in.out_driver_data.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#286 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.hpp#9 edit


[ROCm/clr commit: 2839999356]
 2017-05-25 16:07:03 -04:00
foreman 2839999356 P4 to Git Change 1414382 by cpaquot@cpaquot-ocl-lc-lnx on 2017/05/25 15:55:25 
SWDEV-121486 - Create a metadata structure
	This is needed for UGL/CL interop because in UGL, they do not pass the metadata
	to KMD/KFD via amdgpu_bo_set_metadata. UGL instead will pass the SRD info
	via the mesa_in.out_driver_data.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#286 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.hpp#9 edit
 2017-05-25 16:07:03 -04:00
foreman db91a865ed P4 to Git Change 1414000 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/25 03:00:04 
SWDEV-2 - Change OpenCL version number from 2427 to 2428.

Affected files ...

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


[ROCm/clr commit: 5782f336db]
 2017-05-25 03:11:46 -04:00
foreman 5782f336db P4 to Git Change 1414000 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/25 03:00:04 
SWDEV-2 - Change OpenCL version number from 2427 to 2428.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2175 edit
 2017-05-25 03:11:46 -04:00
foreman 811a3b06b2 P4 to Git Change 1413623 by lmoriche@lmoriche_palamida on 2017/05/24 11:41:52 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Set the default triple to amdgcn-amd-amdhsa-opencl

Affected files ...

... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#9 edit


[ROCm/clr commit: 80b3356ed6]
 2017-05-24 11:49:07 -04:00
foreman 80b3356ed6 P4 to Git Change 1413623 by lmoriche@lmoriche_palamida on 2017/05/24 11:41:52 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Set the default triple to amdgcn-amd-amdhsa-opencl

Affected files ...

... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#9 edit
 2017-05-24 11:49:07 -04:00
foreman 42f8a1a169 P4 to Git Change 1413623 by lmoriche@lmoriche_palamida on 2017/05/24 11:41:52 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Set the default triple to amdgcn-amd-amdhsa-opencl

Affected files ...

... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#9 edit


[ROCm/clr commit: 3623f0d69e]
 2017-05-24 11:49:07 -04:00
foreman 3623f0d69e P4 to Git Change 1413623 by lmoriche@lmoriche_palamida on 2017/05/24 11:41:52 
SWDEV-102733 - [OCL-LC-ROCm] Cmake build Write CMakeLists.txt to enable building with and without the DK environment
	- Set the default triple to amdgcn-amd-amdhsa-opencl

Affected files ...

... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#9 edit
 2017-05-24 11:49:07 -04:00
Evgeny Mankov ed54e3d0ee [FIX] [HIPIFY] Add matchers for function return types. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/73

Examples (https://github.com/thrust/thrust/blob/master/thrust/system/cuda/detail/trivial_copy.inl):

template<typename System1,
         typename System2>
cudaStream_t cuda_memcpy_stream(const thrust::cpp::execution_policy<System1> &,
                                const thrust::cuda::execution_policy<System2> &exec)

template<typename System1,
         typename System2>
cudaMemcpyKind cuda_memcpy_kind(const thrust::cuda::execution_policy<System1> &,
                                const thrust::cpp::execution_policy<System2> &)


[ROCm/clr commit: a19ecab3f2]
 2017-05-24 18:25:40 +03:00
Evgeny Mankov a19ecab3f2 [FIX] [HIPIFY] Add matchers for function return types. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/73

Examples (https://github.com/thrust/thrust/blob/master/thrust/system/cuda/detail/trivial_copy.inl):

template<typename System1,
         typename System2>
cudaStream_t cuda_memcpy_stream(const thrust::cpp::execution_policy<System1> &,
                                const thrust::cuda::execution_policy<System2> &exec)

template<typename System1,
         typename System2>
cudaMemcpyKind cuda_memcpy_kind(const thrust::cuda::execution_policy<System1> &,
                                const thrust::cpp::execution_policy<System2> &)
 2017-05-24 18:25:40 +03:00
Evgeny Mankov bc9b970f82 [FIX] [HIPIFY] Add matchers for function return types. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/73

Examples (https://github.com/thrust/thrust/blob/master/thrust/system/cuda/detail/trivial_copy.inl):

template<typename System1,
         typename System2>
cudaStream_t cuda_memcpy_stream(const thrust::cpp::execution_policy<System1> &,
                                const thrust::cuda::execution_policy<System2> &exec)

template<typename System1,
         typename System2>
cudaMemcpyKind cuda_memcpy_kind(const thrust::cuda::execution_policy<System1> &,
                                const thrust::cpp::execution_policy<System2> &)


[ROCm/hip commit: c863215611]
 2017-05-24 18:25:40 +03:00
Evgeny Mankov c863215611 [FIX] [HIPIFY] Add matchers for function return types. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/73

Examples (https://github.com/thrust/thrust/blob/master/thrust/system/cuda/detail/trivial_copy.inl):

template<typename System1,
         typename System2>
cudaStream_t cuda_memcpy_stream(const thrust::cpp::execution_policy<System1> &,
                                const thrust::cuda::execution_policy<System2> &exec)

template<typename System1,
         typename System2>
cudaMemcpyKind cuda_memcpy_kind(const thrust::cuda::execution_policy<System1> &,
                                const thrust::cpp::execution_policy<System2> &)
 2017-05-24 18:25:40 +03:00
foreman a05773f367 P4 to Git Change 1413393 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/24 03:00:04 
SWDEV-2 - Change OpenCL version number from 2426 to 2427.

Affected files ...

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


[ROCm/clr commit: 5e85545c43]
 2017-05-24 03:17:11 -04:00
foreman 5e85545c43 P4 to Git Change 1413393 by johtaylo@johtaylo-jtincrementor-increment on 2017/05/24 03:00:04 
SWDEV-2 - Change OpenCL version number from 2426 to 2427.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2174 edit
 2017-05-24 03:17:11 -04:00
Ben Sander b4363ffcba Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls) 
[ROCm/clr commit: 35212632e7]
 2017-05-24 01:03:28 -05:00
Ben Sander 35212632e7 Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls) 2017-05-24 01:03:28 -05:00
Ben Sander b7b7c7b7ac Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls) 
[ROCm/hip commit: 578d430bb3]
 2017-05-24 01:03:28 -05:00
Ben Sander 578d430bb3 Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls) 2017-05-24 01:03:28 -05:00
Ben Sander d302498787 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/clr commit: dda70ae514]
 2017-05-24 00:48:10 -05:00
Ben Sander dda70ae514 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.
 2017-05-24 00:48:10 -05:00
Ben Sander 5b9ce41633 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/hip commit: 75f691ec2f]
 2017-05-24 00:48:10 -05:00
Ben Sander 75f691ec2f Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.
 2017-05-24 00:48:10 -05:00
Ben Sander ae983e1b09 Remove HIP_MAX_QUEUES (replaced with HCC_MAX_QUEUES) 
[ROCm/clr commit: d43d57d39c]
 2017-05-23 23:48:01 -05:00
Ben Sander d43d57d39c Remove HIP_MAX_QUEUES (replaced with HCC_MAX_QUEUES) 2017-05-23 23:48:01 -05:00
Ben Sander 07865c3a02 Remove HIP_MAX_QUEUES (replaced with HCC_MAX_QUEUES) 
[ROCm/hip commit: d0ef9d8462]
 2017-05-23 23:48:01 -05:00
Ben Sander d0ef9d8462 Remove HIP_MAX_QUEUES (replaced with HCC_MAX_QUEUES) 2017-05-23 23:48:01 -05:00
Ben Sander 59e07db865 Expand test to cover copy followed by event sync 
[ROCm/clr commit: 92bd54d7b3]
 2017-05-23 23:15:45 -05:00
Ben Sander 92bd54d7b3 Expand test to cover copy followed by event sync 2017-05-23 23:15:45 -05:00
Ben Sander 247c34195f Expand test to cover copy followed by event sync 
[ROCm/hip commit: 236ce70e94]
 2017-05-23 23:15:45 -05:00
Ben Sander 236ce70e94 Expand test to cover copy followed by event sync 2017-05-23 23:15:45 -05:00
Ben Sander 2e8625a208 Use accelerator_scope for create_marker and create_blocking_marker. 
As optimization when system-scope is not needed.


[ROCm/clr commit: 2d5b3359c6]
 2017-05-23 23:15:45 -05:00
Ben Sander 2d5b3359c6 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 97bdbe6590 Use accelerator_scope for create_marker and create_blocking_marker. 
As optimization when system-scope is not needed.


[ROCm/hip commit: 2b253a48b6]
 2017-05-23 23:15:45 -05:00