Jatin Chaudhary
2b15151f95
Removing gcc test for clang
...
Change-Id: Iccf00221a07be920683207daa9ed0e0949259623
2020-02-19 11:09:47 -05:00
Payam
2a63942e35
Removed Static lib for hip target
...
Change-Id: Iea7fc3f26f5d99df622e69aab3898f7bc931fc58
2020-02-19 03:51:55 -05:00
Payam Ghafari
e2fce43499
Merge "removing static lib for hip target" into amd-master-next
2020-02-18 19:16:31 -05:00
Tao Sang
5956b28dcc
Merge "Temporarily comment out Hcc-specific APIs for CLang compiler" into amd-master-next
2020-02-18 18:50:05 -05:00
Evgeny Shcherbakov
50f1957d0d
Merge "adding 'hipHccModuleLaunchKernel' and 'hipExtModuleLaunchKernel'" into amd-master-next
2020-02-18 18:10:22 -05:00
Tao Sang
cc0147a3a3
Merge "Fix bug of hip/samples/2_Cookbook/7_streams" into amd-master-next
2020-02-18 17:41:34 -05:00
Christophe Paquot
9630e40beb
Introducing hip::Device which wraps around amd::Context and deviceId
...
Change-Id: Ie35a6edb65c001b35eb9f5d2af26e765dc41c00e
2020-02-18 17:18:56 -05:00
Payam
cb4637c222
removing static lib for hip target
...
Change-Id: I401f428469d5c1c03278f20c3c24c69636876f7c
2020-02-18 16:46:36 -05:00
Tao Sang
6772dd1bc1
Fix bug of hip/samples/2_Cookbook/7_streams
...
Initialize Kernel_descriptor with matched function name.
Change-Id: I26911d6bc9b2beae186a9e6f9441ce408521bce9
2020-02-18 13:53:21 -05:00
Karthik Jayaprakash
6ec4eb34f4
SWDEV-223394 - Pass module info from hipModuleGetTexRef to internal Platformstate:: functions.
...
Change-Id: I7d1ba3f940f595c3fca74a57fa20f484c52d4741
2020-02-18 11:23:03 -05:00
Payam Ghafari
ed71c618f0
Merge "updated package generation and removed hiphcc_static as a target for hip-vdi" into amd-master-next
2020-02-18 10:47:47 -05:00
Tao Sang
5b2ec8bdf8
Merge "Fix bug of hip/samples/0_Intro/hcc_dialects/vadd_hip" into amd-master-next
2020-02-17 22:01:12 -05:00
Christophe Paquot
9692ac6b5f
Don't create a marker for start event in hipModuleLaunchKernel
...
And also don't optimize the case where start==stop event to compute
elapsed time since the command can be a NDRange one.
HIP directed test will need to be fixed for that.
Change-Id: I64fadd6ab8ab1a490e7a2b7165a591df5a5cf3a2
2020-02-17 14:16:31 -08:00
Evgeny
05db3fceaa
adding 'hipHccModuleLaunchKernel' and 'hipExtModuleLaunchKernel'
...
Change-Id: Id9990ed3041b82956872a088ff019ade69d40afb
2020-02-17 16:06:24 -06:00
Payam Ghafari
a719e355d5
Merge "updated hipcc to include HSA path for clang builds as well" into amd-master-next
2020-02-17 02:01:37 -05:00
Tao Sang
b3f445c0f5
Temporarily comment out Hcc-specific APIs for CLang compiler
...
Temporarily comment out Hcc-specific template functions
hipExtLaunchKernelGGL and hipOccupancyMaxPotentialBlockSize for CLang
compiler so that all test cases under hip/samples can be built
successfully for Clang + Hip/Hcc runtime.
Change-Id: Iafc761257be4a7b34eafa6759a01f369570cd6ce
2020-02-16 22:26:47 -05:00
Tao Sang
30da92e2af
Fix bug of hip/samples/0_Intro/hcc_dialects/vadd_hip
...
For hipLaunchKernelGGL(), hmod->kernargs is empty, thus we need
insert hmod->kernargs[name_str] which is empty.
Change-Id: I95f818d0525da84452e66c5778f0648a643843c7
2020-02-16 17:58:04 -05:00
Payam
28d8a38c0e
updated package generation and removed hiphcc_static as a target for hip-vdi
...
Change-Id: I0067dd6341f47a212cb02b8d43d3ea01644c2391
2020-02-16 03:00:59 -05:00
Tao Sang
9a005eacf3
Support defaultDriver test with Clang+Hcc Runtime
...
Fix the following issues:
1.Ignore hidden arguments of kernel functions.
2.Look up both origial function name and function name with .kd postfix
when argments are retrived from module.
3.Addition, fix compiling issue of LaunchKernel test app.
Change-Id: I9400943f2f02433cb4409b19c0cac3626c2bc454
2020-02-15 19:29:13 -05:00
Payam
fabe62e31f
removing oocupancy tests from hip-vdi for now
...
Change-Id: I06e966d07021af87fa2c195e4bbaf6bcc336658d
2020-02-13 21:40:06 -05:00
Christophe Paquot
f2eb8ec26c
Merge "hipLaunchByPtr and hipLaunchKernel deviceId potential issue" into amd-master-next
2020-02-13 18:49:06 -05:00
Payam
b95968187b
updated hipcc to include HSA path for clang builds as well
...
Change-Id: Icaaa68fdbe79fb16e4e9fedd420460f1479d7fe0
2020-02-13 16:48:24 -05:00
Christophe Paquot
1d4bb503ae
SWDEV-222949 - hipEventRecord
...
hipEventRecord should always create a new marker so it can track work going on at the time the API is called.
Change-Id: I10ce98044be894fbacab8798441ec3d3f2753b93
2020-02-13 15:01:49 -05:00
Christophe Paquot
cc63d2d7b8
hipLaunchByPtr and hipLaunchKernel deviceId potential issue
...
Those APIs should look at the device associated with the stream first.
If that stream is null then get the current device ID.
Change-Id: Iedde1d1644818ba64f128b988f0bd9674f5b8ad6
2020-02-13 12:00:30 -08:00
Tao Sang
f456989339
Merge "Support app(hcc compiled/Hip-Vdi runtime linked)" into amd-master-next
2020-02-13 14:25:30 -05:00
Aaron Enye Shi
85b6905871
HIP-VDI fix CPACK packaging dependencies
...
Change-Id: I64d803499dd8b2fc80b1320f71115ebaf019a9e7
2020-02-13 10:02:49 -05:00
Tao Sang
2699b566cc
Support app(hcc compiled/Hip-Vdi runtime linked)
...
The issues of the following functions have been fixed.
hipModuleLoad: Make Hip-Vdi runtime able to read code object module
generated by Hcc compiler.
hipLaunchKernel: Use introspect method to find function if it cannot
be found from platform state instance.
Change-Id: Id740e5a96614ec6a0b6c704f8f74600bfdc4983e
2020-02-12 16:42:54 -05:00
Laurent Morichetti
ba0674f0a6
Remove cl_icd.cpp from the build.
...
We should be using the temporary fixme.cpp instead.
Change-Id: I7e7a04bb518f56584c41bdb46a9192bde1f70060
2020-02-12 10:46:33 -08:00
Mark Searles
f2c1a4d827
Change 2068543 by michliao@hliao-dev-11-hip-workspace on 2020/02/10 10:04:50
...
SWDEV-125823 - Fix the build issue due to API interface change.
- PR#1625 is temporarily reverted. Revert CL#2064519 correspondingly.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#61 edit
Change-Id: I519b11532d7e6fe8cbee41804155cc9ca64e596c
2020-02-12 00:22:48 -08:00
Laurent Morichetti
2cf3257795
Merge branch 'master' into amd-master-next
...
Change-Id: Ibb7775e7acd263d2ece40a241517bbd15976fdd4
2020-02-12 00:14:07 -08:00
Jatin Chaudhary
ab7526f64c
Revert "Sync hip-targets*.cmake in package with install changes ( #1831 )" ( #1860 )
...
Fixes SWDEV-222155 & SWDEV-222158
This reverts commit 6891615a15 .
2020-02-11 11:56:57 +05:30
Christophe Paquot
6462732e49
SWDEV-220533 - HostMapped should use fine grained.
...
Change-Id: I4ad2064e8e5ea1cd4ed7df143c778ccb685c4f22
2020-02-10 16:53:06 -05:00
Payam Ghafari
b66451e000
Merge "Excluding vdi platform for now from the following tests so we can build" into amd-master-next
2020-02-10 14:28:44 -05:00
Maneesh Gupta
6614ae33e0
gedit/hip.lang does not need a seperate license
2020-02-10 16:27:20 +05:30
Maneesh Gupta
9acdcf27c5
Update copyright section in gedit/hip.lang
2020-02-10 16:25:38 +05:30
Maneesh Gupta
f8e1c01900
Revert "Match Occupancy APIs syntax with CUDA ( #1625 )" ( #1857 )
...
Reverting this for now till we figure out how to avoid the build
breakage.
This reverts commit fa98798b63 .
2020-02-10 10:45:28 +05:30
Alex Voicu
dd34ea95d6
(Maybe) Match alignment between Clang and GCC. ( #1789 )
...
Should fix #1740 and the related internal bug.
2020-02-10 10:44:49 +05:30
mhbliao
a01b262660
[hip] Cleanup compiler wrapper for HIP-Clang. ( #1847 )
2020-02-07 13:28:26 -08:00
Saleel Kudchadker
7eadbcdcc4
HIP/VDI CMake fixes
...
Fix the install directory for libamdhip64.so and create libhiprtc.so symlink
Change-Id: Id731bfa18bb3585c3f9e3ae6697b4f4687c49195
2020-02-07 00:01:35 -08:00
Payam
e4e8c4b74b
Excluding vdi platform for now from the following tests so we can build
...
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b
2020-02-07 02:16:05 -05:00
Michael LIAO
66678b0170
[hipcc] Skip warning on gfx000.
...
- The known target checking should skip `gfx000` as well as it won't be
used in real compilation command formation. The avoid generating
annoying warning on `gfx000`.
2020-02-06 17:09:14 -05:00
Saleel Kudchadker
9bbd94f5ef
Disable symbol versioning for HIP/VDI
...
Change-Id: Ide6372bab136dd5df886ed78f61cd6c06e98e983
2020-02-05 22:20:51 -08:00
Mark Searles
d569132d39
Change 2064519 by michliao@hliao-dev-00-hip.rocm-workspace on 2020/01/30 11:34:18
...
SWDEV-125823 - Fix the build issue due to API interface change.
- `hipOccupancyMaxActiveBlocksPerMultiprocessor` interface is revised
and the runtime needs updating.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#60 edit
Change-Id: Ia7901b0dbbfd37977ce4adf2ae1a821aba0ac044
2020-02-05 14:59:37 -08:00
Laurent Morichetti
258adce78e
Merge branch 'master' into amd-master-next
...
Change-Id: Ib7e7824073f4dfc391fb3833fc90e11b327d3c22
2020-02-05 14:56:08 -08:00
Siu Chi Chan
93e62401c7
Enable code object v3 codgen when compiling with HCC ( #1836 )
...
Change-Id: I590c05a418cc37ec247b89124cef17a7fe8b27e2
2020-02-05 20:56:33 +05:30
vsytch
ef514eef71
Device texture functions should not normalize the sampled pixel ( #1826 )
...
* Device texture functions should not normalize the sampled pixel. This is already done by HW.
* Add support to use h/w capability for normalized float data convertion for driver API's
Co-authored-by: ansurya <50609411+ansurya@users.noreply.github.com >
2020-02-05 20:56:17 +05:30
Laurent Morichetti
b57d64c22e
Merge "Update copyright info for VDI files" into amd-master-next
2020-02-04 17:19:31 -05:00
Laurent Morichetti
2764aee583
Update copyright info for VDI files
...
Change-Id: Ib160fbf89ec89a5895321f73402a33b4d344a68f
2020-02-04 08:47:10 -08:00
saleelk
499938d974
Implement __hipPushCallConfiguration/__hipPopCallConfiguration for hip_clang ( #1845 )
...
This is needed so that the right symbols are present if we want to use hip-clang with hip/hcc runtime
2020-02-04 19:37:57 +05:30
lthakur
4d472b777f
[dtest] Update hipLaunchCoopMultiKernel.cpp ( #1844 )
...
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.
2020-02-04 19:37:38 +05:30