Commit Graph

11608 Commits

Author SHA1 Message Date
foreman c12870228a P4 to Git Change 1966866 by vsytchen@vsytchen-ocl-win10 on 2019/07/12 16:08:01
SWDEV-192353 - 12% Performance drop observed while running ROC_OCL_Perf_CompubenchCL_GPU_W64 only on Vega10 with Win7

	1. Reduce CmdAllocator sub-allocation size to 4KB.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#137 edit


[ROCm/clr commit: 3669ba964e]
2019-07-12 22:12:16 -04:00
Evgeny Mankov 495c6489ee [HIPIFY][doc] Update README.md: the latest cuDNN 7.6.1.34 is supported
[ROCm/clr commit: 608a2a1eb8]
2019-07-12 18:49:54 +03:00
Evgeny Mankov 24af494e97 [HIP] Fix segfault on uninitialized struct members in hipArrayCreate and hipArray3DCreate
[ROCm/clr commit: 299fbd4842]
2019-07-12 16:38:26 +03:00
Evgeny Mankov 129df30a5f [HIPIFY][#1221] Add regex replacements for include refs with path separators while generating hipify-perl
[ROCm/clr commit: 13788368ea]
2019-07-12 16:18:00 +03:00
foreman b1d99d0802 P4 to Git Change 1966294 by chui@ocl-promo-incrementor on 2019/07/12 03:00:10
SWDEV-2 - Change OpenCL version number from 2944 to 2945.

Affected files ...

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


[ROCm/clr commit: a8fb74a8b6]
2019-07-12 03:07:21 -04:00
kpyzhov 71297fa621 Added gfx906 kernel binary to the HIPFB file for hipModule test. (#1215)
[ROCm/clr commit: 728ce926d9]
2019-07-12 03:13:45 +00:00
Yaxun (Sam) Liu 682dcddbbd Add amdgpu targets gfx1010 and gfx1012 (#1211)
[ROCm/clr commit: 4b5061e13f]
2019-07-12 03:13:35 +00:00
foreman f28957f413 P4 to Git Change 1966049 by cpaquot@cpaquot-ocl-lc-lnx on 2019/07/11 19:05:18
SWDEV-189500 - [HIP] Have to force async=false for host to device case as well

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#61 edit


[ROCm/clr commit: a888b06ede]
2019-07-11 19:13:06 -04:00
Evgeny Mankov b5f0cdaa7b [HIP][HIPIFY] Split HIP_ARRAY_DESCRIPTOR struct to HIP_ARRAY_DESCRIPTOR and HIP_ARRAY3D_DESCRIPTOR
[Reason] To be compatible with CUDA [#1133]

Update HIP code, hipify-clang, tests and docs

[TODO] Add support of the corresponding functions on nvcc fallback path


[ROCm/clr commit: f0832fd968]
2019-07-11 14:58:16 +03:00
mhbliao e402a1db65 Add missing compound assignment operators. (#1216)
[ROCm/clr commit: e701e337f9]
2019-07-11 09:16:15 +00:00
Jatin Chaudhary 877fd02244 Adding fix to initialize a dim3 variable from blockIdx. (#1212)
Adding gitignore for ctags

[ROCm/clr commit: 46553d719a]
2019-07-11 09:16:03 +00:00
foreman c2701443d1 P4 to Git Change 1965506 by chui@ocl-promo-incrementor on 2019/07/11 03:00:09
SWDEV-2 - Change OpenCL version number from 2943 to 2944.

Affected files ...

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


[ROCm/clr commit: ba82794af1]
2019-07-11 03:09:43 -04:00
Maneesh Gupta 362938e1b0 Revert "[ci] Disable hipLaunchParm.tst for now" (#1087)
[ROCm/clr commit: e3b1dabdc5]
2019-07-11 00:24:23 +00:00
foreman eeb2ef2b0b P4 to Git Change 1964690 by chui@ocl-promo-incrementor on 2019/07/10 03:00:08
SWDEV-2 - Change OpenCL version number from 2942 to 2943.

Affected files ...

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


[ROCm/clr commit: f4b8358eb6]
2019-07-10 03:10:29 -04:00
Aryan Salmanpour 7a4e3ecc00 [hip][samples] fix a typo in module_api/defaultDriver sample (#1210)
[ROCm/clr commit: b1d8736f4a]
2019-07-10 03:05:19 +00:00
Aryan Salmanpour 3fb7138a61 Fix a compilation error when templated operator<< fails if 'U' type is std::ostream. (#1209)
[ROCm/clr commit: 034e5c0311]
2019-07-10 03:05:04 +00:00
Maneesh Gupta 4c944c9ac5 [ci] Enable tests on ROCm 2.6 (#1208)
[ROCm/clr commit: bb72dd047c]
2019-07-10 03:04:52 +00:00
foreman 6f8ba6d74e P4 to Git Change 1961269 by slinder1@slinder1-fiji-ocllc on 2019/07/09 16:03:15
SWDEV-161424 - Fix broken option handling in Comgr path

	Introduces another potential bug if any options in Options::llvmOptions contain spaces, but this existed before the switch to Comgr.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#50 edit


[ROCm/clr commit: 93c85b966d]
2019-07-09 16:10:34 -04:00
foreman 30b266b2c8 P4 to Git Change 1960804 by chui@ocl-promo-incrementor on 2019/07/09 03:00:08
SWDEV-2 - Change OpenCL version number from 2941 to 2942.

Affected files ...

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


[ROCm/clr commit: 737e74e666]
2019-07-09 03:05:35 -04:00
foreman d259b5ca84 P4 to Git Change 1960615 by gandryey@gera-win10 on 2019/07/08 18:05:10
SWDEV-79445 - HIP generic changes and code clean-up
	- Correct elapsed time calculation. Use event start and end.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#13 edit


[ROCm/clr commit: 3439e27f6d]
2019-07-08 18:14:01 -04:00
darkbuck bd1ba52254 Fix even more typo. (#1204)
[ROCm/clr commit: d0afaff280]
2019-07-08 11:00:51 +00:00
Jatin Chaudhary 6e8edf8890 Adding bounds check before hipMemset (#1190)
* Adding bounds check in ihipMemset

* Adding ihipMemPtrGetInfo to hipMemPtrGetInfo


[ROCm/clr commit: fcb0a3d4e2]
2019-07-08 11:00:38 +00:00
Evgeny Mankov c4928afa45 [HIPIFY] Statistics to CSV file dumping revise
+ Add option -print-stats-csv to dump statistics to CSV file
+ If -o-dir is specified, CSV file will be dumped there
+ Generate 1 summary file sum_stat.csv in case of multiple sources


[ROCm/clr commit: 60a9143d6d]
2019-07-07 20:55:17 +03:00
foreman 40b5f1a0a9 P4 to Git Change 1954476 by chui@ocl-promo-incrementor on 2019/07/07 03:00:07
SWDEV-2 - Change OpenCL version number from 2940 to 2941.

Affected files ...

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


[ROCm/clr commit: 01b3c9a93c]
2019-07-07 03:08:53 -04:00
foreman a2d8515aac P4 to Git Change 1954434 by chui@ocl-promo-incrementor on 2019/07/06 03:00:07
SWDEV-2 - Change OpenCL version number from 2939 to 2940.

Affected files ...

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


[ROCm/clr commit: cf619cedf7]
2019-07-06 03:08:13 -04:00
foreman 1ec1706cc4 P4 to Git Change 1942068 by chui@ocl-promo-incrementor on 2019/07/04 03:00:06
SWDEV-2 - Change OpenCL version number from 2938 to 2939.

Affected files ...

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


[ROCm/clr commit: b1a5dc95c8]
2019-07-04 03:08:21 -04:00
searlmc1 768fca3d42 Fix typo ( T in Vec3_cmp = needs to be int ). (#1203)
Typo introduced here:
commit 1e12e00009
Author: Alex Voicu <alexandru.voicu@amd.com>
Date:   Mon Jun 24 20:02:09 2019 -0500

    Put 3-wide vector types on a ketogenic diet. (#1180)

[ROCm/clr commit: f3bbad0716]
2019-07-04 00:44:26 +00:00
kpyzhov d6b81bc408 Change the type of hipTextureObject_t to pointer to a struct. (#1199)
This is necessary to allow Runtime to perform required texture buffer handling.

[ROCm/clr commit: 43ffe25979]
2019-07-04 00:44:06 +00:00
Jannik 566679ba1d Fix call to cuda library (#1197)
* Remove flags parameter from hipOccupancyMaxPotentialBlockSize

This commit makes the hipOccupancyMaxPotentialBlockSize method consistent with hcc path and the CUDA API.


[ROCm/clr commit: a401997b8e]
2019-07-04 00:43:22 +00:00
Aryan Salmanpour 4b06a21504 [hip] Move _criticalData of ihipStream_t class to private section and use criticalData() to access it (#1177)
[ROCm/clr commit: 7e48231252]
2019-07-04 00:42:19 +00:00
foreman 083dc6fbb0 P4 to Git Change 1940447 by cpaquot@cpaquot-ocl-lc-lnx on 2019/07/03 14:44:49
SWDEV-194872 - [HIP] CUDA and HCC sync after a DeviceToHost async copy.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#60 edit


[ROCm/clr commit: 270c652d0f]
2019-07-03 14:51:15 -04:00
foreman 43a158b0ca P4 to Git Change 1938683 by gandryey@gera-hip-lnx on 2019/07/03 11:20:14
SWDEV-79445 - OCL generic changes and code clean-up
	- Remove old header

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/pro/lnxheaders.h#3 edit


[ROCm/clr commit: 6b7cd4c5ad]
2019-07-03 10:24:10 -05:00
Maneesh Gupta f977bf9278 Fix sample module_api_global for hip-clang (#1201)
module_api_global relies on a HCC only feature which allows host code
to write to device variables. This feature does not exist in CUDA
or hip-clang, which causes the sample not working in CUDA or hip-clang.

This patch fixes the sample by using standard features of CUDA and
hip-clang. The fixed sample works in HCC, CUDA and hip-clang.

[ROCm/clr commit: 3541d18528]
2019-07-03 08:52:19 +00:00
Yaxun (Sam) Liu 2c8502f1db Add __hip_pinned_shadow__ for hip-clang and fix texture reference tests (#1200)
[ROCm/clr commit: 3169f3a881]
2019-07-03 08:51:59 +00:00
Maneesh Gupta 154b861905 Added missing NULL checks and corrected API return values (#1188)
* Added missing NULL checks and corrected API return values as per validation

* Added missing NULL checks


[ROCm/clr commit: a220a8e8e9]
2019-07-03 08:51:39 +00:00
Jatin Chaudhary db5f404b5c Adding new unroll example (#1187)
[ROCm/clr commit: 3cb87cdc46]
2019-07-03 08:51:19 +00:00
Yaxun Sam Liu 79c6028768 Fix sample module_api_global for hip-clang
module_api_global relies on a HCC only feature which allows host code
to write to device variables. This feature does not exist in CUDA
or hip-clang, which causes the sample not working in CUDA or hip-clang.

This patch fixes the sample by using standard features of CUDA and
hip-clang. The fixed sample works in HCC, CUDA and hip-clang.


[ROCm/clr commit: 98648828c0]
2019-07-02 16:36:53 -04:00
foreman 5ff3c0b7ef P4 to Git Change 1929606 by chui@ocl-promo-incrementor on 2019/07/02 03:00:06
SWDEV-2 - Change OpenCL version number from 2937 to 2938.

Affected files ...

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


[ROCm/clr commit: 421f8e1b72]
2019-07-02 03:09:08 -04:00
foreman 98299e6bf2 P4 to Git Change 1928320 by slinder1@slinder1-fiji-ocllc on 2019/07/01 16:20:37
SWDEV-161424 - Always enable and collect Comgr logging

	Restore changelist 1853517, which was backed out in changelist 1861649

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#49 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#29 edit


[ROCm/clr commit: 62c0a6f23e]
2019-07-01 16:23:41 -04:00
foreman 31e08b5d96 P4 to Git Change 1923808 by chui@ocl-promo-incrementor on 2019/06/30 03:00:05
SWDEV-2 - Change OpenCL version number from 2936 to 2937.

Affected files ...

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


[ROCm/clr commit: e4012b8878]
2019-06-30 03:05:05 -04:00
eshcherb 8b74b0e2b2 hip_api_name fixed to be inline to suppress not used warning (#1194)
[ROCm/clr commit: 0218f95c32]
2019-06-30 03:38:43 +00:00
Evgeny Mankov c4396a0aa0 [HIPIFY] Clang 7.1.0 support
+ Provide patch for clang's bug 38811
+ Update Readme.md accordingly


[ROCm/clr commit: b1bc9caef9]
2019-06-29 17:23:18 +03:00
foreman 743fd58bd3 P4 to Git Change 1922102 by chui@ocl-promo-incrementor on 2019/06/29 03:00:04
SWDEV-2 - Change OpenCL version number from 2935 to 2936.

Affected files ...

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


[ROCm/clr commit: 4df681f713]
2019-06-29 03:06:57 -04:00
foreman 46c35fca09 P4 to Git Change 1918811 by vsytchen@vsytchen-remote-ocl-win10 on 2019/06/28 14:47:49
SWDEV-193973 - [OpenCL][NV21] Add support for Navi21

	1. Enable OCLOfflineCompilation for gfx1010/1011/1012.
	2. Skip gfx1030 as there is no support for this target in the device libraries for now.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#80 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/runtime/OCLOfflineCompilation.cpp#21 edit


[ROCm/clr commit: 35b8eb2f0e]
2019-06-28 15:01:03 -04:00
foreman 6a0b041844 P4 to Git Change 1918730 by vsytchen@vsytchen-remote-ocl-win10 on 2019/06/28 14:40:48
SWDEV-193973 - [OpenCL][NV21] Add support for Navi21

	1. Add missing mainline checks

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcounters.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#148 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#88 edit


[ROCm/clr commit: 77b6f9c6e7]
2019-06-28 14:50:33 -04:00
foreman 1e4bf9558c P4 to Git Change 1917740 by cpaquot@cpaquot-ocl-lc-lnx on 2019/06/28 12:03:07
SWDEV-193938 - [HIP] RCCL test fails
	Set default stream to null-stream
	In hipStreamWaitEvent if event_ is null, get the last queued command instead.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#4 edit


[ROCm/clr commit: ccd7799ada]
2019-06-28 12:09:09 -04:00
foreman 6c0d7f9d1a P4 to Git Change 1917655 by vsytchen@vsytchen-remote-ocl-win10 on 2019/06/28 10:05:26
SWDEV-193973 - [OpenCL][NV21] Add support for Navi21

	1. Recognize gfx10.3 in OpenCL.
	2. Don't report nv12/nv12_lite/nv21 for mainline OpenCL.
	3. Disable nv10_lite/nv21_lite for OpenCL (gfx1000/1020 are not supported by LC).

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palbedefs#42 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcounters.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#56 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#147 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/macros.hpp#13 edit


[ROCm/clr commit: 2bc8836012]
2019-06-28 10:14:56 -04:00
foreman 8b83226662 P4 to Git Change 1917620 by yaxunl@yaxunl-lc10 on 2019/06/28 07:57:46
SWDEV-145570 - Fix device name mismatch.

	Not only gfx906 can have device name with +xnack etc.
	Other devices e.g. gfx900 could have that too.
	Make the previous fix more generic.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#33 edit


[ROCm/clr commit: 6768664780]
2019-06-28 08:06:23 -04:00
foreman 1b57fe8cf6 P4 to Git Change 1916766 by chui@ocl-promo-incrementor on 2019/06/28 03:00:05
SWDEV-2 - Change OpenCL version number from 2934 to 2935.

Affected files ...

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


[ROCm/clr commit: c99c79f578]
2019-06-28 03:07:06 -04:00
foreman f4cbe3a464 P4 to Git Change 1914428 by gandryey@gera-win10 on 2019/06/27 18:22:17
SWDEV-79445 - OCL generic changes and code clean-up
	- Remove all compilaiton flags for LC. LC should be selected dynamically only.

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/OPTIONS.def#141 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#146 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#86 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#130 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.cpp#45 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#312 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/macros.hpp#12 edit


[ROCm/clr commit: c3f3ef430f]
2019-06-27 18:24:28 -04:00