Commit Graph

51 Commits

Author SHA1 Message Date
foreman 00680db557 P4 to Git Change 1766349 by michliao@hliao-dev-00-hip.rocm-workspace on 2019/04/05 14:24:45
SWDEV-144570 - Fix pointer attribute query.

	- For memory not registered with runtime, return
	  `hipErrorInvalidValue`. That's the behavior expected to check whether
	  a host buffer is pinned.
	- Return `hipErrorInvalidDevice` in case a registered memory object
	  cannot find its matching device.

	RB: http://ocltc.amd.com/reviews/r/17094/

Affected files ...

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


[ROCm/clr commit: f695910290]
2019-04-05 14:51:37 -04:00
foreman a0f0714729 P4 to Git Change 1766264 by cpaquot@cpaquot-ocl-lc-lnx on 2019/04/05 11:38:18
SWDEV-145570 - [HIP] Use a context with all devices in system for host register
	hipHostRegister and hipMemcpy 0x10 and 0x20 fail in mGPU systems because
	we only register the memory on the current device. But in HIP, the registering
	needs to happen on all devices.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#26 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#50 edit


[ROCm/clr commit: 7a58581c81]
2019-04-05 11:58:25 -04:00
foreman df8687b499 P4 to Git Change 1766076 by michliao@hliao-dev-00-hip.rocm-workspace on 2019/04/04 17:35:28
SWDEV-144570 - Fix pointer attribute query.

	- Device should be numbered from zero.

	RB: http://ocltc.amd.com/reviews/r/17090/

Affected files ...

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


[ROCm/clr commit: 3b461e01ae]
2019-04-04 17:50:08 -04:00
foreman 1251ab0181 P4 to Git Change 1764069 by michliao@hliao-dev-00-hip-workspace on 2019/04/01 11:23:34
SWDEV-144570 - Handle zero-byte memset & memcpy

	- Properly handle zero-byte memset & memcpy by skipping the real stuff.

	RB: http://ocltc.amd.com/reviews/r/17062/

Affected files ...

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


[ROCm/clr commit: 6220c5059d]
2019-04-01 11:51:06 -04:00
foreman 707f3ec6ed P4 to Git Change 1759248 by cpaquot@cpaquot-ocl-lc-lnx on 2019/03/20 18:32:19
SWDEV-183452 - [HIP] Typo of | instead of &

Affected files ...

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


[ROCm/clr commit: 9682f81a75]
2019-03-20 19:18:10 -04:00
foreman 95c6f8fed5 P4 to Git Change 1759224 by cpaquot@cpaquot-ocl-lc-lnx on 2019/03/20 17:47:43
SWDEV-183452 - [HIP] PyTorch test_pin_memory fails
	hipPointerGetAttributes should return hipMemoryTypeHost for hipHostMalloc memories.

Affected files ...

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


[ROCm/clr commit: a63b38c304]
2019-03-20 18:43:07 -04:00
foreman bad53fbdd3 P4 to Git Change 1757948 by kjayapra@1_HIPWS_SL_IPC on 2019/03/18 18:29:24
SWDEV-144570 - Implementation of
	               hipMemcpyToSymbol, hipMemcpyFromSymbol,
	               hipMemcpyToSymbolAsync, hipMemcpyFromSymbolAsync,
	               hipGetSymbolAddress, hipModuleGetGlobal

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#12 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#23 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#45 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#20 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#101 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#45 edit


[ROCm/clr commit: e432cfb2e9]
2019-03-18 18:44:55 -04:00
foreman deeefffff5 P4 to Git Change 1752994 by kjayapra@2_HIPWS_SL_D32 on 2019/03/07 14:06:54
SWDEV-145570 - Implementation of ihipMemsetD32 and ihipMemsetD32Async
	       HIP-HCC Info: https://github.com/ROCm-Developer-Tools/HIP/pull/933

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#11 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#12 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#44 edit


[ROCm/clr commit: 1f45d27b9f]
2019-03-07 14:58:49 -05:00
foreman 33214c5e42 P4 to Git Change 1736033 by kjayapra@9_HIPWS_IPCCHKIN on 2019/01/25 17:44:48
SWDEV-145570 - IPC Mem Handle Changes for HIP.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#20 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#43 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#330 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#112 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#42 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.hpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.hpp#108 edit


[ROCm/clr commit: c22af4142d]
2019-01-25 19:18:53 -05:00
foreman 427070ef47 P4 to Git Change 1728676 by cpaquot@cpaquot-ocl-lc-lnx on 2019/01/10 14:29:52
SWDEV-145570 - [HIP] Add API tracing, enabled via LOG_LEVEL=3

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#19 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#42 edit
... //depot/stg/opencl/drivers/opencl/api/hip/trace_helper.h#1 add


[ROCm/clr commit: 427327b92c]
2019-01-10 14:46:01 -05:00
foreman c1bb44fa73 P4 to Git Change 1593706 by skudchad@skudchad_test2_win_opencl on 2018/08/14 18:44:29
SWDEV-145570 - [HIP] Implement hipError*

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_error.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#41 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_peer.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_profile.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_surface.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#9 edit


[ROCm/clr commit: 2ec2cfd3c1]
2018-08-14 18:54:13 -04:00
foreman ee0e1fafe2 P4 to Git Change 1590010 by skudchad@skudchad_test2_win_opencl on 2018/08/06 21:18:48
SWDEV-145570 - [HIP] - Fix some issues in hip runtime
	- Set stream for event
	- Free mem needs to be reported in bytes but runtime backends reports in Kb

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#15 edit


[ROCm/clr commit: b4ccaeffe1]
2018-08-06 21:24:14 -04:00
foreman 934eca953a P4 to Git Change 1589062 by cpaquot@cpaquot-ocl-lc-lnx on 2018/08/02 18:34:20
SWDEV-145570 - [HIP] Fix a segfault exposed by rocBlas.

Affected files ...

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


[ROCm/clr commit: 08a308dd59]
2018-08-02 18:52:37 -04:00
foreman 7664c89d3e P4 to Git Change 1588185 by vsytchen@vsytchen-win10 on 2018/08/01 11:46:00
SWDEV-145570 - [HIP] Correctly handle calculating the offset when retrieving the amd::Memory object from a prepinned pointer

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

Affected files ...

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


[ROCm/clr commit: 85777ea939]
2018-08-01 12:08:35 -04:00
foreman 50b6d51a72 P4 to Git Change 1587799 by vsytchen@vsytchen-win10 on 2018/07/31 14:47:31
SWDEV-145570 - [HIP] refactor hipMemcpy* functions to correctly handle copies using prepinned memory

	The current implementation of hipMemcpy functions picks the copy type based on a flag that the user passes. However, one can use the hipMemcpyHostToDevice/hipMemcpyDeviceToHost flag in a combination with prepinned memory. By using the WriteMemoryCommand/ReadMemoyCommand in this case, we will pin the same host memory twice. This is fine on PAL/Linux, since pinning the same VA range is a noop, but this will start failing once we switch to using device memory with HIP/VDI/HSA.

	The solution is to ignore the hipMemcpyKind flag and let the runtime decide what kind of copy is best to do. Except for the case when hipMemcpyHostToHost is passed, since both host pointers may be prepinned.

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

Affected files ...

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


[ROCm/clr commit: b02040e934]
2018-07-31 15:07:56 -04:00
foreman 774a2be098 P4 to Git Change 1577282 by skudchad@skudchad_test2_win_opencl on 2018/07/06 15:02:32
SWDEV-145570 - [HIP] Fix hipMalloc3D

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

Affected files ...

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


[ROCm/clr commit: 01813aae67]
2018-07-06 15:13:22 -04:00
foreman b5914098d4 P4 to Git Change 1574251 by skudchad@skudchad_rocm on 2018/06/29 01:49:57
SWDEV-145570 - [HIP] Fix hipHostUnregister.

Affected files ...

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


[ROCm/clr commit: 167d628a49]
2018-06-29 01:59:22 -04:00
foreman 7bc91d5c18 P4 to Git Change 1572348 by skudchad@skudchad_test2_win_opencl on 2018/06/25 13:21:41
SWDEV-145570 - [HIP] - Fix hipHostGetDevicePointer. hipHostRegister tests now passes

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

Affected files ...

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


[ROCm/clr commit: 6523c1109c]
2018-06-25 13:29:56 -04:00
foreman 31028977f1 P4 to Git Change 1567831 by skudchad@skudchad_test2_win_opencl on 2018/06/13 13:20:10
SWDEV-145570 - [HIP] - Implement hipMemset3D

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#33 edit


[ROCm/clr commit: 2688b75663]
2018-06-13 13:36:52 -04:00
foreman b1b51ba1e7 P4 to Git Change 1567203 by skudchad@skudchad_test2_win_opencl on 2018/06/12 12:01:43
SWDEV-145570 - [HIP] -  Since getMemoryObject is now used in hip_texture it shouldnt be inline

Affected files ...

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


[ROCm/clr commit: 73dcd702e1]
2018-06-12 12:11:19 -04:00
foreman 73850c27d3 P4 to Git Change 1564420 by skudchad@skudchad_rocm on 2018/06/05 19:38:52
SWDEV-145570 - [HIP] - Find memobj in correct class

Affected files ...

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


[ROCm/clr commit: f92ce11e65]
2018-06-05 19:43:49 -04:00
foreman 24ec56cba1 P4 to Git Change 1562965 by skudchad@skudchad_test2_win_opencl on 2018/06/01 14:48:31
SWDEV-145570 - [HIP] - Implement hipHostRegister/Unregister, hipHostAlloc.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#12 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#30 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#8 edit


[ROCm/clr commit: 2c4c7ab564]
2018-06-01 15:01:45 -04:00
foreman bf393cab7a P4 to Git Change 1559149 by skudchad@skudchad_test2_win_opencl on 2018/05/24 11:54:02
SWDEV-145570 - [HIP] - Implement hipMemcpy2DToArray.

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

Affected files ...

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


[ROCm/clr commit: 9cdb308045]
2018-05-24 12:01:44 -04:00
foreman f436a9791a P4 to Git Change 1558526 by skudchad@skudchad_test2_win_opencl on 2018/05/23 13:34:33
SWDEV-145570 - [HIP]  Implement hipPointerGetAttributes.

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

Affected files ...

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


[ROCm/clr commit: 113c711b81]
2018-05-23 13:40:52 -04:00
foreman 4abe730e57 P4 to Git Change 1557352 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/21 19:53:00
SWDEV-145570 - [HIP]  Sync streams in hipFree. hipTestHalf passes now.

Affected files ...

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


[ROCm/clr commit: 6c06a08783]
2018-05-21 20:02:17 -04:00
foreman 4bc4f3e0ab P4 to Git Change 1555866 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/16 16:27:00
SWDEV-145570 - [HIP] Store HIP mem flags inside amd::Buffer's flags
	Use the 16 upper bits of amd::Buffer's flags field instead of adding a new field.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#26 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#86 edit


[ROCm/clr commit: 48a85c01e5]
2018-05-16 16:35:53 -04:00
foreman 6453962807 P4 to Git Change 1555193 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/15 16:19:50
SWDEV-145570 - [HIP] Implemented events

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#9 edit


[ROCm/clr commit: a896cb9af0]
2018-05-15 16:26:16 -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
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
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
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
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
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
foreman 4db0c47650 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/clr commit: 9aef0311c1]
2018-04-25 12:32:11 -04:00
foreman 03e7b4704e 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/clr commit: 5eace16718]
2018-04-24 14:05:20 -04:00
foreman 7823592e65 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/clr commit: 22439e8644]
2018-04-19 18:35:00 -04:00
foreman ff18c03439 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/clr commit: e19802c5c9]
2018-04-10 17:41:24 -04:00
foreman d393bbbd62 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/clr commit: 03a6601214]
2018-04-06 18:08:18 -04:00
foreman 2bf865a669 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/clr commit: 6fc37f7147]
2018-04-05 15:02:43 -04:00
foreman 78f2644004 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/clr commit: 1a5f98c021]
2018-04-04 13:24:15 -04:00
foreman f45c2eb542 P4 to Git Change 1524135 by cpaquot@cpaquot-ocl-lc-lnx on 2018/03/07 19:52:00
SWDEV-145570 - [HIP] Hip Rearchitecture
	Implemented hipHostAlloc

Affected files ...

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


[ROCm/clr commit: 336d1e589c]
2018-03-07 20:03:36 -05:00
foreman d8f628753c P4 to Git Change 1522211 by lmoriche@lmoriche_opencl_dev2 on 2018/03/02 17:41:47
SWDEV-145570 - [HIP] - Hip Rearchitecture
	- Rename cuda* launch functions -> hip*
	- Add more function prototypes to compile the HIP tests

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#1 add


[ROCm/clr commit: f27e6709eb]
2018-03-02 17:55:48 -05:00
foreman b84cfe7b08 P4 to Git Change 1521675 by lmoriche@lmoriche_opencl_dev2 on 2018/03/01 22:50:06
SWDEV-145570 - [HIP] - Hip Rearchitecture
	- Add initial prototype implementation

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/Makefile#11 edit
... //depot/stg/opencl/drivers/opencl/api/hip/fixme.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_error.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.rc#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#1 add


[ROCm/clr commit: 13f4e897fc]
2018-03-01 22:57:20 -05:00
foreman 41fed64377 P4 to Git Change 1516173 by skudchad@skudchad_rocm on 2018/02/14 15:02:45
SWDEV-145570 -  Initial hip api checkin

Affected files ...

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


[ROCm/clr commit: ce7a19fa55]
2018-02-14 15:08:01 -05:00