76333 Commit
Autore SHA1 Messaggio Data
foreman f3e2d275c5 P4 to Git Change 1995665 by skudchad@skudchad_test2_win_opencl on 2019/09/09 14:36:57
SWDEV-199293 - Implement hiprtcGetLoweredName

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/17960/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#3 edit
2019-09-09 14:42:47 -04:00
eshcherb b1d33ba719 Merge pull request #14 from rkebichi/amd-master
corrected return value from Pop API call

[ROCm/roctracer commit: 450a4802df]
2019-09-09 13:26:22 -05:00
eshcherb 450a4802df Merge pull request #14 from rkebichi/amd-master
corrected return value from Pop API call
2019-09-09 13:26:22 -05:00
eshcherb 4a75bda819 Merge pull request #13 from rkebichi/amd-master
Update roctx.cpp

[ROCm/roctracer commit: 2ef3889b51]
2019-09-09 13:15:26 -05:00
eshcherb 2ef3889b51 Merge pull request #13 from rkebichi/amd-master
Update roctx.cpp
2019-09-09 13:15:26 -05:00
Jenkins 2dcff60dbb Merge 'master' into 'amd-master'
Change-Id: Ibb1dbe78aa52c8aeb77851ee1471e1edaec4c654


[ROCm/clr commit: 4b88d83acc]
2019-09-09 05:10:28 -04:00
Jenkins 4b88d83acc Merge 'master' into 'amd-master'
Change-Id: Ibb1dbe78aa52c8aeb77851ee1471e1edaec4c654
2019-09-09 05:10:28 -04:00
Jenkins 2f7a11093f Merge 'master' into 'amd-master'
Change-Id: Ibb1dbe78aa52c8aeb77851ee1471e1edaec4c654


[ROCm/hip commit: cbe6b65e2c]
2019-09-09 05:10:28 -04:00
Jenkins cbe6b65e2c Merge 'master' into 'amd-master'
Change-Id: Ibb1dbe78aa52c8aeb77851ee1471e1edaec4c654
2019-09-09 05:10:28 -04:00
foreman b73ab08843 P4 to Git Change 1995043 by chui@ocl-promo-incrementor on 2019/09/07 03:00:33
SWDEV-2 - Change OpenCL version number from 2991 to 2992.

Affected files ...

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


[ROCm/clr commit: d37c45e6b6]
2019-09-07 12:03:56 -04:00
foreman d37c45e6b6 P4 to Git Change 1995043 by chui@ocl-promo-incrementor on 2019/09/07 03:00:33
SWDEV-2 - Change OpenCL version number from 2991 to 2992.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2739 edit
2019-09-07 12:03:56 -04:00
Evgeny Mankov 452b53fa21 Merge pull request #1398 from emankov/master
[HIPIFY] Add device functions support

[ROCm/clr commit: 861dada8ea]
2019-09-07 19:00:00 +03:00
Evgeny Mankov 861dada8ea Merge pull request #1398 from emankov/master
[HIPIFY] Add device functions support
2019-09-07 19:00:00 +03:00
Evgeny Mankov cec523f647 Merge pull request #1398 from emankov/master
[HIPIFY] Add device functions support

[ROCm/hip commit: 29d09eb269]
2019-09-07 19:00:00 +03:00
Evgeny Mankov 29d09eb269 Merge pull request #1398 from emankov/master
[HIPIFY] Add device functions support
2019-09-07 19:00:00 +03:00
foreman fb96543a7d P4 to Git Change 1994974 by skudchad@skudchad_test2_win_opencl on 2019/09/06 19:09:36
SWDEV-199293 - Implement some hipRTC apis.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/17953/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#18 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#2 edit


[ROCm/clr commit: 9a839c46dc]
2019-09-06 19:11:43 -04:00
foreman 9a839c46dc P4 to Git Change 1994974 by skudchad@skudchad_test2_win_opencl on 2019/09/06 19:09:36
SWDEV-199293 - Implement some hipRTC apis.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/17953/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#18 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#2 edit
2019-09-06 19:11:43 -04:00
foreman bf11a2e460 P4 to Git Change 1994974 by skudchad@skudchad_test2_win_opencl on 2019/09/06 19:09:36
SWDEV-199293 - Implement some hipRTC apis.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/17953/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#18 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#2 edit


[ROCm/hip commit: 8167dee7d5]
2019-09-06 19:11:43 -04:00
foreman 8167dee7d5 P4 to Git Change 1994974 by skudchad@skudchad_test2_win_opencl on 2019/09/06 19:09:36
SWDEV-199293 - Implement some hipRTC apis.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/17953/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#18 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#2 edit
2019-09-06 19:11:43 -04:00
Sean Keely f2599fccb6 Enable trap handler on APUs.
Change-Id: Ifdc8c2782498b3fbe238d773120d378c47918d07
2019-09-06 18:10:20 -04:00
Sean Keely 286cf8f732 Enable trap handler on APUs.
Change-Id: Ifdc8c2782498b3fbe238d773120d378c47918d07


[ROCm/ROCR-Runtime commit: f2599fccb6]
2019-09-06 18:10:20 -04:00
Sean Keely f9d3796db8 Correct doorbell_queue_map allocation.
doorbell_queue_map should always be allocated or we will need to
add branches around all accesses.

Change-Id: I994c0eaf4be62c1a4a37bd06894272dba1fc1da6
2019-09-06 18:10:20 -04:00
Sean Keely 9c6f904413 Correct doorbell_queue_map allocation.
doorbell_queue_map should always be allocated or we will need to
add branches around all accesses.

Change-Id: I994c0eaf4be62c1a4a37bd06894272dba1fc1da6


[ROCm/ROCR-Runtime commit: f9d3796db8]
2019-09-06 18:10:20 -04:00
Yong Zhao baa2957895 kfdtest: Add gfx1012 initial test coverage
Change-Id: I983d4dd6c17b2eaadd5abf4b71e090a14cace303
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>
2019-09-06 14:42:43 -04:00
Yong Zhao c3a66a975b kfdtest: Add gfx1012 initial test coverage
Change-Id: I983d4dd6c17b2eaadd5abf4b71e090a14cace303
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>


[ROCm/ROCR-Runtime commit: baa2957895]
2019-09-06 14:42:43 -04:00
Yong Zhao 3ecd83e52d libhsakmt: Support gfx1012
The gfx version item is yet to be added.

Change-Id: Ia6c487447e5a5df80c0c12fe150939175068024b
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>
2019-09-06 14:42:32 -04:00
Yong Zhao 7f5a93ef2a libhsakmt: Support gfx1012
The gfx version item is yet to be added.

Change-Id: Ia6c487447e5a5df80c0c12fe150939175068024b
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>


[ROCm/ROCR-Runtime commit: 3ecd83e52d]
2019-09-06 14:42:32 -04:00
Gilbert Lee dbb7500fd1 RDMA HDP flush fix
[ROCm/rccl commit: 86ce0a93b5]
2019-09-06 16:35:55 +00:00
Gilbert Lee 86ce0a93b5 RDMA HDP flush fix 2019-09-06 16:35:55 +00:00
Yong Zhao d6539ddc24 libhsakmt: Implement HSA_FORCE_ASIC_TYPE to overwrite asic type
Force all the GPUs to a certain type, use the below command:
HSA_FORCE_ASIC_TYPE="10.1.0 1 gfx1010 14"
meaning major.minor.step dgpu asic_name asic_id

This will faciliate the cooperation across the teams for bringing up
ASICs which reuse existing device IDs.

Change-Id: I40fe4c9b46d3ccb3e38ea52250e80e82fb50fb0f
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>
2019-09-06 12:12:42 -04:00
Yong Zhao fab21d6d81 libhsakmt: Implement HSA_FORCE_ASIC_TYPE to overwrite asic type
Force all the GPUs to a certain type, use the below command:
HSA_FORCE_ASIC_TYPE="10.1.0 1 gfx1010 14"
meaning major.minor.step dgpu asic_name asic_id

This will faciliate the cooperation across the teams for bringing up
ASICs which reuse existing device IDs.

Change-Id: I40fe4c9b46d3ccb3e38ea52250e80e82fb50fb0f
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>


[ROCm/ROCR-Runtime commit: d6539ddc24]
2019-09-06 12:12:42 -04:00
Evgeny Mankov 755d1a9ea6 [HIPIFY] Add device functions support
+ Add a corresponding matcher cudaDeviceFuncCall to match only (__device__ or __global__) and not __host__ functions.
+ Add a corresponding device functions mapping:
  only unsupported are listed, cause supported are exactly the same as of CUDA and do not need transformation;
  make FindAndReplace for device functions separated from host API calls.
+ Add a test to distinguish device functions and user-defined.


[ROCm/clr commit: aec10d6ee1]
2019-09-06 18:34:12 +03:00
Evgeny Mankov aec10d6ee1 [HIPIFY] Add device functions support
+ Add a corresponding matcher cudaDeviceFuncCall to match only (__device__ or __global__) and not __host__ functions.
+ Add a corresponding device functions mapping:
  only unsupported are listed, cause supported are exactly the same as of CUDA and do not need transformation;
  make FindAndReplace for device functions separated from host API calls.
+ Add a test to distinguish device functions and user-defined.
2019-09-06 18:34:12 +03:00
Evgeny Mankov 17b734afde [HIPIFY] Add device functions support
+ Add a corresponding matcher cudaDeviceFuncCall to match only (__device__ or __global__) and not __host__ functions.
+ Add a corresponding device functions mapping:
  only unsupported are listed, cause supported are exactly the same as of CUDA and do not need transformation;
  make FindAndReplace for device functions separated from host API calls.
+ Add a test to distinguish device functions and user-defined.


[ROCm/hip commit: 6602fadc16]
2019-09-06 18:34:12 +03:00
Evgeny Mankov 6602fadc16 [HIPIFY] Add device functions support
+ Add a corresponding matcher cudaDeviceFuncCall to match only (__device__ or __global__) and not __host__ functions.
+ Add a corresponding device functions mapping:
  only unsupported are listed, cause supported are exactly the same as of CUDA and do not need transformation;
  make FindAndReplace for device functions separated from host API calls.
+ Add a test to distinguish device functions and user-defined.
2019-09-06 18:34:12 +03:00
Yong Zhao 09d192802a kfdtest: Remove useless test cases
Those tests are actually did not function up to its expectation because
some underlying functions such as suspend/resume and disable/enable KFD
were not implemented. Those interfaces would never be implemented, so
delete them.

Change-Id: Ib5872ba2f35e307221e43791cda1782c6b6bb4d1
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>
2019-09-06 11:12:17 -04:00
Yong Zhao cc050951de kfdtest: Remove useless test cases
Those tests are actually did not function up to its expectation because
some underlying functions such as suspend/resume and disable/enable KFD
were not implemented. Those interfaces would never be implemented, so
delete them.

Change-Id: Ib5872ba2f35e307221e43791cda1782c6b6bb4d1
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>


[ROCm/ROCR-Runtime commit: 09d192802a]
2019-09-06 11:12:17 -04:00
Yong Zhao 9048fb5a1a kfdtest: Implement SuspendAndWakeUp()
Change-Id: I16384cd0ca35f15841344ded4d4237a0a862a934
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>
2019-09-06 11:11:49 -04:00
Yong Zhao 9b1e0f5a5e kfdtest: Implement SuspendAndWakeUp()
Change-Id: I16384cd0ca35f15841344ded4d4237a0a862a934
Signed-off-by: Yong Zhao <Yong.Zhao@amd.com>


[ROCm/ROCR-Runtime commit: 9048fb5a1a]
2019-09-06 11:11:49 -04:00
rkebichi de29108439 Update roctx.cpp
[ROCm/roctracer commit: c15059cb2b]
2019-09-06 10:56:25 -04:00
rkebichi c15059cb2b Update roctx.cpp 2019-09-06 10:56:25 -04:00
rkebichi b754b9a965 Update roctx.cpp
[ROCm/roctracer commit: 5b444aaef3]
2019-09-06 10:45:25 -04:00
rkebichi 5b444aaef3 Update roctx.cpp 2019-09-06 10:45:25 -04:00
foreman 95c0f07e54 P4 to Git Change 1994498 by skudchad@skudchad_test2_win_opencl on 2019/09/06 04:25:22
SWDEV-202136 - Fix windows build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#26 edit


[ROCm/clr commit: 860615b64d]
2019-09-06 04:33:24 -04:00
foreman 860615b64d P4 to Git Change 1994498 by skudchad@skudchad_test2_win_opencl on 2019/09/06 04:25:22
SWDEV-202136 - Fix windows build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#26 edit
2019-09-06 04:33:24 -04:00
foreman d59a4d4b77 P4 to Git Change 1994498 by skudchad@skudchad_test2_win_opencl on 2019/09/06 04:25:22
SWDEV-202136 - Fix windows build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#26 edit


[ROCm/hip commit: 5db35686db]
2019-09-06 04:33:24 -04:00
foreman 5db35686db P4 to Git Change 1994498 by skudchad@skudchad_test2_win_opencl on 2019/09/06 04:25:22
SWDEV-202136 - Fix windows build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#26 edit
2019-09-06 04:33:24 -04:00
foreman 6edcdd9e3c P4 to Git Change 1994455 by chui@ocl-promo-incrementor on 2019/09/06 03:00:32
SWDEV-2 - Change OpenCL version number from 2990 to 2991.

Affected files ...

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


[ROCm/clr commit: f21e52fd06]
2019-09-06 03:06:07 -04:00
foreman f21e52fd06 P4 to Git Change 1994455 by chui@ocl-promo-incrementor on 2019/09/06 03:00:32
SWDEV-2 - Change OpenCL version number from 2990 to 2991.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2738 edit
2019-09-06 03:06:07 -04:00
Evgeny 258c868a49 setting hip backend library by env HIP_BACKEND_LIB for VDI support
[ROCm/roctracer commit: 3aad90a320]
2019-09-05 20:20:38 -05:00