AI/rocm-systems
2
0 Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
76 333 коммитов 3 Ветки 0 Теги
develop
Граф коммитов
76333 Коммитов
This Branch
This Branch
Все ветки
Автор SHA1 Сообщение Дата
Wilkin 8c6a5522b5 OpenCL BLIT for Image library 
- include support for gfx702

Change-Id: If681a4eef9bd076e25300e1c1bca55b4f7c92b46


[ROCm/ROCR-Runtime commit: 170e2a142f]
 2018-07-06 10:35:44 -04:00
Rahul Garg f25b05c793 Cleaned up hipMemset3D test 
[ROCm/clr commit: 7261799835]
 2018-07-06 14:54:08 +05:30
Rahul Garg 7261799835 Cleaned up hipMemset3D test 2018-07-06 14:54:08 +05:30
Rahul Garg 14c424827b Cleaned up hipMemset3D test 
[ROCm/hip commit: 18944113ed]
 2018-07-06 14:54:08 +05:30
Rahul Garg 18944113ed Cleaned up hipMemset3D test 2018-07-06 14:54:08 +05:30
foreman d41cb5f07f P4 to Git Change 1576949 by johtaylo@johtaylo-jtincrementor2-increment on 2018/07/06 03:00:06 
SWDEV-2 - Change OpenCL version number from 2688 to 2689.

Affected files ...

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


[ROCm/clr commit: 73f7b87f92]
 2018-07-06 03:13:56 -04:00
foreman 73f7b87f92 P4 to Git Change 1576949 by johtaylo@johtaylo-jtincrementor2-increment on 2018/07/06 03:00:06 
SWDEV-2 - Change OpenCL version number from 2688 to 2689.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2436 edit
 2018-07-06 03:13:56 -04:00
foreman ae3b7bb3f2 P4 to Git Change 1576872 by skudchad@skudchad_rocm on 2018/07/05 20:20:21 
SWDEV-145570 - [HIP] - Add hipMalloc3D to linker symtable.
	- Add structure for hipFuncGetAttributes

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#11 edit


[ROCm/clr commit: e51c42ac66]
 2018-07-05 20:29:27 -04:00
foreman e51c42ac66 P4 to Git Change 1576872 by skudchad@skudchad_rocm on 2018/07/05 20:20:21 
SWDEV-145570 - [HIP] - Add hipMalloc3D to linker symtable.
	- Add structure for hipFuncGetAttributes

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#11 edit
 2018-07-05 20:29:27 -04:00
foreman f4ef34f7e9 P4 to Git Change 1576872 by skudchad@skudchad_rocm on 2018/07/05 20:20:21 
SWDEV-145570 - [HIP] - Add hipMalloc3D to linker symtable.
	- Add structure for hipFuncGetAttributes

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#11 edit


[ROCm/hip commit: e143868b47]
 2018-07-05 20:29:27 -04:00
foreman e143868b47 P4 to Git Change 1576872 by skudchad@skudchad_rocm on 2018/07/05 20:20:21 
SWDEV-145570 - [HIP] - Add hipMalloc3D to linker symtable.
	- Add structure for hipFuncGetAttributes

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#11 edit
 2018-07-05 20:29:27 -04:00
Felix Kuehling d3228f363e Fix wrong loop termination condition 
Compare with gpu_mem_count instead of deprecated NUM_OF_SUPPORTED_GPUS
to prevent overflows in case no dGPUs are present.

Change-Id: I71fcb7503ba4c20bffadbdb04cefc4e4027a7df7
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
 2018-07-05 17:04:40 -04:00
Felix Kuehling 16246764ce Fix wrong loop termination condition 
Compare with gpu_mem_count instead of deprecated NUM_OF_SUPPORTED_GPUS
to prevent overflows in case no dGPUs are present.

Change-Id: I71fcb7503ba4c20bffadbdb04cefc4e4027a7df7
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>


[ROCm/ROCR-Runtime commit: d3228f363e]
 2018-07-05 17:04:40 -04:00
Aaron Enye Shi 0e5ef747e6 Enable surface functions on HIP clang path 
Fix surface test on HIP clang path.


[ROCm/clr commit: 5862ae4b6a]
 2018-07-05 20:49:47 +00:00
Aaron Enye Shi 5862ae4b6a Enable surface functions on HIP clang path 
Fix surface test on HIP clang path.
 2018-07-05 20:49:47 +00:00
Aaron Enye Shi 0dde5be16b Enable surface functions on HIP clang path 
Fix surface test on HIP clang path.


[ROCm/hip commit: 22b60afa0d]
 2018-07-05 20:49:47 +00:00
Aaron Enye Shi 22b60afa0d Enable surface functions on HIP clang path 
Fix surface test on HIP clang path.
 2018-07-05 20:49:47 +00:00
Aaron Enye Shi eab9cacef2 Implement hip_ldg Functions into HIP header 
Move all the function definitions for hip_ldg.cpp into hip_ldg.h header and enable for HIP clang path.


[ROCm/clr commit: d39508b4fd]
 2018-07-05 20:38:46 +00:00
Aaron Enye Shi d39508b4fd Implement hip_ldg Functions into HIP header 
Move all the function definitions for hip_ldg.cpp into hip_ldg.h header and enable for HIP clang path.
 2018-07-05 20:38:46 +00:00
Aaron Enye Shi 17453a6278 Implement hip_ldg Functions into HIP header 
Move all the function definitions for hip_ldg.cpp into hip_ldg.h header and enable for HIP clang path.


[ROCm/hip commit: 76f86ef097]
 2018-07-05 20:38:46 +00:00
Aaron Enye Shi 76f86ef097 Implement hip_ldg Functions into HIP header 
Move all the function definitions for hip_ldg.cpp into hip_ldg.h header and enable for HIP clang path.
 2018-07-05 20:38:46 +00:00
Aaron Enye Shi 94cc27d4d6 Implement min/max functions in HIP header 
Remove using hc::precise_math min and max. Instead we can use ocml directly for device and std:: for host.


[ROCm/clr commit: b362c53475]
 2018-07-05 20:15:41 +00:00
Aaron Enye Shi b362c53475 Implement min/max functions in HIP header 
Remove using hc::precise_math min and max. Instead we can use ocml directly for device and std:: for host.
 2018-07-05 20:15:41 +00:00
Aaron Enye Shi 8e1a7fdd09 Implement min/max functions in HIP header 
Remove using hc::precise_math min and max. Instead we can use ocml directly for device and std:: for host.


[ROCm/hip commit: 47d78e372e]
 2018-07-05 20:15:41 +00:00
Aaron Enye Shi 47d78e372e Implement min/max functions in HIP header 
Remove using hc::precise_math min and max. Instead we can use ocml directly for device and std:: for host.
 2018-07-05 20:15:41 +00:00
Rahul Garg 1751bc7c26 Added another variant of bindtextoarray for direct porting 
[ROCm/clr commit: 017f668a72]
 2018-07-05 23:41:31 +05:30
Rahul Garg 017f668a72 Added another variant of bindtextoarray for direct porting 2018-07-05 23:41:31 +05:30
Rahul Garg 9735598cd1 Added another variant of bindtextoarray for direct porting 
[ROCm/hip commit: bd4816fc85]
 2018-07-05 23:41:31 +05:30
Rahul Garg bd4816fc85 Added another variant of bindtextoarray for direct porting 2018-07-05 23:41:31 +05:30
Rahul Garg 61b632944b Corrected enum type 
[ROCm/clr commit: b15b08d0db]
 2018-07-05 23:11:39 +05:30
Rahul Garg b15b08d0db Corrected enum type 2018-07-05 23:11:39 +05:30
Rahul Garg 399ec56015 Corrected enum type 
[ROCm/hip commit: 4acf489bd5]
 2018-07-05 23:11:39 +05:30
Rahul Garg 4acf489bd5 Corrected enum type 2018-07-05 23:11:39 +05:30
Rahul Garg c548c3d833 Added tex2dlayered mapping for HIP/NVCC 
[ROCm/clr commit: f080abe5a5]
 2018-07-05 23:00:41 +05:30
Rahul Garg f080abe5a5 Added tex2dlayered mapping for HIP/NVCC 2018-07-05 23:00:41 +05:30
Rahul Garg 0d40be6866 Added tex2dlayered mapping for HIP/NVCC 
[ROCm/hip commit: 19bae58e48]
 2018-07-05 23:00:41 +05:30
Rahul Garg 19bae58e48 Added tex2dlayered mapping for HIP/NVCC 2018-07-05 23:00:41 +05:30
foreman efb43fbae7 P4 to Git Change 1576542 by jatang@jatang-opencl-hsa-stg5 on 2018/07/05 09:29:34 
SWDEV-126897 - Remove un-necessary synchronize() for Device Enqueue in LC/ROCm path.

	We don't need it since we have a hsa_signal_wait_acquire() to wait for the scheduler to finish. Moreover, synchronize() sends a barrier packet that could get stuck for some reason.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#25 edit


[ROCm/clr commit: e2b18eda3e]
 2018-07-05 09:39:08 -04:00
foreman e2b18eda3e P4 to Git Change 1576542 by jatang@jatang-opencl-hsa-stg5 on 2018/07/05 09:29:34 
SWDEV-126897 - Remove un-necessary synchronize() for Device Enqueue in LC/ROCm path.

	We don't need it since we have a hsa_signal_wait_acquire() to wait for the scheduler to finish. Moreover, synchronize() sends a barrier packet that could get stuck for some reason.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#25 edit
 2018-07-05 09:39:08 -04:00
foreman 46f5afe7da P4 to Git Change 1576407 by johtaylo@johtaylo-jtincrementor2-increment on 2018/07/05 03:00:04 
SWDEV-2 - Change OpenCL version number from 2687 to 2688.

Affected files ...

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


[ROCm/clr commit: 5d025cb8bb]
 2018-07-05 03:06:54 -04:00
foreman 5d025cb8bb P4 to Git Change 1576407 by johtaylo@johtaylo-jtincrementor2-increment on 2018/07/05 03:00:04 
SWDEV-2 - Change OpenCL version number from 2687 to 2688.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2435 edit
 2018-07-05 03:06:54 -04:00
Aaron Enye Shi f78a8d7fd6 Implement Memory Fence Functions in header 
Enabled __llvm_fence_* functions for seq_cst.


[ROCm/clr commit: 96ab7c7b25]
 2018-07-04 23:35:24 +00:00
Aaron Enye Shi 96ab7c7b25 Implement Memory Fence Functions in header 
Enabled __llvm_fence_* functions for seq_cst.
 2018-07-04 23:35:24 +00:00
Aaron Enye Shi 0ea959ba9d Implement Memory Fence Functions in header 
Enabled __llvm_fence_* functions for seq_cst.


[ROCm/hip commit: 930a16bccd]
 2018-07-04 23:35:24 +00:00
Aaron Enye Shi 930a16bccd Implement Memory Fence Functions in header 
Enabled __llvm_fence_* functions for seq_cst.
 2018-07-04 23:35:24 +00:00
foreman 86d502a1f8 P4 to Git Change 1576247 by gandryey@gera-w8 on 2018/07/04 16:55:54 
SWDEV-158017 - CL_DEVICE_GLOBAL_FREE_MEMORY_AMD doesn't work correctly on PAL backend
	- Change the free memory detection to account possible memory allocation with oversubscription.
	- Make sure resource cache isn't counted as allocated memory

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#593 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.cpp#244 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.hpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#25 edit


[ROCm/clr commit: 7e185b873e]
 2018-07-04 17:04:53 -04:00
foreman 7e185b873e P4 to Git Change 1576247 by gandryey@gera-w8 on 2018/07/04 16:55:54 
SWDEV-158017 - CL_DEVICE_GLOBAL_FREE_MEMORY_AMD doesn't work correctly on PAL backend
	- Change the free memory detection to account possible memory allocation with oversubscription.
	- Make sure resource cache isn't counted as allocated memory

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#593 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.cpp#244 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.hpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#25 edit
 2018-07-04 17:04:53 -04:00
Aaron Enye Shi 303a8be7d3 Workaround cast warning of smaller integer type for __to_local 
For now, guard the __to_local function for device compile only since a local pointer should be same size as unsigned int on GPU compile. Also change to void* instead of char*.


[ROCm/clr commit: ce9ca744dc]
 2018-07-04 20:52:55 +00:00
Aaron Enye Shi ce9ca744dc Workaround cast warning of smaller integer type for __to_local 
For now, guard the __to_local function for device compile only since a local pointer should be same size as unsigned int on GPU compile. Also change to void* instead of char*.
 2018-07-04 20:52:55 +00:00
Aaron Enye Shi 6bcb3cca86 Workaround cast warning of smaller integer type for __to_local 
For now, guard the __to_local function for device compile only since a local pointer should be same size as unsigned int on GPU compile. Also change to void* instead of char*.


[ROCm/hip commit: 07de5cb334]
 2018-07-04 20:52:55 +00:00