Commit Graph

13150 Commits

Author SHA1 Message Date
Ben Sander b1d3df6484 Deprecate hipMallocHost and hipFreeHost.
These will print compiler warnings if used, so we can weed them out
before removing.

Also add a default flags args for hipHostAlloc, in the C++ functioin
headers.  So you can replace hipMallocHost(&ptr, size( with hipHostAlloc(&ptr, size)


[ROCm/clr commit: 57365eb7a3]
2016-03-19 22:53:59 -05:00
Ben Sander c75b63b61c Refactor waitALlDevices and async mem copy.
- move waitAllStreams to device member function.
- create separate stream member function for copyAsync, like copySync.
  hipMemcpyAsync now calls the copyAsync.


[ROCm/clr commit: a88c2b1ec9]
2016-03-19 05:42:19 -05:00
Ben Sander d41836a4a1 Fix bug: test was allocating host mem instead of device mem.
Caused assertion when checking free + allocated should
not exceed total.  Bug introduced in hipHostAlloc conversion.


[ROCm/clr commit: 4c6fd4e7ec]
2016-03-19 04:11:39 -05:00
Ben Sander cf95ea5468 Swap in corrected hipHostAlloc (bad merge)
[ROCm/clr commit: aaa2429feb]
2016-03-19 04:11:08 -05:00
Ben Sander 3305c49949 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging
Conflicts:
	src/hip_hcc.cpp


[ROCm/clr commit: 90ad8ddc5d]
2016-03-19 03:22:09 -05:00
Ben Sander 3323d2005c disable mt streams tests (for now)
[ROCm/clr commit: efc9df8805]
2016-03-19 03:10:31 -05:00
Ben Sander 57c08b7fce Describe HIP env vars
[ROCm/clr commit: c39b0f9660]
2016-03-19 03:09:57 -05:00
Ben Sander 1abdd6602f Fix copy and sync bugs. Remove extra sync in default stream.
- NULL stream was waiting for itself to be empty before each command.
- Force "blocking" streams to wait for NULL to empty.  This was missing
  before.
- async copy was disabling itself via trueAsync=false for common cases.

Refactor:
- rename _null_stream to _default_stream.
- move some null sync function to defaultSync, move to dev member func.


[ROCm/clr commit: 44522eb607]
2016-03-19 02:44:26 -05:00
Ben Sander d207f3bc26 Add beastperiteration and onesize for testing.
onesize allows running tests at one specific size.


[ROCm/clr commit: 5197cf250d]
2016-03-19 02:43:04 -05:00
foreman 666951f151 P4 to Git Change 1249106 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/19 03:00:11
SWDEV-2 - Change OpenCL version number from 2067 to 2068.

Affected files ...

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


[ROCm/clr commit: ef7612cfb3]
2016-03-19 03:12:35 -04:00
foreman f7347666d7 P4 to Git Change 1249103 by smekhano@stas-rampitec-hsa on 2016/03/19 00:35:23
SWDEV-77584 - HSA HLC: constant fold get_local_size() with reqd_work_group_size attribute

	Testing: smoke, precheckin, conformance non_uniform_work_group
	Reviewed by Valery Pykhtin

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/optimizer.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/AMDUtils.h#5 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/AMDIntrinsic.h#5 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/AMDMetadataUtils.h#4 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/Utils/AMDLibCalls.h#37 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILKernelManager.cpp#53 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/IntrinsicUtils/AMDIntrinsic.src_cpp#8 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/SPIR/AMDMetadataUtils.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/Utils/AMDLibCalls.cpp#61 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/Utils/AMDUtils.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/src/ocl/features/metadata/local_size_reqd.cl#1 add
... //depot/stg/opencl/drivers/opencl/tests/hsa/src/ocl/features/metadata/local_size_reqd_intr.cl#1 add
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/llc_opt.tlst#87 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/ocl_features.tlst#53 edit


[ROCm/clr commit: 80cdbed438]
2016-03-19 00:43:22 -04:00
Ben Sander d3a3e0ba63 Improve formatting - line up cols
[ROCm/clr commit: c5d0813f03]
2016-03-18 23:43:04 -05:00
Ben Sander c55187604c Print Pinned or Unpinned in result summary
[ROCm/clr commit: 3dc6906855]
2016-03-18 21:28:29 -05:00
Aditya Atluri 2bc7b1f3ba Update CUDA_Runtime_API_functions_supported_by_HIP.md
[ROCm/clr commit: a17e390283]
2016-03-18 11:28:06 -05:00
Aditya Atluri 336001aa29 Create CUDA_Runtime_API_functions_supported_by_HIP.md
[ROCm/clr commit: 564d13a0b3]
2016-03-18 11:23:44 -05:00
Ben Sander 203eeda2f7 Supported --aliged mode. Add results check for H2D and D2H.
[ROCm/clr commit: 690486b9eb]
2016-03-18 03:09:52 -05:00
Ben Sander b1fe0120ca Refactor copy code.
-Move staging buffer locks inside the staging buffer code.
-Remove dedicated per-device completion_signal + per-device lock -
instead allocated signal from the per-stream pool.   This elimintes
the lock and allows more concurrency.
-remove switch HIP_DISABLE_BIDIR_MEMCPY


[ROCm/clr commit: e64174f47a]
2016-03-18 03:02:00 -05:00
foreman 4365f4231c P4 to Git Change 1248757 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/18 03:00:16
SWDEV-2 - Change OpenCL version number from 2066 to 2067.

Affected files ...

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


[ROCm/clr commit: 35181ad34b]
2016-03-18 03:06:16 -04:00
Ben Sander a0d3c018c0 Refactor staging buffer and sync copies.
- refactor staging buffer to operate on hsa* data structures not
  hc::accelerator.
- use hsa_memory_allocate to allocate staging buffers rather than
  am_alloc.
- Refactor device reset with single member function.  Don't reallocate
  staging buffers on reset.
- Properly track dependencies based on command type.  Add new deps for
  H2D and D2D rather than overloading H2D.


[ROCm/clr commit: 3b45e064f9]
2016-03-17 20:09:10 -05:00
foreman 24b1911f57 P4 to Git Change 1248319 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/17 03:00:18
SWDEV-2 - Change OpenCL version number from 2065 to 2066.

Affected files ...

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


[ROCm/clr commit: 5a093ba1e9]
2016-03-17 03:10:49 -04:00
Ben Sander dd90a8ff34 Refactor to isolate staging buffer code.
[ROCm/clr commit: 1b7cc7d921]
2016-03-17 00:20:56 -05:00
Ben Sander 622902d408 Start separaration of staging_buffer.cpp code.
Still #include staging_buffer.cpp into hip_hcc.cpp.
Directed tests compile hip_hcc to static library and use the library.


[ROCm/clr commit: a1879ba59b]
2016-03-16 22:26:49 -05:00
Ben Sander c903229e9a Add aligned alloc
[ROCm/clr commit: c9d46bdcde]
2016-03-16 21:55:57 -05:00
Ben Sander 931b58f438 Checkpoint code cleanup.
- Refactor ihipStream in prep for thread-safe implementation.
- Do some work on PinInPlace implementation.


[ROCm/clr commit: 8acb53e160]
2016-03-16 21:16:29 -05:00
foreman 0dab729085 P4 to Git Change 1248071 by skeely@HSA_Perforce on 2016/03/16 13:57:32
SWDEV-90207 - Initial Mesa implementation.  Interop is disabled pending further testing.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsadefs.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsadevice.cpp#59 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsadevice.hpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsaglinterop.cpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsaglinterop.hpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsamemory.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsamemory.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsaregisters.hpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/hsasettings.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/hsa_foundation/mesa_glinterop.h#1 add
... //depot/stg/opencl/drivers/opencl/runtime/utils/util.hpp#11 edit


[ROCm/clr commit: b0cc1d1094]
2016-03-16 14:07:05 -04:00
Aditya Atluri b3612a7356 changed flag in hipHostRegister
[ROCm/clr commit: 4b96e8c789]
2016-03-16 08:01:53 -05:00
Aditya Atluri 420797aed8 src/ fixed hipHostAllocDefault flags
[ROCm/clr commit: 6beed19460]
2016-03-16 07:32:54 -05:00
Aditya Atluri 488512466a Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging
[ROCm/clr commit: 9b78f0a454]
2016-03-16 07:17:22 -05:00
Aditya Atluri d62227266b Added performance test for memcpy
[ROCm/clr commit: 7567a6c0ac]
2016-03-16 07:16:51 -05:00
Aditya Atluri 63523fbeb7 tests/src [v4] Added feature for partial writes on CPU
[ROCm/clr commit: 6baeb08e1c]
2016-03-16 07:04:40 -05:00
Aditya Atluri 9f9a56597c test/src [v3] clean up
[ROCm/clr commit: 9b772c8553]
2016-03-16 05:30:29 -05:00
Aditya Atluri 6253fbbfe5 increased iteration size
[ROCm/clr commit: 8f527d2288]
2016-03-16 05:24:08 -05:00
Aditya Atluri 2a0d9ffb9c added cudaHostRegister test
[ROCm/clr commit: a60649868d]
2016-03-16 05:15:03 -05:00
foreman 8e8b778ddd P4 to Git Change 1247863 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/16 03:00:13
SWDEV-2 - Change OpenCL version number from 2064 to 2065.

Affected files ...

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


[ROCm/clr commit: 96be165c4a]
2016-03-16 03:09:19 -04:00
Aditya Atluri 7493d6074a corrected first and second kernel dispatch
[ROCm/clr commit: 369d01086f]
2016-03-15 14:22:00 -05:00
Aditya Atluri 343cf7e864 Added single kernel launch to sample
[ROCm/clr commit: a6441c3334]
2016-03-15 21:05:15 -05:00
foreman a28efbda7f P4 to Git Change 1247541 by smekhano@stas-rampitec-hsa on 2016/03/15 13:32:04
SWDEV-77584 - fixed work of option -cl-uniform-work-group-size to produce requirenopartialworkgroups in hsail

	Testing: smoke, precheckin
	Reviewed by Evgeny Mankov

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/codegen.cpp#67 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILKernelManager.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/ocl_features.tlst#52 edit


[ROCm/clr commit: 0967db2af7]
2016-03-15 13:46:39 -04:00
Aditya Atluri 649c943833 added performance metrics for kernel dispatch
[ROCm/clr commit: b7bf5830c1]
2016-03-15 12:37:24 -05:00
Aditya Atluri dbc1196236 v2 deprecating hipMallocHost with hipHostAlloc
[ROCm/clr commit: 2743a5082f]
2016-03-15 13:39:15 -05:00
foreman 8bee1611b9 P4 to Git Change 1247486 by weizhang@weizhang-lnx-opencl on 2016/03/15 11:01:21
SWDEV-89454 - The memory pointed by m_nativeDisplayHandle should be freed at IOL.

	  The memory pointed by m_nativeDisplayHandle is allocated in IOL, so it should be freed at IOL as well. Otherwise, the error of "double free or corruption" happens.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDevice.cpp#162 edit


[ROCm/clr commit: c33a49c7f6]
2016-03-15 11:10:14 -04:00
Aditya Atluri 5327f3cbac Deprecating hipMallocHost to hipHostAlloc
[ROCm/clr commit: 4d4d592e0c]
2016-03-15 06:30:16 -05:00
foreman 432e0e0f36 P4 to Git Change 1247337 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/15 03:00:12
SWDEV-2 - Change OpenCL version number from 2063 to 2064.

Affected files ...

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


[ROCm/clr commit: dfdedf8c1b]
2016-03-15 03:12:32 -04:00
Ben Sander 0573890c39 print device config info
[ROCm/clr commit: bdefb70862]
2016-03-14 23:02:49 -05:00
Ben Sander 19a0fb0e0e Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging
Conflicts:
	src/hip_hcc.cpp
	tests/src/CMakeLists.txt


[ROCm/clr commit: 15a8e8f8a0]
2016-03-14 15:01:26 -05:00
Ben Sander a24528abcb enable DB, comments
[ROCm/clr commit: 0d05517d0a]
2016-03-14 14:40:41 -05:00
Ben Sander 649f9834e8 Add Bidir copy test and help.
[ROCm/clr commit: 87c15a3629]
2016-03-14 14:39:23 -05:00
foreman e30924c0f3 P4 to Git Change 1246912 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/14 03:00:09
SWDEV-2 - Change OpenCL version number from 2062 to 2063.

Affected files ...

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


[ROCm/clr commit: bca662bb54]
2016-03-14 03:11:41 -04:00
Ben Sander 0aa6e9df26 refactor, add support for speccing xfers in bytes
[ROCm/clr commit: 0aab91123b]
2016-03-13 09:41:06 -05:00
foreman 0214a6ffde P4 to Git Change 1246830 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/13 04:00:10
SWDEV-2 - Change OpenCL version number from 2061 to 2062.

Affected files ...

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


[ROCm/clr commit: 42fcc19238]
2016-03-13 04:10:50 -04:00
Ben Sander 5efb582db5 Remove ROCR_V2, assume=1
[ROCm/clr commit: 59f0ef2801]
2016-03-12 04:08:13 -06:00