Commit Graph

12493 Commits

Author SHA1 Message Date
Aditya Atluri 248b42d3e3 include arch specific ir on fallback path
Change-Id: Ib04996aae2c21eb73ef2a9f6305915e0caccd704


[ROCm/clr commit: 26b5e57cfd]
2017-02-08 12:19:06 -06:00
Aditya Atluri 14dcdff8f4 Fixed Hawaii link issues
1. Split hip_ir.ll to hip_hc.ll and hip_hc_gfx803.ll
 a. hip_hc.ll contains arch generic ir implementations
 b. hip_hc_gfx803.ll contains gfx803 (fiji, polaris) specific ir
2. HIPCC can now parse --amdgpu-target=*.
 a. Usage: hipcc --amdgpu-target=gfx803 --amdgpu-target=gfx701
 b. TODO: Convert to --amdgpu-target=gfx803,gfx701
3. With LLC in HCC able to generate native f16 isa, removed inline half asm math ops
4. Fixed threadfence and threadfence_block to use functions in rocdl

Change-Id: Ic9a9e3e04139b0d75d2c2a263c030ca77adc1019


[ROCm/clr commit: 60ec83c683]
2017-02-08 12:04:05 -06:00
Evgeny Mankov 2cef50ac30 [HIPIFY] Readme.md update.
[ROCm/clr commit: cc8a7f3d3e]
2017-02-08 19:50:05 +03:00
Evgeny Mankov 508311dafe [HIPIFY] Readme.md update.
+ Launching example.
+ Delimiter "--" is strongly recommended.
+ "-x cuda" option is mentioned as well.


[ROCm/clr commit: b3098091fd]
2017-02-08 19:43:32 +03:00
foreman aa891c0385 P4 to Git Change 1370604 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/08 03:00:09
SWDEV-2 - Change OpenCL version number from 2359 to 2360.

Affected files ...

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


[ROCm/clr commit: a7f69bff2b]
2017-02-08 03:11:12 -05:00
foreman 1de65a1948 P4 to Git Change 1370387 by wchau@wchau_OCL_boltzmann on 2017/02/07 17:00:35
SWDEV-103424 - [ROCm CQE][OCL] OCLRuntime - OCLCreateBuffer tests are failing.  The failure is due to AQL cannot support global size > 32bit range.  Adding dispatch split support for ROCm, similar to that of GSL (CL#1159349), to resolve the issue.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#56 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/runtime/OCLCreateBuffer.cpp#6 edit


[ROCm/clr commit: dadd21fced]
2017-02-07 17:13:15 -05:00
Aditya Atluri d191eac0e2 Fixed HIP for C runtime
1. fixed constant memory test
2. added runtime gcc/g++ test
3. added fix for runtime with gcc/g++

Change-Id: Ie14dad6633411b188bdeea044e140b6d5beabe16


[ROCm/clr commit: be6d01ebc3]
2017-02-07 13:15:36 -06:00
Aditya Atluri 110303c087 fixed vector types for c
Change-Id: I2330e976060f9a038929cd51be07ae2ee98e81ce


[ROCm/clr commit: 6d8007e28c]
2017-02-07 11:09:54 -06:00
Rahul Garg 1b11b60e9d Command scripts for latency measurements
Change-Id: I8c28765a09fb0358447367939de524b12699a317


[ROCm/clr commit: 73b56e690f]
2017-02-07 15:03:46 +05:30
foreman 7077128e0b P4 to Git Change 1369977 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/07 03:00:07
SWDEV-2 - Change OpenCL version number from 2358 to 2359.

Affected files ...

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


[ROCm/clr commit: ef61b25945]
2017-02-07 03:10:20 -05:00
foreman 08a43a240b P4 to Git Change 1369850 by gandryey@gera-w8 on 2017/02/06 18:15:17
SWDEV-112661 - [ROCm CQE][OCLonLC][QR][G] 80 failures observed with Images(Samplerless and Samplerless pitch) tests
	- Make sure the pitch for image buffer is properly aligned to the reported device info

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#10 edit


[ROCm/clr commit: c9cbcbf0f5]
2017-02-06 18:22:59 -05:00
foreman 18da2685da P4 to Git Change 1369662 by gandryey@gera-w8 on 2017/02/06 13:52:13
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- reenable HSA copy in ROCr, since OCL copy doesn't really fix the hang issue in integer_ops, but just delays it.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#30 edit


[ROCm/clr commit: 064f21aa74]
2017-02-06 14:08:48 -05:00
foreman 20daef2a8e P4 to Git Change 1369504 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/06 03:00:04
SWDEV-2 - Change OpenCL version number from 2357 to 2358.

Affected files ...

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


[ROCm/clr commit: df6f6de805]
2017-02-06 03:14:54 -05:00
Maneesh Gupta c072d54c50 Disable broken test: hipC
Change-Id: I061aa125bbdc9f14bc870266ab0735593c861903


[ROCm/clr commit: 0bef861f1a]
2017-02-06 13:00:50 +05:30
foreman d21a308c20 P4 to Git Change 1369347 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/05 03:00:10
SWDEV-2 - Change OpenCL version number from 2356 to 2357.

Affected files ...

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


[ROCm/clr commit: 3d78cc9365]
2017-02-05 03:10:19 -05:00
foreman ca7a01716b P4 to Git Change 1369315 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/04 03:00:04
SWDEV-2 - Change OpenCL version number from 2355 to 2356.

Affected files ...

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


[ROCm/clr commit: 6a684f91a6]
2017-02-04 03:15:20 -05:00
foreman a5e2d28f34 P4 to Git Change 1369302 by todli@todli-win-opencl-kv1 on 2017/02/04 00:49:06
SWDEV-107271 - Fix crash that happens when Resource::create() fails and "owner" gets cleared. This is only triggered by Conformance test Basic progvar_prog_scope_misc on Raven with 16GB memory (8GB is fine), but should be a general bug.
	http://ocltc.amd.com/reviews/r/12253

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#11 edit


[ROCm/clr commit: c2ca879dec]
2017-02-04 00:59:54 -05:00
foreman 84217acb21 P4 to Git Change 1369163 by todli@todli-win-opencl-kv1 on 2017/02/03 17:19:46
SWDEV-96241 - fix OpenCL/LC build failure

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#43 edit


[ROCm/clr commit: 28f7b5b678]
2017-02-03 17:29:15 -05:00
Aditya Atluri 3937b398e9 changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b


[ROCm/clr commit: f009f3533d]
2017-02-03 10:53:36 -06:00
foreman 41f7a9f955 P4 to Git Change 1368828 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/03 03:00:04
SWDEV-2 - Change OpenCL version number from 2354 to 2355.

Affected files ...

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


[ROCm/clr commit: 5615f44274]
2017-02-03 03:10:56 -05:00
foreman fcf63c43c8 P4 to Git Change 1368703 by todli@todli-win-opencl-kv1 on 2017/02/02 18:12:31
SWDEV-96241 - Support SDI on PAL (runtime changes)

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#42 edit


[ROCm/clr commit: 1eda218988]
2017-02-02 18:23:12 -05:00
foreman 3db14ee4cb P4 to Git Change 1368336 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/02 03:00:03
SWDEV-2 - Change OpenCL version number from 2353 to 2354.

Affected files ...

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


[ROCm/clr commit: 917f2935ed]
2017-02-02 03:15:42 -05:00
Aditya Atluri f36992067b fixed symbol memcpy issue
Change-Id: I89d7401be51d194bcbf771020ba66e3d3b6a18f8


[ROCm/clr commit: 0d4e6ae60a]
2017-02-01 17:54:59 -06:00
foreman 73fe771169 P4 to Git Change 1368253 by gandryey@gera-w8 on 2017/02/01 18:29:08
SWDEV-112352 - [ROCm CQE][OCLonLC][QR][G] Aborted/Segmentation fault is observed with "sub_buffers_read_write_dual_devices" of Buffers, due to CL#1364923
	- Keep system memory for multiple devices in case of possible initialization on the second device

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#41 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#9 edit


[ROCm/clr commit: a10c33ad77]
2017-02-01 18:39:14 -05:00
foreman d53338df44 P4 to Git Change 1367969 by gandryey@gera-lnx-rcf-lc on 2017/02/01 11:53:10
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Disable ROCr copy buffer and use runtime kernel to avoid  HW hangs in integer_ops.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/blit.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#29 edit


[ROCm/clr commit: c0d4edda9d]
2017-02-01 12:03:40 -05:00
foreman b71d37e251 P4 to Git Change 1367952 by gandryey@gera-w8 on 2017/02/01 11:11:26
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Back out changelist 1367810. A hang was delayed, but still occured much later in the test.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#16 edit


[ROCm/clr commit: c36d89754a]
2017-02-01 11:21:13 -05:00
foreman df17314d2e P4 to Git Change 1367882 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/01 03:00:05
SWDEV-2 - Change OpenCL version number from 2352 to 2353.

Affected files ...

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


[ROCm/clr commit: 3ee45f2c08]
2017-02-01 03:07:06 -05:00
foreman 1c12ea1371 P4 to Git Change 1367875 by smekhano@stas-mwamba-rocm on 2017/02/01 01:33:12
SWDEV-105835 - ROCm OpenCL: add -amdgpu-internalize-symbols to BE

	The option -amdgpu-internalize-symbols allows to drop unused symbols from program,
	functions and global variables. This saves compile time and object size, a lot in
	case of a big program.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#55 edit


[ROCm/clr commit: df22dc2a47]
2017-02-01 01:41:59 -05:00
foreman 01482a67c9 P4 to Git Change 1367810 by gandryey@gera-w8 on 2017/01/31 19:02:27
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Make HSA copy call lock protected, due to a possible race condition and HW hangs in integer_ops long_math test

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#15 edit


[ROCm/clr commit: a7a4a6dbad]
2017-01-31 19:09:43 -05:00
foreman 9e93e41146 P4 to Git Change 1367466 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/31 03:00:05
SWDEV-2 - Change OpenCL version number from 2351 to 2352.

Affected files ...

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


[ROCm/clr commit: b0862beab2]
2017-01-31 03:06:32 -05:00
foreman 347b14e315 P4 to Git Change 1367307 by gandryey@gera-w8 on 2017/01/30 16:30:52
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Add missing row and slice pitches to fix "clReadWriteImage Pitch"  and "clFillImage pitch" tests

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#9 edit


[ROCm/clr commit: d301d438f8]
2017-01-30 16:41:55 -05:00
foreman 88816ae021 P4 to Git Change 1367270 by gandryey@gera-w8 on 2017/01/30 15:31:49
SWDEV-112273 - [ROCm CQE][OCLonLC][QR][G] 2 of 9 tests failed with mem_host_flags due to CL#1366459
	- Keep system memory for images with UHP allocations

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#38 edit


[ROCm/clr commit: cfac74adbf]
2017-01-30 15:38:27 -05:00
foreman 6dbb4a0843 P4 to Git Change 1367147 by cpaquot@hog-ocl on 2017/01/30 13:05:47
SWDEV-106178 - Implemented image from buffer

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#8 edit


[ROCm/clr commit: 5d09207455]
2017-01-30 13:13:28 -05:00
foreman d52c21c593 P4 to Git Change 1367051 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/30 03:00:06
SWDEV-2 - Change OpenCL version number from 2350 to 2351.

Affected files ...

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


[ROCm/clr commit: 6fdb718f12]
2017-01-30 03:08:58 -05:00
foreman 923717e1d7 P4 to Git Change 1367013 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/29 03:00:05
SWDEV-2 - Change OpenCL version number from 2349 to 2350.

Affected files ...

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


[ROCm/clr commit: e9533d4cb9]
2017-01-29 03:09:05 -05:00
foreman 363c8ebe9f P4 to Git Change 1366988 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/28 03:00:05
SWDEV-2 - Change OpenCL version number from 2348 to 2349.

Affected files ...

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


[ROCm/clr commit: 92d90b726f]
2017-01-28 03:14:01 -05:00
Aditya Atluri 4085e01263 removed host math functions from math_functions.h
Change-Id: I90d8784e2d6b58c6fade9f0fa12c0db3ee417d3e


[ROCm/clr commit: a5d017e406]
2017-01-27 17:38:43 -06:00
Aditya Atluri 324409b2bb changed device code tests to work not to work as one
Change-Id: I0eec1eab19dda3b703bc3a0d778a6bbb2802a412


[ROCm/clr commit: eee520def9]
2017-01-27 09:20:14 -06:00
Aditya Atluri ebb51a54b9 fixed arch compiler flag
Change-Id: I19f7a0ea513d6b8059f0c10cd0e7a5ead510e246


[ROCm/clr commit: a8c51b822b]
2017-01-27 08:51:48 -06:00
Aditya Atluri 6c272debb9 fixed threadfence ir
Change-Id: Ia3afb54bdb50864e678d849608d72a3c321edba1


[ROCm/clr commit: 537dc7597b]
2017-01-27 08:42:26 -06:00
Aditya Atluri 4b732551bb fixed kernel only compilation for module api
Change-Id: I567992fa9b87125318edba41fd82d2f7bc5504a1


[ROCm/clr commit: 33d89d06aa]
2017-01-27 08:41:42 -06:00
Rahul Garg 24a50f7606 hipMallocArray fixes for NV path
Change-Id: I1ca43e6bc0cd405998888005c20dfb1ea57003d5


[ROCm/clr commit: 125983eed9]
2017-01-27 14:32:08 +05:30
foreman aa850366f2 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


[ROCm/clr commit: 40561d2c67]
2017-01-27 03:12:31 -05:00
foreman ca4a2ca2a0 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


[ROCm/clr commit: 027f8d9108]
2017-01-26 14:52:51 -05:00
foreman ece92c4e21 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


[ROCm/clr commit: 5fd072d9b3]
2017-01-26 13:45:49 -05:00
pensun 41bb48dd49 more fix on hipmallocarray on NV path
Change-Id: I890a36cab10c101f4a112bc4567f765b318d486c


[ROCm/clr commit: f18efd5d15]
2017-01-26 12:30:52 -06:00
pensun 0ecc88bebd fix missing semicolon on NV path
Change-Id: I3cfecb7bd534578a1f5a07ca9397092dcf01db07


[ROCm/clr commit: 42f22162e0]
2017-01-26 11:28:15 -06:00
foreman 3bf60565c8 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


[ROCm/clr commit: 356b1574bf]
2017-01-26 03:14:16 -05:00
Ben Sander b46ee1d193 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.


[ROCm/clr commit: 1a24178c78]
2017-01-25 21:53:17 -06:00
Ben Sander ad2ba66ce6 Read HCC_OPT_FLUSH and optimize dispatch accordingly.
If HCC is in this mode, we can use less aggressive flushes in some
cases.


[ROCm/clr commit: 2f7a8ec39c]
2017-01-25 21:50:52 -06:00