76333 Commits
Autor SHA1 Mensaje Fecha
Alex Voicu 5e90c6a081 Missing __device__. 2018-06-01 19:48:36 +01:00
Alex Voicu 4306856ec9 Fix typos / address review comments.
[ROCm/clr commit: 91d9ec75d7]
2018-06-01 16:20:21 +01:00
Alex Voicu 91d9ec75d7 Fix typos / address review comments. 2018-06-01 16:20:21 +01:00
Alex Voicu 82e4fecfeb Fix typos / address review comments.
[ROCm/hip commit: ebd6d49cd2]
2018-06-01 16:20:21 +01:00
Alex Voicu ebd6d49cd2 Fix typos / address review comments. 2018-06-01 16:20:21 +01:00
Alex Voicu 130e9d409e Re-sync with upstream.
[ROCm/clr commit: f2d7f112ab]
2018-06-01 15:49:05 +01:00
Alex Voicu f2d7f112ab Re-sync with upstream. 2018-06-01 15:49:05 +01:00
Alex Voicu b9bf931765 Re-sync with upstream.
[ROCm/hip commit: 417869821d]
2018-06-01 15:49:05 +01:00
Alex Voicu 417869821d Re-sync with upstream. 2018-06-01 15:49:05 +01:00
Yaxun (Sam) Liu 95f240612d Update INSTALL.md
[ROCm/clr commit: bb9ad15c34]
2018-06-01 10:19:02 -04:00
Yaxun (Sam) Liu bb9ad15c34 Update INSTALL.md 2018-06-01 10:19:02 -04:00
Yaxun (Sam) Liu b46a961f1d Update INSTALL.md
[ROCm/hip commit: 8ccb069226]
2018-06-01 10:19:02 -04:00
Yaxun (Sam) Liu 8ccb069226 Update INSTALL.md 2018-06-01 10:19:02 -04:00
Evgeny 53211acd04 test: scenario with different counters sets per dispatch
Change-Id: Ia0866d485128e7295cbf98c3241a6113ce8d98b8
2018-06-01 09:06:51 -05:00
Evgeny 81356f3745 test: scenario with different counters sets per dispatch
Change-Id: Ia0866d485128e7295cbf98c3241a6113ce8d98b8


[ROCm/rocprofiler commit: 53211acd04]
2018-06-01 09:06:51 -05:00
Rahul Garg 11e33a1203 Map hipArray alloc flags on NVCC
[ROCm/clr commit: b1b9a477a2]
2018-06-01 17:28:43 +05:30
Rahul Garg b1b9a477a2 Map hipArray alloc flags on NVCC 2018-06-01 17:28:43 +05:30
Rahul Garg 17ff646d18 Map hipArray alloc flags on NVCC
[ROCm/hip commit: d3621a2500]
2018-06-01 17:28:43 +05:30
Rahul Garg d3621a2500 Map hipArray alloc flags on NVCC 2018-06-01 17:28:43 +05:30
Maneesh Gupta 73cbb7bb7b Merge pull request #484 from gargrahul/fix_malloc_hiphostreg
Fix memcpy2D for malloc+ hostRegister

[ROCm/clr commit: 095d4dd91e]
2018-06-01 16:53:25 +05:30
Maneesh Gupta 095d4dd91e Merge pull request #484 from gargrahul/fix_malloc_hiphostreg
Fix memcpy2D for malloc+ hostRegister
2018-06-01 16:53:25 +05:30
Maneesh Gupta eded0da7b5 Merge pull request #484 from gargrahul/fix_malloc_hiphostreg
Fix memcpy2D for malloc+ hostRegister

[ROCm/hip commit: df450c6680]
2018-06-01 16:53:25 +05:30
Maneesh Gupta df450c6680 Merge pull request #484 from gargrahul/fix_malloc_hiphostreg
Fix memcpy2D for malloc+ hostRegister
2018-06-01 16:53:25 +05:30
Maneesh Gupta 2a9a7b9aa3 Merge pull request #447 from ROCm-Developer-Tools/feature_native_vector_types
Switch over to using native vector types, for better codegen. Remove noise.

[ROCm/clr commit: 3fec282097]
2018-06-01 13:58:07 +05:30
Maneesh Gupta 3fec282097 Merge pull request #447 from ROCm-Developer-Tools/feature_native_vector_types
Switch over to using native vector types, for better codegen. Remove noise.
2018-06-01 13:58:07 +05:30
Maneesh Gupta 121993cae8 Merge pull request #447 from ROCm-Developer-Tools/feature_native_vector_types
Switch over to using native vector types, for better codegen. Remove noise.

[ROCm/hip commit: 68c36f9125]
2018-06-01 13:58:07 +05:30
Maneesh Gupta 68c36f9125 Merge pull request #447 from ROCm-Developer-Tools/feature_native_vector_types
Switch over to using native vector types, for better codegen. Remove noise.
2018-06-01 13:58:07 +05:30
Maneesh Gupta 125f6201c8 Merge pull request #466 from ROCm-Developer-Tools/feature_use_Float16
Feature use _Float16 and match CUDA __half behaviour.

[ROCm/clr commit: 8ecb3eeb55]
2018-06-01 13:50:12 +05:30
Maneesh Gupta 8ecb3eeb55 Merge pull request #466 from ROCm-Developer-Tools/feature_use_Float16
Feature use _Float16 and match CUDA __half behaviour.
2018-06-01 13:50:12 +05:30
Maneesh Gupta 7f9b00ba19 Merge pull request #466 from ROCm-Developer-Tools/feature_use_Float16
Feature use _Float16 and match CUDA __half behaviour.

[ROCm/hip commit: bdf2645713]
2018-06-01 13:50:12 +05:30
Maneesh Gupta bdf2645713 Merge pull request #466 from ROCm-Developer-Tools/feature_use_Float16
Feature use _Float16 and match CUDA __half behaviour.
2018-06-01 13:50:12 +05:30
foreman bb8c5fc084 P4 to Git Change 1562633 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/01 03:00:06
SWDEV-2 - Change OpenCL version number from 2667 to 2668.

Affected files ...

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


[ROCm/clr commit: 9c63c5efb5]
2018-06-01 03:10:53 -04:00
foreman 9c63c5efb5 P4 to Git Change 1562633 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/01 03:00:06
SWDEV-2 - Change OpenCL version number from 2667 to 2668.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2415 edit
2018-06-01 03:10:53 -04:00
Yaxun (Sam) Liu 65a299f8c2 Update INSTALL.md
[ROCm/clr commit: 3ed6fff0db]
2018-05-31 23:55:42 -04:00
Yaxun (Sam) Liu 3ed6fff0db Update INSTALL.md 2018-05-31 23:55:42 -04:00
Yaxun (Sam) Liu d7737975e9 Update INSTALL.md
[ROCm/hip commit: 98491cd759]
2018-05-31 23:55:42 -04:00
Yaxun (Sam) Liu 98491cd759 Update INSTALL.md 2018-05-31 23:55:42 -04:00
foreman 0f8c914c5f P4 to Git Change 1562507 by skudchad@skudchad_test2_win_opencl on 2018/05/31 18:10:39
SWDEV-145570 - [HIP] - Fix HIP build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#11 edit


[ROCm/clr commit: 28247da814]
2018-05-31 18:18:00 -04:00
foreman 28247da814 P4 to Git Change 1562507 by skudchad@skudchad_test2_win_opencl on 2018/05/31 18:10:39
SWDEV-145570 - [HIP] - Fix HIP build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#11 edit
2018-05-31 18:18:00 -04:00
foreman fe2d99b857 P4 to Git Change 1562507 by skudchad@skudchad_test2_win_opencl on 2018/05/31 18:10:39
SWDEV-145570 - [HIP] - Fix HIP build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#11 edit


[ROCm/hip commit: bad00db6ea]
2018-05-31 18:18:00 -04:00
foreman bad00db6ea P4 to Git Change 1562507 by skudchad@skudchad_test2_win_opencl on 2018/05/31 18:10:39
SWDEV-145570 - [HIP] - Fix HIP build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#11 edit
2018-05-31 18:18:00 -04:00
foreman 86cab131cf P4 to Git Change 1562330 by gandryey@gera-w8 on 2018/05/31 14:48:10
SWDEV-79445 - OCL generic changes and code clean-up
	- Restore reatain/release methods in the device object, removed in CL#1398097. There is a crash in the old SHOC11_DeviceMemory test on TC.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#305 edit


[ROCm/clr commit: 97223251ca]
2018-05-31 14:55:04 -04:00
foreman 97223251ca P4 to Git Change 1562330 by gandryey@gera-w8 on 2018/05/31 14:48:10
SWDEV-79445 - OCL generic changes and code clean-up
	- Restore reatain/release methods in the device object, removed in CL#1398097. There is a crash in the old SHOC11_DeviceMemory test on TC.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#305 edit
2018-05-31 14:55:04 -04:00
Felix Kuehling 0462744965 Add fallback for GPUVM doorbell mapping
Upstream KFD doesn't support mapping doorbells to GPUVM yet. Fall
back to the old method.

Change-Id: I452a6fc59b88329b833844e3914c480c2f13c82d
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
2018-05-31 13:17:27 -04:00
Felix Kuehling da46bda904 Add fallback for GPUVM doorbell mapping
Upstream KFD doesn't support mapping doorbells to GPUVM yet. Fall
back to the old method.

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


[ROCm/ROCR-Runtime commit: 0462744965]
2018-05-31 13:17:27 -04:00
Felix Kuehling 7495e74257 Cosmetic changes to kfd_ioctl.h
Make it more similar with upstream.

Change-Id: I982ccfd4045d96e3c30bc84d38d0e03db8de9b08
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
2018-05-31 13:17:27 -04:00
Felix Kuehling c3c36d0afd Cosmetic changes to kfd_ioctl.h
Make it more similar with upstream.

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


[ROCm/ROCR-Runtime commit: 7495e74257]
2018-05-31 13:17:27 -04:00
Felix Kuehling 571e2cf7e4 Update KFD-Thunk ioctl ABI to match upstream
- Clean up and renumber scratch memory ioctl
- Renumber get_tile_config ioctl
- Renumber set_trap_handler ioctl
- Update KFD_IOC_ALLOC_MEM_FLAGS
- Renumber GPUVM memory management ioctls
- Remove unused SEP_PROCESS_DGPU_APERTURE ioctl
- Update memory management ioctls
    Replace device_ids_array_size (in bytes) with n_devices. Fix error
    handling and use n_success to update device_id arrays in objects.

This commit breaks the ABI and requires a corresponding KFD change.

Change-Id: Ibf0af5a5188e817c886eab388d1533130fc18293
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
2018-05-31 13:17:27 -04:00
Felix Kuehling 212b7f50dd Update KFD-Thunk ioctl ABI to match upstream
- Clean up and renumber scratch memory ioctl
- Renumber get_tile_config ioctl
- Renumber set_trap_handler ioctl
- Update KFD_IOC_ALLOC_MEM_FLAGS
- Renumber GPUVM memory management ioctls
- Remove unused SEP_PROCESS_DGPU_APERTURE ioctl
- Update memory management ioctls
    Replace device_ids_array_size (in bytes) with n_devices. Fix error
    handling and use n_success to update device_id arrays in objects.

This commit breaks the ABI and requires a corresponding KFD change.

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


[ROCm/ROCR-Runtime commit: 571e2cf7e4]
2018-05-31 13:17:27 -04:00
Alex Voicu a9cabfc8df Re-sync with upstream. Add integer abs.
[ROCm/clr commit: e03ca1a72e]
2018-05-31 16:38:00 +01:00