Commit Graph

13691 Commits

Author SHA1 Message Date
Aditya Atluri a8c51b822b fixed arch compiler flag
Change-Id: I19f7a0ea513d6b8059f0c10cd0e7a5ead510e246
2017-01-27 08:51:48 -06:00
Aditya Atluri 537dc7597b fixed threadfence ir
Change-Id: Ia3afb54bdb50864e678d849608d72a3c321edba1
2017-01-27 08:42:26 -06:00
Aditya Atluri 33d89d06aa fixed kernel only compilation for module api
Change-Id: I567992fa9b87125318edba41fd82d2f7bc5504a1
2017-01-27 08:41:42 -06:00
Rahul Garg 125983eed9 hipMallocArray fixes for NV path
Change-Id: I1ca43e6bc0cd405998888005c20dfb1ea57003d5
2017-01-27 14:32:08 +05:30
foreman 40561d2c67 P4 to Git Change 1366677 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/27 03:00:05
SWDEV-2 - Change OpenCL version number from 2347 to 2348.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2094 edit
2017-01-27 03:12:31 -05:00
foreman 027f8d9108 P4 to Git Change 1366502 by gandryey@gera-lnx-rcf-lc on 2017/01/26 14:44:13
SWDEV-112016 - [ROCm CQE][OCLonLC][QR][G] Seg fault observed with "sub_buffers_read_write" of Buffers, due to CL#1364923
	- Take the host pointer for CPU access in bufferfill.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#8 edit
2017-01-26 14:52:51 -05:00
foreman 5fd072d9b3 P4 to Git Change 1366459 by gandryey@gera-w8 on 2017/01/26 13:37:23
SWDEV-112016 - [ROCm CQE][OCLonLC][QR][G] Seg fault observed with "sub_buffers_read_write" of Buffers, due to CL#1364923
	- Fix subbuffers logic with AHP allocations
	- Make AHP allocations to use UHP path

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#7 edit
2017-01-26 13:45:49 -05:00
pensun f18efd5d15 more fix on hipmallocarray on NV path
Change-Id: I890a36cab10c101f4a112bc4567f765b318d486c
2017-01-26 12:30:52 -06:00
pensun 42f22162e0 fix missing semicolon on NV path
Change-Id: I3cfecb7bd534578a1f5a07ca9397092dcf01db07
2017-01-26 11:28:15 -06:00
foreman 356b1574bf P4 to Git Change 1366316 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/26 03:00:04
SWDEV-2 - Change OpenCL version number from 2346 to 2347.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2093 edit
2017-01-26 03:14:16 -05:00
Ben Sander 1a24178c78 Add HIP_FAIL_SOC.
Fail sub-optimal-copies rather than perform them slowly.
SOC occur on async copy of unpinned memory, or P2P copy between GPUs
that are not peers.
2017-01-25 21:53:17 -06:00
Ben Sander 2f7a8ec39c Read HCC_OPT_FLUSH and optimize dispatch accordingly.
If HCC is in this mode, we can use less aggressive flushes in some
cases.
2017-01-25 21:50:52 -06:00
foreman 32413bdc80 P4 to Git Change 1366280 by kzhuravl@kzhuravl-kaveri-cl-on-lc on 2017/01/25 21:14:50
SWDEV-94644 - Switch back to bare numbers in pal when processing note entries. In order to use constants and enums from the llvm's header, we need to clean up similar loader's header (they conflict). Ideally we should move torwards not having headers with similar definitions.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#32 edit
2017-01-25 21:21:04 -05:00
foreman 4ad12d089c P4 to Git Change 1366205 by kzhuravl@kzhuravl-fiji-cl-on-lc on 2017/01/25 18:04:35
SWDEV-94644 - Make sure we are processing metadata note entry with supported n_type. Update build log and fail for not supported metadata n_type. Use constants defined in AMDGPUPTNote.h

	This change is needed for https://reviews.llvm.org/D29115

	This change is required for CL 1366203

	ReviewBoardURL: http://ocltc.amd.com/reviews/r/12223/
	Testing: lightning conformance tests locally

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#54 edit
2017-01-25 18:12:20 -05:00
foreman ff3c30e9ce P4 to Git Change 1365943 by lmoriche@lmoriche_opencl_dev on 2017/01/25 11:37:20
SWDEV-102726 - [OCL-LC-ROCm] Open source OpenCL Runtime
	- Cleanups: Remove CL_HSA_ENABLED/DISABLED_AMD.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_context.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_device.cpp#60 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl1.2/CL/cl_ext.h#13 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl2.0/CL/cl_ext.h#28 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl2.1/CL/cl_ext.h#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/appprofile.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/appprofile.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#208 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#283 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocappprofile.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#36 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#53 edit
2017-01-25 11:44:06 -05:00
foreman aae258198d P4 to Git Change 1365943 by lmoriche@lmoriche_opencl_dev on 2017/01/25 11:37:20
SWDEV-102726 - [OCL-LC-ROCm] Open source OpenCL Runtime
	- Cleanups: Remove CL_HSA_ENABLED/DISABLED_AMD.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_context.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_device.cpp#60 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl1.2/CL/cl_ext.h#13 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl2.0/CL/cl_ext.h#28 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/khronos/headers/opencl2.1/CL/cl_ext.h#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/appprofile.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/appprofile.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#208 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#283 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocappprofile.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#36 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#53 edit
2017-01-25 11:44:06 -05:00
Aditya Atluri 33a3ebad27 added device functions header to hip_runtime.h
Change-Id: I635931e1fbe4b7f0f64f3a126c0f1badcd6d234b
2017-01-25 08:14:30 -06:00
foreman c3b34aeaa7 P4 to Git Change 1365827 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/25 03:00:09
SWDEV-2 - Change OpenCL version number from 2345 to 2346.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2092 edit
2017-01-25 03:09:55 -05:00
pensun a8fcbb2584 Add more hip_bug.md entry, regarding hang after hipLaunchKernel
Change-Id: I5800cb627179ec0e913cd36d332fb8c2994ab71e
2017-01-24 22:43:25 -06:00
pensun 24d9827688 Initial commit on hip_bugs markdown doc
Change-Id: I5a6915337b8664cfed9eaee9443c6e4406348574
2017-01-24 22:30:36 -06:00
foreman 37b3d8078e P4 to Git Change 1365284 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/24 03:00:10
SWDEV-2 - Change OpenCL version number from 2344 to 2345.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2091 edit
2017-01-24 03:18:42 -05:00
Ben Sander 73ef364c74 Add debug tip to docs 2017-01-23 22:34:41 -06:00
Ben Sander 27447f10c2 Show dynamic shared mem usage not static. 2017-01-23 22:34:41 -06:00
Ben Sander bc809460f5 Move core env var processing to env.cpp 2017-01-23 22:34:41 -06:00
Ben Sander 4de3df746c Add debug tips to docs 2017-01-23 22:34:41 -06:00
Ben Sander fe24996326 Add debug tips to docs 2017-01-23 22:34:41 -06:00
Ben Sander d19c4767b7 Log error with ihipLogError. Cleans up CXL trace display. 2017-01-23 22:34:41 -06:00
Ben Sander df74158d1c Add HIP_IGNORE_HCC_VERSION.
Ignores strict checking of HCC and HIP version.
Can be useful when developing new HCC code.
2017-01-23 22:34:41 -06:00
foreman 454621b7f1 P4 to Git Change 1364923 by gandryey@gera-lnx-rcf-lc on 2017/01/23 11:48:45
SWDEV-110996 - OCL to use the blit manager instead ROCr implementing copyRect API

	- Implement the blit manager functionality in ROCm backened. This checki-in also fixes SWDEV-95079, SWDEV-95068, SWDEV-95069, SWDEV-95071

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#35 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.hpp#5 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.cpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.hpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#6 edit
2017-01-23 11:59:51 -05:00
foreman 77f4cda6b8 P4 to Git Change 1364840 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/23 03:00:29
SWDEV-2 - Change OpenCL version number from 2343 to 2344.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2090 edit
2017-01-23 03:17:12 -05:00
foreman 8de92f6aae P4 to Git Change 1364702 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/22 03:00:06
SWDEV-2 - Change OpenCL version number from 2342 to 2343.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2089 edit
2017-01-22 03:11:32 -05:00
foreman eb7af95016 P4 to Git Change 1364632 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/21 03:00:05
SWDEV-2 - Change OpenCL version number from 2341 to 2342.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2088 edit
2017-01-21 03:11:14 -05:00
foreman 8618ed31ca P4 to Git Change 1364611 by asalmanp@asalmanp-opencl-stg on 2017/01/20 19:12:14
SWDEV-111478 - [Vega] Clinfo doesn't report the CPU as a CL device.

	amdocl12cl64.dll is not loaded in Windows 10 (RS1) because the driverstore path wasn't searched to load for this module. Added the path to fix this issue.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/12211/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#563 edit
... //depot/stg/opencl/drivers/opencl/runtime/os/os.cpp#6 edit
2017-01-20 19:20:32 -05:00
foreman cd7b121d91 P4 to Git Change 1364608 by skudchad@skudchad_test_win_opencl2 on 2017/01/20 19:05:41
SWDEV-107075 - [OCL][VG10] Conformance RQ Mipmaps tests are failing.
	- Extending this change to all gfx9

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#15 edit
2017-01-20 19:10:08 -05:00
Aditya Atluri 9952117d64 added ir code sad u8
Change-Id: Ie0d454b3bb9a6c9a028c091ad3aa969719b02cc9
2017-01-20 17:21:51 -06:00
Aditya Atluri 97315e8748 added driver_types.h and texture_types.h header files to hip
Change-Id: Ic3b2403f07d6767dadf83d6c278fd14e87f6acdb
2017-01-20 17:09:52 -06:00
Aditya Atluri 5b2d4c0e60 fixed hipArray issues
1. Fixed build issues produced from previous commit
2. Create new header files to manage data structures better

Change-Id: I704d82c196c1858ed7617d76e40612eb507d2aa0
2017-01-20 16:54:48 -06:00
Aditya Atluri 5f10a69ef7 changes device functions documentation according to the supported apis
Change-Id: I47ac6bbde11d54d8265e0d27ec8cd5da4d03eb8e
2017-01-20 14:19:09 -06:00
Aditya Atluri a7fa600176 added nvcc backend for hipArrays
1. Added hip_texture.h to hip_runtime_api.h as cuda does declare array runtime apis inside cuda_runtime_api.h
2. Added nvcc backend for hipArray runtime apis
3. Didn't test on nvidia platform (should work)

Change-Id: I1a14aef41840e4f55e5535132e3443a918b55967
2017-01-20 14:11:45 -06:00
Aditya Atluri fd2e6ac2f0 added more test coverage for vector data types
Change-Id: I9f57a8b597bd2ee4b265eadfd0859531497a6ada
2017-01-20 13:52:02 -06:00
Aditya Atluri 02190736e3 fixed compilation issues for vector types and math functions
1. Added math_functions.h to hip_runtime.h
2. Changed operator overloading classifier static to static inline
3. Added vector types test for gpu
4. Seperated __host__ and __device__ for math functions in headers

Change-Id: I499862fad5d7b10da686da9011d7ecefe523f8e2
2017-01-20 09:49:11 -06:00
foreman cf09d06cb4 P4 to Git Change 1364218 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/20 03:00:45
SWDEV-2 - Change OpenCL version number from 2340 to 2341.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2087 edit
2017-01-20 03:19:06 -05:00
Ben Sander db3f4889ca Add HIP_SYNC_HOST_ALLOC, HipReadEnv 2017-01-19 23:55:24 -06:00
Ben Sander 6de88d4293 Change ihipDeviceSetState,ihipDevice* so it doesn't log error
Cleans up debug trace.
2017-01-19 23:55:24 -06:00
Aditya Atluri fe5f45caaf added operator overloading for complex data types
Change-Id: Id96d5d000651914169f04497af6ff78ad96d846a
2017-01-19 15:15:25 -06:00
Ben Sander ca1cef4e06 Doc update - describe debug techniques
Also tweak sample to remove unneeded HIP_KERNEL_NAME.
Comment update
2017-01-19 12:40:45 -06:00
Ben Sander 2ffc9f4e22 Fix debug display for Module launch kernels 2017-01-19 12:40:45 -06:00
foreman 7403de545e P4 to Git Change 1363842 by asalmanp@asalmanp-opencl-stg on 2017/01/19 11:35:19
SWDEV-107075 - [OCL][VG10] Conformance RQ Mipmaps tests are failing. Adding a temporary workaround for Vega10 to disable sDMA transfers for MemToImage and ImageToMem for 1Darray image format for now and use Kernles instead until the failures can be root-caused and fixed.
	GPU_DISABLE_SDMA_IMG_MEM_IMG environment variable was also added to quickly enable back the sDMA for testing and continuing the current failure investigation.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/12194/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#265 edit
2017-01-19 11:45:14 -05:00
Rahul Garg aa3f278475 Fixed hipcommander default execution for HCSWAP-106
Change-Id: I9fbd10dfaeeb4928b2ec23ceed131b5200a658f9
2017-01-19 15:04:32 +05:30
foreman 4b86b7c587 P4 to Git Change 1363682 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/19 03:00:04
SWDEV-2 - Change OpenCL version number from 2339 to 2340.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2086 edit
2017-01-19 03:14:52 -05:00