Граф коммитов

5495 Коммитов

Автор SHA1 Сообщение Дата
Aaron Enye Shi 3d3356a2ed Fix hipMathFunction for gfx906
[ROCm/clr commit: 4488f9f7a7]
2018-05-11 10:53:07 -04:00
Alex Voicu 2973f68465 Don't use magic constants, they're evil.
Also clarify that the register count cannot be queried at the moment.

[ROCm/clr commit: eded014abc]
2018-05-11 11:31:46 +01:00
Alex Voicu 4e6996282d Add support for the hipFuncGetAttributes interface.
[ROCm/clr commit: bf9529aaa8]
2018-05-11 03:35:10 +01:00
Siu Chi Chan 04bf6c5109 initial gfx906 support
[ROCm/clr commit: 368affcea4]
2018-05-10 19:28:00 +00:00
Evgeny Mankov f7d2e7bbe7 [HIPIFY][DNN] support of cuDNN 7.1.3 - continuation
- not finished yet.
- based on https://github.com/ROCmSoftwarePlatform/hipDNN.
- testing on https://github.com/baidu-research/DeepBench.


[ROCm/clr commit: b31df9cc60]
2018-05-10 17:36:51 +03:00
foreman 39ea36a458 P4 to Git Change 1552807 by skudchad@skudchad_test2_win_opencl on 2018/05/09 18:08:07
SWDEV-145570 - [HIP] - Release a stream first before taking it off from the set.
	- Queue::create() needs to be called before returning a valid queue.

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

Affected files ...

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


[ROCm/clr commit: 1426982a65]
2018-05-09 18:15:41 -04:00
foreman 970febab07 P4 to Git Change 1552209 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/08 20:24:32
SWDEV-145570 - [HIP] Use the as_amd()->asHostQueue with streamSet

Affected files ...

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


[ROCm/clr commit: d4bb6a0a11]
2018-05-08 20:30:17 -04:00
foreman 24e9cf40cc P4 to Git Change 1552198 by skudchad@skudchad_rocm on 2018/05/08 18:57:32
SWDEV-145570 - [HIP] - Synchronize the legacy default stream with other blocking streams as per the spec.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#5 edit


[ROCm/clr commit: 813c770d73]
2018-05-08 19:04:35 -04:00
Yaxun (Sam) Liu 7d7125195c Fix warning about inlined function is not defined
[ROCm/clr commit: 4c2d2b9e69]
2018-05-08 16:38:50 -04:00
foreman f894b68a7d P4 to Git Change 1552011 by skudchad@skudchad_test2_win_opencl on 2018/05/08 14:48:45
SWDEV-145570 - [HIP] Fix offset calculation when getting a memory object. Also include case when destination VA may just be a CPU host VA and not nessarily device alloced.
	- Fix hipMemset* to write each byte and now a dword as per the spec

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

Affected files ...

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


[ROCm/clr commit: 434912d2ca]
2018-05-08 15:43:13 -04:00
Yaxun (Sam) Liu cd2b1f1baf Add __assert_fail, __device_trap and hipErrorAssert for clang
[ROCm/clr commit: eeedfc5567]
2018-05-08 15:42:27 -04:00
Siu Chi Chan 16d8a56909 add intrinsics mbcnt_lo, mbcnt_hi, lane_id
[ROCm/clr commit: 4f12ddea8f]
2018-05-08 13:43:53 -04:00
Evgeny Mankov 912494f3fe [HIPIFY][Blas] Sync with CUDA 9.1
[ROCm/clr commit: 57d9ced72a]
2018-05-08 20:42:30 +03:00
Evgeny Mankov 6e6f6f630d [HIPIFY] Sync with hipBLAS
[ROCm/clr commit: 089ac77b97]
2018-05-08 19:20:47 +03:00
Rahul Garg a7be5be448 Added hipMemset3D
[ROCm/clr commit: 78568435da]
2018-05-07 10:24:30 +05:30
Tom Maenan Read Cutting f0e89ba61e Add space between ### and Notes in hip_terms
Makes `Notes` an H3 heading.

[ROCm/clr commit: 06538c2b6d]
2018-05-05 13:30:11 +01:00
foreman 72312f6cc9 P4 to Git Change 1550648 by skudchad@skudchad_test2_win_opencl on 2018/05/04 20:56:00
SWDEV-145570 - [HIP]
	- Implement hipMemcpyHtoD/DtoH/DtoD/ and their Async APIs
	- Combine logic for hipMemset/Memcpy/Memset2D/Memcpy2D that can be shared across multiple APIs

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

Affected files ...

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


[ROCm/clr commit: 6b7ec8f427]
2018-05-05 00:34:05 -04:00
emankov 98ca496432 [HIPIFY][test] Undo commit "Apply .clangformat to all repo source files"
Commit broke tests due to code and comments formatting changes, thus FileCheck fails on checks, which are in comments.


[ROCm/clr commit: 0d756720b2]
2018-05-04 22:23:16 +03:00
foreman 46dc10bdd8 P4 to Git Change 1550526 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/04 15:00:44
SWDEV-145570 - [HIP] Missing HIP_INIT_API macro in hipDeviceSynchronize.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#9 edit


[ROCm/clr commit: 05b48c7450]
2018-05-04 15:12:48 -04:00
foreman 5ab0c5758c P4 to Git Change 1550486 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/04 14:00:33
SWDEV-145570 - [HIP] Fix multithread init
	Make the g_ihipInitialized variable per thread
	And make sure to assign a default g_context

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#9 edit


[ROCm/clr commit: a6c58d73f6]
2018-05-04 14:13:13 -04:00
Evgeny Mankov 5ddc1b37a6 [HIPIFY][test] add cuDNN test
[ROCm/clr commit: 0bf8e42caa]
2018-05-04 12:37:15 +03:00
Evgeny Mankov 19106d767e [HIPIFY][doc] Readme.md update
+ supported CUDA version to LLVM version correspondence table is added.
+ Test section is rewritten.
+ Windows support is added.


[ROCm/clr commit: b6d4c7cfe6]
2018-05-04 10:50:18 +03:00
foreman de2b0d5bba P4 to Git Change 1550010 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/03 21:16:06
SWDEV-145570 - [HIP] Fixed region initialization

Affected files ...

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


[ROCm/clr commit: f404808c04]
2018-05-03 21:26:33 -04:00
foreman 9d351947ec P4 to Git Change 1549971 by skudchad@skudchad_rocm on 2018/05/03 18:39:37
SWDEV-145570 - [HIP] -  Fix build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#21 edit


[ROCm/clr commit: d6ffa28a5f]
2018-05-03 18:56:01 -04:00
foreman c3ff6cb312 P4 to Git Change 1549965 by skudchad@skudchad_test2_win_opencl on 2018/05/03 18:15:18
SWDEV-145570 - [HIP] -  Minor fixes. Use coarse grain for hipMallocPitch

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

Affected files ...

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


[ROCm/clr commit: f1f8ea8266]
2018-05-03 18:26:45 -04:00
Evgeny Mankov d008022018 [HIPIFY] Initial cuDNN support
- based on https://github.com/ROCmSoftwarePlatform/hipDNN.
- lit testing was supplemented with CUDA_DNN_ROOT_DIR for cuDNN testing.
- single cuDNN test was added.


[ROCm/clr commit: 4d19bd1da5]
2018-05-03 11:33:40 +03:00
Evgeny Mankov b7cbef22de Merge pull request #417 from emankov/master
[HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)

[ROCm/clr commit: 0ad4d520ed]
2018-05-03 10:45:51 +03:00
Lakhan Singh 6278830c1a Null checks added for hipmallocpitch and hipmemcpy apis
[ROCm/clr commit: 12d8a47c0c]
2018-05-03 09:27:50 +05:30
foreman 8ea8ef1836 P4 to Git Change 1549067 by skudchad@skudchad_rocm on 2018/05/02 17:40:37
SWDEV-145570 - [HIP] - Fix build

Affected files ...

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


[ROCm/clr commit: 16f6cf55e9]
2018-05-02 22:25:53 -04:00
foreman d607c40410 P4 to Git Change 1549060 by skudchad@skudchad_test2_win_opencl on 2018/05/02 17:36:53
SWDEV-145570 - [HIP] - Add hipMemcpyDeviceToDevice/hipMemcpyHostToHost/hipMemcpyDefault cases to hipMemcpy/hipMemcpyAsync, hipMemset2DAsync

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

Affected files ...

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


[ROCm/clr commit: ed35f0693f]
2018-05-02 21:08:53 -04:00
foreman a6af6ea8d7 P4 to Git Change 1549012 by lmoriche@lmoriche_opencl_dev2 on 2018/05/02 16:56:02
SWDEV-145570 - [HIP] - Add hipMemset2DAsync, fix the HCC triple for device binaries (make sure to update to the latest HCC).

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#10 edit


[ROCm/clr commit: 57a05ba4d5]
2018-05-02 19:14:52 -04:00
Rahul Garg db7e579529 Cleaned up
[ROCm/clr commit: 976b9ed200]
2018-05-02 12:54:17 +05:30
Rahul Garg 6f05c37cde Fix texture 3D for HIP/NVCC
[ROCm/clr commit: 1d76c48e3d]
2018-05-02 11:56:37 +05:30
foreman 8bd2c78f00 P4 to Git Change 1548560 by skudchad@skudchad_rocm on 2018/05/01 18:53:54
SWDEV-145570 - [HIP] - Fix hipDeviceSynchronize.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#8 edit


[ROCm/clr commit: 6bd6d3d4c1]
2018-05-01 19:01:10 -04:00
foreman cdc8f6b9cc P4 to Git Change 1548558 by skudchad@skudchad_test2_win_opencl on 2018/05/01 18:39:58
SWDEV-145570 - [HIP] -  Implement some of hipMem*Async and hipMemSet2D APIs. Part 4.

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

Affected files ...

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


[ROCm/clr commit: 4a081cbc2f]
2018-05-01 18:46:32 -04:00
foreman eea99696ec P4 to Git Change 1548476 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/01 15:50:51
SWDEV-145570 - [HIP]
	Added support for null stream avoiding creating/destroying dummy streams.
	Added basic event class for hipEvent* support.
	Refactored some common functionality: No more direct access to g_context.
	Support hipStreamSynchronize(0).

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#8 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#7 edit


[ROCm/clr commit: c874bb2b90]
2018-05-01 18:10:09 -04:00
Maneesh Gupta db489e63b0 Merge pull request #420 from ROCm-Developer-Tools/sunway513-patch-1
Update hip_bugs.md

[ROCm/clr commit: e1af82d81e]
2018-05-01 12:43:01 +05:30
Maneesh Gupta d6f360e65d Merge pull request #419 from gargrahul/fix_hip_gcc_host_build
Fix gcc build issues for host code

[ROCm/clr commit: 2e6b46f308]
2018-05-01 12:42:50 +05:30
Maneesh Gupta 6183085a89 Merge pull request #414 from aaronenyeshi/patch-1
Remove unsupported targets gfx801 and gfx802

[ROCm/clr commit: fb82411b23]
2018-05-01 12:38:49 +05:30
Maneesh Gupta 9ac65ca55c Merge pull request #415 from deven-amd/master
Checkin to fix bugs in math functions.

[ROCm/clr commit: af0c227df4]
2018-05-01 12:29:03 +05:30
Maneesh Gupta 1bc33c9356 Merge pull request #410 from gargrahul/hipCtx_deprecation_warning
Mark hipCtx APIs as deprecated

[ROCm/clr commit: f8431772a8]
2018-05-01 12:23:22 +05:30
Maneesh Gupta 56a1a3e232 Merge pull request #411 from luckynikki/SWDEV-141024
SWDEV-141024

[ROCm/clr commit: 1a5c72885a]
2018-05-01 09:29:26 +05:30
Maneesh Gupta 60a66aa10d Merge pull request #406 from gargrahul/fix_tex1D_coordinate_type
Resolve tex1D float to int conversion issue

[ROCm/clr commit: 885e51e1a5]
2018-05-01 09:18:11 +05:30
foreman 5bf9bda231 P4 to Git Change 1548145 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/30 21:15:56
SWDEV-145570 - [HIP] Handle hStream=nullptr case

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#7 edit


[ROCm/clr commit: 7e5c7954b9]
2018-04-30 21:20:26 -04:00
foreman 1db82364e8 P4 to Git Change 1548038 by lmoriche@lmoriche_opencl_dev2 on 2018/04/30 15:55:18
SWDEV-145570 - [HIP] Fix kernel disptach for HCC compiled programs.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#6 edit


[ROCm/clr commit: 12c490ff1d]
2018-04-30 20:17:46 -04:00
foreman e3e5e23762 P4 to Git Change 1547830 by skudchad@skudchad_test2_win_opencl on 2018/04/30 12:03:10
SWDEV-145570 - [HIP] - Add couple of hip_mem* APIs. Part 3.

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

Affected files ...

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


[ROCm/clr commit: 88f8260277]
2018-04-30 14:55:41 -04:00
foreman 067ff5f823 P4 to Git Change 1547825 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/30 11:59:32
SWDEV-145570 - [HIP] Fixed release build

Affected files ...

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


[ROCm/clr commit: bc34be99d2]
2018-04-30 13:34:32 -04:00
Peng 465fb7a03d Update hip_bugs.md
Remove several out-date links in hip_bugs.md document

[ROCm/clr commit: ac591da0dd]
2018-04-30 09:36:37 -05:00
foreman dca97e71f2 P4 to Git Change 1547686 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/30 00:52:23
SWDEV-145570 - [HIP] CreateTexture with hipArray

Affected files ...

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


[ROCm/clr commit: ad390dbe6d]
2018-04-30 01:03:06 -04:00
foreman c9bf543320 P4 to Git Change 1547669 by lmoriche@lmoriche_opencl_dev2 on 2018/04/29 14:53:31
SWDEV-145570 - [HIP] Fix kernel disptach for HCC compiled programs.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#34 edit


[ROCm/clr commit: 9f4d0049aa]
2018-04-29 15:04:45 -04:00