6425 Коммитов

Автор SHA1 Сообщение Дата
Evgeny Mankov f40a69409b [HIPIFY][test] add cuDNN test
[ROCm/hip commit: a56b480c5e]
2018-05-04 12:37:15 +03:00
Evgeny Mankov 61d95e4b42 [HIPIFY][doc] Readme.md update
+ supported CUDA version to LLVM version correspondence table is added.
+ Test section is rewritten.
+ Windows support is added.


[ROCm/hip commit: 054c3f71f0]
2018-05-04 10:50:18 +03:00
foreman 263a583c01 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/hip commit: 0508a4ed37]
2018-05-03 21:26:33 -04:00
foreman 0c52fe6234 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/hip commit: 99d3444f00]
2018-05-03 18:56:01 -04:00
foreman 2f4bfed956 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/hip commit: 3ad5f2a01b]
2018-05-03 18:26:45 -04:00
Evgeny Mankov 057b13fc4a [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/hip commit: fe421c89b2]
2018-05-03 11:33:40 +03:00
Evgeny Mankov 1b652107f7 Merge pull request #417 from emankov/master
[HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)

[ROCm/hip commit: e1d1835798]
2018-05-03 10:45:51 +03:00
Lakhan Singh 51dbf4f5ca Null checks added for hipmallocpitch and hipmemcpy apis
[ROCm/hip commit: 6411ca1f6d]
2018-05-03 09:27:50 +05:30
foreman 7b03ff80d4 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/hip commit: a10512c510]
2018-05-02 22:25:53 -04:00
foreman 129f0a9d0f 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/hip commit: 445d300d63]
2018-05-02 21:08:53 -04:00
foreman 7d6c9d4602 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/hip commit: 0ddf288904]
2018-05-02 19:14:52 -04:00
Rahul Garg e687245eb0 Cleaned up
[ROCm/hip commit: b4585a2a90]
2018-05-02 12:54:17 +05:30
Rahul Garg ab1dabe61b Fix texture 3D for HIP/NVCC
[ROCm/hip commit: 9de5f23d54]
2018-05-02 11:56:37 +05:30
foreman 01296ff827 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/hip commit: 5f549b62e8]
2018-05-01 19:01:10 -04:00
foreman 07cc8f7a6d 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/hip commit: 9c7b328101]
2018-05-01 18:46:32 -04:00
foreman 0e2eaa1aa1 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/hip commit: 61378a359c]
2018-05-01 18:10:09 -04:00
Maneesh Gupta c41d423404 Merge pull request #420 from ROCm-Developer-Tools/sunway513-patch-1
Update hip_bugs.md

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

[ROCm/hip commit: adcd8553c3]
2018-05-01 12:42:50 +05:30
Maneesh Gupta 825c697d32 Merge pull request #414 from aaronenyeshi/patch-1
Remove unsupported targets gfx801 and gfx802

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

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

[ROCm/hip commit: caa13f98ed]
2018-05-01 12:23:22 +05:30
Maneesh Gupta b40c05e452 Merge pull request #411 from luckynikki/SWDEV-141024
SWDEV-141024

[ROCm/hip commit: d2a51ee651]
2018-05-01 09:29:26 +05:30
Maneesh Gupta 93fc0a8312 Merge pull request #406 from gargrahul/fix_tex1D_coordinate_type
Resolve tex1D float to int conversion issue

[ROCm/hip commit: 365d155774]
2018-05-01 09:18:11 +05:30
foreman e6c77307b7 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/hip commit: dc1497535d]
2018-04-30 21:20:26 -04:00
foreman 7a594eacaa 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/hip commit: 213f721318]
2018-04-30 20:17:46 -04:00
foreman cffb35e422 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/hip commit: 6f7e33cb91]
2018-04-30 14:55:41 -04:00
foreman 5695bb3ca8 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/hip commit: 36d2d37804]
2018-04-30 13:34:32 -04:00
Peng 919254839a Update hip_bugs.md
Remove several out-date links in hip_bugs.md document

[ROCm/hip commit: 2e76f563cd]
2018-04-30 09:36:37 -05:00
foreman 9bbba2ee75 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/hip commit: 5fc5d098a9]
2018-04-30 01:03:06 -04:00
foreman b51c887a83 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/hip commit: 1cb879968b]
2018-04-29 15:04:45 -04:00
foreman c3847507d9 P4 to Git Change 1547563 by lmoriche@lmoriche_opencl_dev2 on 2018/04/27 21:10:47
SWDEV-145570 - [HIP] - Add support for HCC compiled binaries.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elf_types.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_dump.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_dynamic.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_header.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_note.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_relocation.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_section.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_segment.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_strings.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_symbols.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_utils.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#7 edit


[ROCm/hip commit: 2605d50ce7]
2018-04-27 21:21:31 -04:00
Deven Desai 43c2724907 Fixing a copy/paste error in my previous checkin
[ROCm/hip commit: 76a7d7e374]
2018-04-27 12:59:51 +00:00
Deven Desai 2b3332ac72 Checkin to add unit tests for fixes in my previous commit
This change adds unit tests for

1. __hisinf
2. __hisnan
2. abs(long long)
3. lgamma(double)


[ROCm/hip commit: 4be4cf644f]
2018-04-25 17:53:21 +00:00
foreman 67731a083a P4 to Git Change 1546224 by skudchad@skudchad_test2_win_opencl on 2018/04/25 12:24:40
SWDEV-145570 - [HIP] - Add hipMemcpyTo/FromArray APIs.

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

Affected files ...

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


[ROCm/hip commit: 18c7c164c6]
2018-04-25 12:32:11 -04:00
Rahul Garg c1b94eb29f Fix gcc build issues for host code
[ROCm/hip commit: 639001933c]
2018-04-25 12:30:11 +05:30
foreman 066a072226 P4 to Git Change 1545859 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/24 16:44:17
SWDEV-145570 - [HIP] Get hipCtx_simple to pass
	Implemented hipCtxGetDevice
	hipCtxCreate must push the created context onto the context stack
	hipCtxDestroy must check if the top of the stack is the context being destroy
	and not just pop the top of the stack w/o checking.

Affected files ...

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


[ROCm/hip commit: d2fbde728c]
2018-04-24 16:49:38 -04:00
Paul 8643ed5ca9 Add host and device targets
[ROCm/hip commit: 516d92f4d7]
2018-04-24 14:04:24 -05:00
Evgeny Mankov 6b53512635 [HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)
Execution Control [deprecated since 7.0]:
cudaConfigureCall -> hipConfigureCall
cudaLaunch -> hipLaunchByPtr
cudaSetupArgument -> hipSetupArgument

Surfaces (partially):
cudaSurfaceObject_t -> hipSurfaceObject_t
cudaSurfaceBoundaryMode -> hipSurfaceBoundaryMode
cudaCreateSurfaceObject -> hipCreateSurfaceObject
cudaDestroySurfaceObject -> hipDestroySurfaceObject

Memory Management:
cudaMemset2DAsync -> hipMemset2DAsync


[ROCm/hip commit: 6f501f6094]
2018-04-24 22:04:04 +03:00
Deven Desai 16d2b986aa Checkin to fix bugs in math functions.
This change fixes the following bugs that were discovered while debuggnig TF unit test failures (cwise_ops_test)

1. __hisinf and __hisnan routines
   Both had incorrect implementations.

2. abs
   A "long long" (64bit int) version was missing, resulting in the 32bit version being used for 64bit ints (which resulted in incorrect results, when the value passed in was outside the 32bit int range)

3. lgamma
  We seemed to have a custom version for the 'double' datatype (which was giving incorrect results). Replaced it with a call to the 'double' version of the underlying 'hc::precision_math::lgamma'


[ROCm/hip commit: af586bbbf2]
2018-04-24 18:10:07 +00:00
foreman f4b08ad496 P4 to Git Change 1545750 by skudchad@skudchad_test2_win_opencl on 2018/04/24 13:55:57
SWDEV-145570 - [HIP] - Add some hip_mem* APIs. Part 2.

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

Affected files ...

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


[ROCm/hip commit: 13355e5de5]
2018-04-24 14:05:20 -04:00
Aaron Enye Shi 583942c3cb Remove unsupported targets gfx801 and gfx802
These architectures are no longer supported. Should not compile for them.

[ROCm/hip commit: 433866eb60]
2018-04-23 15:25:35 -04:00
Evgeny Mankov 540fc92b1c [HIPIFY] undo apply .clangformat to HIPIFY source files
[ROCm/hip commit: 8499e79e2b]
2018-04-23 20:22:15 +03:00
foreman 1cafd8bd20 P4 to Git Change 1544858 by skudchad@skudchad_rocm on 2018/04/22 21:07:25
SWDEV-144570 - [HIP] - Fix a few APIs and typos.

Affected files ...

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


[ROCm/hip commit: 66640b546f]
2018-04-22 21:17:27 -04:00
Rahul Garg 6538884ebe Added deprecation note in cuCtx section
[ROCm/hip commit: 39b5b07dc3]
2018-04-20 22:43:58 +05:30
Rahul Garg c4df5688c4 Moved deprecated macro to the end
[ROCm/hip commit: 19cb6c61ab]
2018-04-20 21:57:23 +05:30
Lakhan Singh 701de3092b SWDEV-141024
[ROCm/hip commit: 1c2509dc04]
2018-04-20 17:40:00 +05:30
Rahul Garg 3b4875ba77 Mark hipCtx APIs as deprecated
[ROCm/hip commit: a039dbf2dd]
2018-04-20 17:34:48 +05:30
foreman 10d96d33ce P4 to Git Change 1544061 by skudchad@skudchad_test2_win_opencl on 2018/04/19 18:24:45
SWDEV-145570 - [HIP] - Add some hip_mem* APIs

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

Affected files ...

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


[ROCm/hip commit: 3ce752065a]
2018-04-19 18:35:00 -04:00
foreman 07285483d9 P4 to Git Change 1543751 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/19 11:17:02
SWDEV-145570 - [HIP] Implemented a bunch of texture APIs

Affected files ...

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


[ROCm/hip commit: 63babe9e66]
2018-04-19 12:27:09 -04:00
Rahul Garg 80d7e34418 Resolve tex1D float to int conversion issue
[ROCm/hip commit: ffe18d1505]
2018-04-18 14:15:18 +05:30