AI/rocm-systems
2
0 Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
76,333 Commits 3 Branches 0 Tags
develop
Commit Graph
76333 Commits
This Branch
This Branch
All Branches
Author SHA1 Message Date
Konstantin Pyzhov e04e408a37 hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov ae391b3211 hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 
[ROCm/hip commit: e29c9d50a6]
 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov e29c9d50a6 hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov b2e3880696 Refined hipSetDevice test. 
[ROCm/clr commit: 29fd3812e5]
 2019-05-03 05:39:45 -04:00
Konstantin Pyzhov 29fd3812e5 Refined hipSetDevice test. 2019-05-03 05:39:45 -04:00
Konstantin Pyzhov 45eb04ea5c Refined hipSetDevice test. 
[ROCm/hip commit: 069fb7e486]
 2019-05-03 05:39:45 -04:00
Konstantin Pyzhov 069fb7e486 Refined hipSetDevice test. 2019-05-03 05:39:45 -04:00
foreman 35b325c15a P4 to Git Change 1777875 by chui@ocl-promo-incrementor on 2019/05/03 03:00:03 
SWDEV-2 - Change OpenCL version number from 2888 to 2889.

Affected files ...

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


[ROCm/clr commit: 0f72983a61]
 2019-05-03 03:09:51 -04:00
foreman 0f72983a61 P4 to Git Change 1777875 by chui@ocl-promo-incrementor on 2019/05/03 03:00:03 
SWDEV-2 - Change OpenCL version number from 2888 to 2889.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2636 edit
 2019-05-03 03:09:51 -04:00
Felix Kuehling c8d823eb10 kfdtest: Make eviction tests more robust 
- Run more graphics command submissions with shorter delay between
  them
- Synchronize after every graphics command submission
- Include the big VRAM BO in the BOList of the command submission
  to trigger more evictions
- In QueueTest, run AMDGPU command submissions concurrently with
  compute shader on the user mode queue
- Submit AMDGPU commands to GFX queue instead of compute queue to
  avoid deadlocks between user-mode and kernel-mode queues on the
  same pipe
- Allocate slightly less memory from KFD to avoid allocation errors
  due to fragmentation or memory leaks in previous tests
- Running only two processes maximizes the number of KFD evictions
  (probably because of lower chances of evicting non-KFD BOs)

Change-Id: If05d53f5fcf690b6488998a3f933f120ddaa71ee
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
 2019-05-02 17:34:11 -04:00
Felix Kuehling 4b8a5ead52 kfdtest: Make eviction tests more robust 
- Run more graphics command submissions with shorter delay between
  them
- Synchronize after every graphics command submission
- Include the big VRAM BO in the BOList of the command submission
  to trigger more evictions
- In QueueTest, run AMDGPU command submissions concurrently with
  compute shader on the user mode queue
- Submit AMDGPU commands to GFX queue instead of compute queue to
  avoid deadlocks between user-mode and kernel-mode queues on the
  same pipe
- Allocate slightly less memory from KFD to avoid allocation errors
  due to fragmentation or memory leaks in previous tests
- Running only two processes maximizes the number of KFD evictions
  (probably because of lower chances of evicting non-KFD BOs)

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


[ROCm/ROCR-Runtime commit: c8d823eb10]
 2019-05-02 17:34:11 -04:00
foreman 96044cf114 P4 to Git Change 1777625 by asalmanp@asalmanp-ocl-stg on 2019/05/02 14:31:30 
SWDEV-132899 - [OCL][GFX10] Add support for Navi12Lite

	ReviewBaordURL = http://ocltc.amd.com/reviews/r/17281/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palbedefs#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#78 edit


[ROCm/clr commit: 441d322dc8]
 2019-05-02 15:20:45 -04:00
foreman 441d322dc8 P4 to Git Change 1777625 by asalmanp@asalmanp-ocl-stg on 2019/05/02 14:31:30 
SWDEV-132899 - [OCL][GFX10] Add support for Navi12Lite

	ReviewBaordURL = http://ocltc.amd.com/reviews/r/17281/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palbedefs#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#78 edit
 2019-05-02 15:20:45 -04:00
Michael LIAO 9823184397 [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/clr commit: aad19f6171]
 2019-05-02 12:34:07 -04:00
Michael LIAO aad19f6171 [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.
 2019-05-02 12:34:07 -04:00
Michael LIAO b7ae0b6442 [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/hip commit: 16a27e06ee]
 2019-05-02 12:34:07 -04:00
Michael LIAO 16a27e06ee [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.
 2019-05-02 12:34:07 -04:00
foreman 590ca4c37c P4 to Git Change 1777295 by chui@ocl-promo-incrementor on 2019/05/02 03:00:03 
SWDEV-2 - Change OpenCL version number from 2887 to 2888.

Affected files ...

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


[ROCm/clr commit: b6712eb2ed]
 2019-05-02 03:13:01 -04:00
foreman b6712eb2ed P4 to Git Change 1777295 by chui@ocl-promo-incrementor on 2019/05/02 03:00:03 
SWDEV-2 - Change OpenCL version number from 2887 to 2888.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2635 edit
 2019-05-02 03:13:01 -04:00
Michael LIAO 08fa23f774 [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.


[ROCm/clr commit: a9f90713f3]
 2019-05-01 22:26:35 -04:00
Michael LIAO a9f90713f3 [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.
 2019-05-01 22:26:35 -04:00
Michael LIAO 2c2b897902 [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.


[ROCm/hip commit: 44692978fe]
 2019-05-01 22:26:35 -04:00
Michael LIAO 44692978fe [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.
 2019-05-01 22:26:35 -04:00
foreman f567589672 P4 to Git Change 1777225 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 18:47:25 
SWDEV-188233 - [HIP] Implemented hipGetChannelDesc.

Affected files ...

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


[ROCm/clr commit: b39d02b166]
 2019-05-01 19:53:29 -04:00
foreman b39d02b166 P4 to Git Change 1777225 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 18:47:25 
SWDEV-188233 - [HIP] Implemented hipGetChannelDesc.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#11 edit
 2019-05-01 19:53:29 -04:00
foreman 8c0263f6c5 P4 to Git Change 1777225 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 18:47:25 
SWDEV-188233 - [HIP] Implemented hipGetChannelDesc.

Affected files ...

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


[ROCm/hip commit: 3ad9c3f984]
 2019-05-01 19:53:29 -04:00
foreman 3ad9c3f984 P4 to Git Change 1777225 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 18:47:25 
SWDEV-188233 - [HIP] Implemented hipGetChannelDesc.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#11 edit
 2019-05-01 19:53:29 -04:00
foreman 70c54adc71 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit


[ROCm/clr commit: d3774315a0]
 2019-05-01 18:43:47 -04:00
foreman d3774315a0 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit
 2019-05-01 18:43:47 -04:00
foreman 2d2e37205f P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit


[ROCm/clr commit: ef45e9ab42]
 2019-05-01 18:43:47 -04:00
foreman ef45e9ab42 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit
 2019-05-01 18:43:47 -04:00
foreman 486506f113 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit


[ROCm/hip commit: ba93e1ae21]
 2019-05-01 18:43:47 -04:00
foreman ba93e1ae21 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit
 2019-05-01 18:43:47 -04:00
Wenkai Du b0e3a2ac64 allow using different memory types for input and output buffers 
[ROCm/rccl-tests commit: 3f89175af5]
 2019-05-01 12:58:04 -07:00
Wenkai Du 3f89175af5 allow using different memory types for input and output buffers 2019-05-01 12:58:04 -07:00
foreman 9c291c3119 P4 to Git Change 1776901 by gandryey@gera-w8 on 2019/05/01 11:42:45 
SWDEV-187956 - [CQE OCL][NAVI 10][WIN][LNX] Assertion failure observed with Subtests of OpenMM on PAL/LC path
	- Correct the number of SIMDs and SIMD width for Navi10.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#51 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#24 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/runtime/OCLDeviceQueries.cpp#54 edit


[ROCm/clr commit: 268627d98e]
 2019-05-01 12:05:50 -04:00
foreman 268627d98e P4 to Git Change 1776901 by gandryey@gera-w8 on 2019/05/01 11:42:45 
SWDEV-187956 - [CQE OCL][NAVI 10][WIN][LNX] Assertion failure observed with Subtests of OpenMM on PAL/LC path
	- Correct the number of SIMDs and SIMD width for Navi10.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#51 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#24 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/runtime/OCLDeviceQueries.cpp#54 edit
 2019-05-01 12:05:50 -04:00
foreman 60bed323a1 P4 to Git Change 1776881 by jatang@jatang_win_pal_lc on 2019/05/01 11:04:10 
SWDEV-174198 - Back out changelist 1776874.

	Need to wait for //depot/main/drivers/inc/asic_reg/ai_id.h promotion.

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/linker.cpp#161 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/libUtils.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings.h#58 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#54 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#49 edit
... //depot/stg/opencl/drivers/opencl/compiler/tools/driver/driver.cpp#71 edit


[ROCm/clr commit: e79e3e6f21]
 2019-05-01 11:49:17 -04:00
foreman e79e3e6f21 P4 to Git Change 1776881 by jatang@jatang_win_pal_lc on 2019/05/01 11:04:10 
SWDEV-174198 - Back out changelist 1776874.

	Need to wait for //depot/main/drivers/inc/asic_reg/ai_id.h promotion.

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/linker.cpp#161 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/libUtils.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings.h#58 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#54 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#49 edit
... //depot/stg/opencl/drivers/opencl/compiler/tools/driver/driver.cpp#71 edit
 2019-05-01 11:49:17 -04:00
foreman bfefbd1dc0 P4 to Git Change 1776874 by jatang@jatang_win_pal_lc on 2019/05/01 10:56:52 
SWDEV-174198 - Add support for MI100.

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/linker.cpp#160 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/libUtils.cpp#38 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings.h#57 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#53 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#48 edit
... //depot/stg/opencl/drivers/opencl/compiler/tools/driver/driver.cpp#70 edit


[ROCm/clr commit: c8d38859e0]
 2019-05-01 11:44:42 -04:00
foreman c8d38859e0 P4 to Git Change 1776874 by jatang@jatang_win_pal_lc on 2019/05/01 10:56:52 
SWDEV-174198 - Add support for MI100.

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/linker.cpp#160 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/libUtils.cpp#38 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings.h#57 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#53 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#48 edit
... //depot/stg/opencl/drivers/opencl/compiler/tools/driver/driver.cpp#70 edit
 2019-05-01 11:44:42 -04:00
foreman 016cc2c43f P4 to Git Change 1776811 by chui@ocl-promo-incrementor on 2019/05/01 03:00:07 
SWDEV-2 - Change OpenCL version number from 2886 to 2887.

Affected files ...

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


[ROCm/clr commit: e9dedd6682]
 2019-05-01 03:09:33 -04:00
foreman e9dedd6682 P4 to Git Change 1776811 by chui@ocl-promo-incrementor on 2019/05/01 03:00:07 
SWDEV-2 - Change OpenCL version number from 2886 to 2887.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2634 edit
 2019-05-01 03:09:33 -04:00
foreman 5f144110be P4 to Git Change 1776765 by todli@todli-win-opencl-kv1 on 2019/04/30 19:30:32 
SWDEV-181817 - remove HostMemDirectAccess flag for non-tiled 3D image, so that unimplemented pal::Resouce::mapLayers() will not be hit by Fill Image path.

	ocltc.amd.com/reviews/r/17238/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#23 edit


[ROCm/clr commit: cf74994c54]
 2019-04-30 19:41:57 -04:00
foreman cf74994c54 P4 to Git Change 1776765 by todli@todli-win-opencl-kv1 on 2019/04/30 19:30:32 
SWDEV-181817 - remove HostMemDirectAccess flag for non-tiled 3D image, so that unimplemented pal::Resouce::mapLayers() will not be hit by Fill Image path.

	ocltc.amd.com/reviews/r/17238/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#23 edit
 2019-04-30 19:41:57 -04:00
Oak Zeng 804aa90a22 Add MMIO_REMAP heap type 
Add a MMIO_REMAP heap type and expose mmio virtual address
through HsaKmtGetNodeMemoryProperties



Change-Id: I1e585e6dfbec8fa7c85f1dda7b89b763a8e2c439
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>
 2019-04-30 15:40:50 -05:00
Oak Zeng dbfa65a604 Add MMIO_REMAP heap type 
Add a MMIO_REMAP heap type and expose mmio virtual address
through HsaKmtGetNodeMemoryProperties



Change-Id: I1e585e6dfbec8fa7c85f1dda7b89b763a8e2c439
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>


[ROCm/ROCR-Runtime commit: 804aa90a22]
 2019-04-30 15:40:50 -05:00
Evgeny Mankov 86c59f7bc9 Merge pull request #1063 from emankov/master 
[HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example

[ROCm/clr commit: be1e22ffe3]
 2019-04-30 17:40:05 +03:00
Evgeny Mankov be1e22ffe3 Merge pull request #1063 from emankov/master 
[HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example
 2019-04-30 17:40:05 +03:00
Evgeny Mankov 12d4111e16 Merge pull request #1063 from emankov/master 
[HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example

[ROCm/hip commit: 4e09081554]
 2019-04-30 17:40:05 +03:00