AI/rocm-systems
2
0
Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
6 157 коммитов 3 Ветки 0 Теги
b8cc5e4a333363cda1205abdeba0927c06fa708e
Граф коммитов

5443 Коммитов

Автор SHA1 Сообщение Дата
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
Rahul Garg e1e88f3bff Added hipMemset2DAsync support 
[ROCm/hip commit: 3cfb9c0d40]
 2018-04-17 18:27:27 +05:30
Maneesh Gupta e119cc4f85 Merge pull request #400 from gargrahul/hipModule_cleanup 
hip_module code cleanup

[ROCm/hip commit: 33ada06de9]
 2018-04-17 09:00:15 +05:30
Aaron Enye Shi 608a68fe74 Clean up triple_to_hsa_isa naming (#403) 
[ROCm/hip commit: 5a80c16cd2]
 2018-04-17 06:47:55 +05:30
foreman 68e33fdf84 P4 to Git Change 1541938 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/16 18:27:17 
SWDEV-145570 - [HIP] Set/GetDevice and Create/DestroyTextureObject
	Implemented Set/GetDevice relying on g_context (current context)
	Implemented create linear/2D texture object function
	Implemented hipDestroyTextureObject

Affected files ...

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


[ROCm/hip commit: 250e08f31f]
 2018-04-16 18:37:17 -04:00
Rahul Garg 372e2016d1 hip_module code cleanup 
-Fixed missing ihipLogStatus in hipModuleLoad()
-Fixed some ihipXXX functions


[ROCm/hip commit: 1446f78799]
 2018-04-16 15:35:04 +05:30
Aaron Enye Shi 4074ed9fc6 Fix bug when using older rocr naming (#399) 
[ROCm/hip commit: 1a281240d6]
 2018-04-14 15:47:46 +05:30
foreman f064799323 P4 to Git Change 1541197 by skudchad@skudchad_test2_win_opencl on 2018/04/13 17:49:07 
SWDEV-145570 - [HIP] -  Add missing HIP APIs and  fill sym table references. The HIP tests can now build if we do a symlink to libhip_hcc.so that we build with VDI in the install folder in github HIP.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_profile.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#3 edit


[ROCm/hip commit: e6718d9747]
 2018-04-13 18:19:28 -04:00
Aaron Enye Shi 28ff48c951 Fix new gfx target naming convention (#397) 
This was introduced in recent xnack changes naming changes which affected our offload bundler. This patch will fix issues in HIP samples, ROCR tests, and others.

[ROCm/hip commit: ab7e727fa2]
 2018-04-13 16:24:39 +05:30
Maneesh Gupta 29c54aa96a Merge pull request #395 from lmoriche/master 
Add missing __device__ function attributes.

[ROCm/hip commit: bda18af06d]
 2018-04-12 14:51:32 +05:30
Maneesh Gupta cc03530896 Merge pull request #393 from mangupta/cmake_update_deps 
[cmake] Update target build dependencies

[ROCm/hip commit: 97f67ced66]
 2018-04-12 14:36:49 +05:30
Rahul Garg 89511823f0 Correct missed ihipMemsetCopyDataType change 
[ROCm/hip commit: 16c89d101a]
 2018-04-12 10:27:19 +05:30
Rahul Garg abe14442a5 Changed ihipMemsetCopyDataType to ihipMemsetDataType 
[ROCm/hip commit: 3d6eb75828]
 2018-04-12 09:29:22 +05:30
Laurent Morichetti 3d9e3019d0 Add missing __device__ function attributes. 
[ROCm/hip commit: 211c18e674]
 2018-04-11 09:29:37 -07:00
Rahul Garg 6c4236dfb6 Fix hipMemset stream resolution 
[ROCm/hip commit: 294bf50f68]
 2018-04-11 19:01:53 +05:30
Rahul Garg 36c6e0019d hipMemset refactoring 
[ROCm/hip commit: 412a35be20]
 2018-04-11 15:58:48 +05:30
Maneesh Gupta 01e4cf1c68 [cmake] Update target build dependencies 
Change-Id: Ib1c34135c0d04f88daa695e7a90272225d7e64b0


[ROCm/hip commit: b1be325745]
 2018-04-11 15:30:13 +05:30
Maneesh Gupta 177cf7fea5 Merge pull request #391 from lmoriche/master 
Create one hipModule_t per device

[ROCm/hip commit: 7c43396596]
 2018-04-11 13:06:58 +05:30
foreman f768306d03 P4 to Git Change 1539198 by skudchad@skudchad_test2_win_opencl on 2018/04/10 17:32:14 
SWDEV-145570 - [HIP] -  Add HIP API skeletons for Peer and memory

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_peer.cpp#1 add


[ROCm/hip commit: 04decb72fc]
 2018-04-10 17:41:24 -04:00
Laurent Morichetti 10f3cc1f27 Create one hipModule_t per device 
[ROCm/hip commit: 91f996035c]
 2018-04-10 08:57:34 -07:00
Maneesh Gupta a7f4ee044f Merge pull request #390 from mangupta/hipmemcpy_fix 
hipMemcpyAsync returns success when trying to copy 0 bytes

[ROCm/hip commit: 399a17d755]
 2018-04-09 14:02:36 +05:30
Maneesh Gupta 9d80544e28 Merge pull request #388 from lmoriche/master 
Add support for clang offload bundles and <<<>>> kernel launch.

[ROCm/hip commit: ac7c5dfd0b]
 2018-04-09 12:40:28 +05:30
Maneesh Gupta 4077c681c9 hipMemcpyAsync returns success when trying to copy 0 bytes 
Change-Id: I4c0ee7ccc7563e2df657b50356cdd7fec9a1ef15


[ROCm/hip commit: 03eca1c57e]
 2018-04-09 12:39:44 +05:30
Maneesh Gupta 5c6d2e9c3a [ci] Disable nvcc CI builds 
[ROCm/hip commit: 4ac59148a9]
 2018-04-09 12:23:56 +05:30
foreman 0e4817fc7d P4 to Git Change 1537729 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/06 17:59:29 
SWDEV-145570 - [HIP] Use Svm path for both hipMalloc and hipHostMalloc
	Make sure hipMemCpy uses SvmBuffer to fetch the cl_mem

Affected files ...

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


[ROCm/hip commit: e7f206d249]
 2018-04-06 18:08:18 -04:00
Siu Chi Chan 83343a2bba adjust the hcc work week for the texture fix 
[ROCm/hip commit: f48e471dd4]
 2018-04-06 15:46:55 -04:00
Laurent Morichetti de2f2a87ff Don't include __clang_cuda_builtin_vars.h 
[ROCm/hip commit: bc6fa2bc62]
 2018-04-05 16:27:05 -07:00
foreman 0093f50049 P4 to Git Change 1537232 by skudchad@skudchad_rocm on 2018/04/05 15:00:24 
SWDEV-145570 - [HIP] - Fix typo and fix build.

Affected files ...

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


[ROCm/hip commit: ce88da9c1b]
 2018-04-05 15:12:53 -04:00
foreman 741b97f54b P4 to Git Change 1537228 by skudchad@skudchad_test2_win_opencl on 2018/04/05 14:53:31 
SWDEV-145570 - [HIP] -  Add HIP Memory, texture, surface, context api skeletons

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_surface.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#1 add


[ROCm/hip commit: 204ecba4b6]
 2018-04-05 15:02:43 -04:00
foreman 14251122d1 P4 to Git Change 1536925 by vsytchen@vsytchen-ocl-win10 on 2018/04/04 17:20:38 
SWDEV-79445 - OCL generic changes and code clean-up

	1. This change replaces the use of std::map with std::unordered_map to improve lookup/insert time.
	2. Replace the use of std::make_pair and std::pair constructor with uniform initialization for cleaner code.
	3. Replace the use of std::Container::iterator type with the auto keyword for cleaner code.
	4. Use range based for loops where needed.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_context.cpp#58 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d10.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d10_amd.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d11.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d11_amd.hpp#13 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d9.cpp#34 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d9_amd.hpp#17 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_gl.cpp#57 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_pipe.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#46 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/appprofile.hpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/cpu/cpuprogram.cpp#72 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/cpu/cpuvirtual.cpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#216 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#297 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuappprofile.cpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpubinary.cpp#59 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpucompiler.cpp#158 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#587 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#322 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprintf.cpp#46 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#237 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#70 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.cpp#242 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#415 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.hpp#143 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palappprofile.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcompiler.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#79 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#59 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#60 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#46 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/CMakeLists.txt#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/pro/prodevice.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/pro/prodevice.hpp#5 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocbinary.hpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#42 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccounters.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprintf.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#81 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#81 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#89 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.cpp#49 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.hpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.cpp#129 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.hpp#102 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/perfctr.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.cpp#91 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.hpp#43 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/sampler.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.cpp#17 edit


[ROCm/hip commit: 15f11c983f]
 2018-04-04 18:00:17 -04:00
Laurent Morichetti 9e1d2064c9 Add support for clang offload bundles and <<<>>> kernel launch. 
[ROCm/hip commit: 0c1893ea62]
 2018-04-04 13:32:33 -07:00
foreman 70fd3504cc P4 to Git Change 1536698 by skudchad@skudchad_test2_win_opencl on 2018/04/04 13:18:19 
SWDEV-145570 - [HIP] -  Add HIP Memory api skeletons

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

Affected files ...

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


[ROCm/hip commit: 4574e01740]
 2018-04-04 13:24:15 -04:00
Maneesh Gupta 4ee5ce1c40 Cleanup bin directory 
Remove hccgenco.sh and hsa-api-filter-cxl.txt

Change-Id: I5942aec911a2fe6c871fe0eb5f44a0b243552b79


[ROCm/hip commit: 228fae1224]
 2018-04-04 14:31:40 +05:30