Commit Graph

64357 Commits

Author SHA1 Message Date
Maneesh Gupta 0827e44a90 Updates to HIP version string format
HIP patch version is now a monotonically increasing number

Change-Id: Ia6e35794b702bbd2018c502564d0a65997819687
2016-08-12 23:21:37 +05:30
Maneesh Gupta 54d1f14ae0 Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830


[ROCm/hip-tests commit: 339590da90]
2016-08-12 13:50:22 +05:30
Maneesh Gupta 339590da90 Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830
2016-08-12 13:50:22 +05:30
Maneesh Gupta 07262c48ba Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830


[ROCm/clr commit: 7c03a0604a]
2016-08-12 13:50:22 +05:30
Maneesh Gupta 7c03a0604a Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830
2016-08-12 13:50:22 +05:30
Maneesh Gupta 0ec10f571c Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830


[ROCm/hip commit: d192976b00]
2016-08-12 13:50:22 +05:30
Maneesh Gupta d192976b00 Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830
2016-08-12 13:50:22 +05:30
foreman d2fe4d8738 P4 to Git Change 1302360 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/08/12 03:00:08
SWDEV-2 - Change OpenCL version number from 2193 to 2194.

Affected files ...

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


[ROCm/clr commit: 5f050651a1]
2016-08-12 03:08:54 -04:00
foreman 5f050651a1 P4 to Git Change 1302360 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/08/12 03:00:08
SWDEV-2 - Change OpenCL version number from 2193 to 2194.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1940 edit
2016-08-12 03:08:54 -04:00
Jeffrey Poznanovic cea99c239b Adding hipblas include files
Change-Id: I73064d410acd8f655dc62eaeb6f4bdefc5381e35


[ROCm/clr commit: dd680ad86a]
2016-08-12 11:59:25 +05:30
Jeffrey Poznanovic dd680ad86a Adding hipblas include files
Change-Id: I73064d410acd8f655dc62eaeb6f4bdefc5381e35
2016-08-12 11:59:25 +05:30
Jeffrey Poznanovic cbe87288c8 Adding hipblas include files
Change-Id: I73064d410acd8f655dc62eaeb6f4bdefc5381e35


[ROCm/hip commit: 48491a3978]
2016-08-12 11:59:25 +05:30
Jeffrey Poznanovic 48491a3978 Adding hipblas include files
Change-Id: I73064d410acd8f655dc62eaeb6f4bdefc5381e35
2016-08-12 11:59:25 +05:30
foreman 229a8862dc P4 to Git Change 1302288 by cpaquot@hog-ocl on 2016/08/11 19:32:24
SWDEV-100298 - oclPerfImageMapUnmap test fails in Fiji
	Reverted back CL #1295719 and instead copy back the whole host mem data onto the device memory since that's what is done at map time.

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

Affected files ...

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


[ROCm/clr commit: 4bc132bc87]
2016-08-11 20:19:39 -04:00
foreman 4bc132bc87 P4 to Git Change 1302288 by cpaquot@hog-ocl on 2016/08/11 19:32:24
SWDEV-100298 - oclPerfImageMapUnmap test fails in Fiji
	Reverted back CL #1295719 and instead copy back the whole host mem data onto the device memory since that's what is done at map time.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#7 edit
2016-08-11 20:19:39 -04:00
Aditya Atluri 570e6242a3 Added fix for using HCC_VERSION
1. The variable is brought outside the conditional so that its scope is increased

Change-Id: I2d2689553e67930050fe5b3648739f0f72c3bbc8


[ROCm/clr commit: 5a47758033]
2016-08-11 16:13:44 -05:00
Aditya Atluri 5a47758033 Added fix for using HCC_VERSION
1. The variable is brought outside the conditional so that its scope is increased

Change-Id: I2d2689553e67930050fe5b3648739f0f72c3bbc8
2016-08-11 16:13:44 -05:00
Aditya Atluri 25fa1336e6 Added fix for using HCC_VERSION
1. The variable is brought outside the conditional so that its scope is increased

Change-Id: I2d2689553e67930050fe5b3648739f0f72c3bbc8


[ROCm/hip commit: 3be747c41e]
2016-08-11 16:13:44 -05:00
Aditya Atluri 3be747c41e Added fix for using HCC_VERSION
1. The variable is brought outside the conditional so that its scope is increased

Change-Id: I2d2689553e67930050fe5b3648739f0f72c3bbc8
2016-08-11 16:13:44 -05:00
Aditya Atluri a178c9b9e2 Change hipcc to take HCC_HOME from hipconfig by default
1. Current implementation checks both env var and value in hipconfig and reports error
2. New implementation gives value in hipconfig with highest priority
3. If hipconfig is not present, fall back to env variables.

To Devs: No need to switch between environment variables for different HCC + different HIP.

Change-Id: I6cdf37e1429d7f07be3a68c7e5ba1533d832962b


[ROCm/clr commit: df1dd53453]
2016-08-11 15:31:24 -05:00
Aditya Atluri df1dd53453 Change hipcc to take HCC_HOME from hipconfig by default
1. Current implementation checks both env var and value in hipconfig and reports error
2. New implementation gives value in hipconfig with highest priority
3. If hipconfig is not present, fall back to env variables.

To Devs: No need to switch between environment variables for different HCC + different HIP.

Change-Id: I6cdf37e1429d7f07be3a68c7e5ba1533d832962b
2016-08-11 15:31:24 -05:00
Aditya Atluri fd564cc04c Change hipcc to take HCC_HOME from hipconfig by default
1. Current implementation checks both env var and value in hipconfig and reports error
2. New implementation gives value in hipconfig with highest priority
3. If hipconfig is not present, fall back to env variables.

To Devs: No need to switch between environment variables for different HCC + different HIP.

Change-Id: I6cdf37e1429d7f07be3a68c7e5ba1533d832962b


[ROCm/hip commit: ef68f2f293]
2016-08-11 15:31:24 -05:00
Aditya Atluri ef68f2f293 Change hipcc to take HCC_HOME from hipconfig by default
1. Current implementation checks both env var and value in hipconfig and reports error
2. New implementation gives value in hipconfig with highest priority
3. If hipconfig is not present, fall back to env variables.

To Devs: No need to switch between environment variables for different HCC + different HIP.

Change-Id: I6cdf37e1429d7f07be3a68c7e5ba1533d832962b
2016-08-11 15:31:24 -05:00
Evgeny Mankov dad90dcfa1 clang-hipify: Add support for nested macro expansion and translation.
Fixes bug “HIPIFY: nested macro is not hipified”
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/33

Example:
#include "cuda_runtime.h"
#define MY_MACRO(func, flags) (func, flags)
...
cudaEvent_t *event = NULL;
MY_MACRO(cudaEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

where cudaEventDisableTiming is a defined numeric literal and thus a nested MACRO:
#define cudaEventDisableTiming 0x02 /**< Event will not record timing data */

After hipifying now:
MY_MACRO(hipEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

Should be:
MY_MACRO(hipEventCreateWithFlags(event, hipEventDisableTiming), NULL);


[ROCm/clr commit: aba73d6673]
2016-08-11 22:29:55 +03:00
Evgeny Mankov aba73d6673 clang-hipify: Add support for nested macro expansion and translation.
Fixes bug “HIPIFY: nested macro is not hipified”
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/33

Example:
#include "cuda_runtime.h"
#define MY_MACRO(func, flags) (func, flags)
...
cudaEvent_t *event = NULL;
MY_MACRO(cudaEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

where cudaEventDisableTiming is a defined numeric literal and thus a nested MACRO:
#define cudaEventDisableTiming 0x02 /**< Event will not record timing data */

After hipifying now:
MY_MACRO(hipEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

Should be:
MY_MACRO(hipEventCreateWithFlags(event, hipEventDisableTiming), NULL);
2016-08-11 22:29:55 +03:00
Evgeny Mankov 4596f44fbe clang-hipify: Add support for nested macro expansion and translation.
Fixes bug “HIPIFY: nested macro is not hipified”
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/33

Example:
#include "cuda_runtime.h"
#define MY_MACRO(func, flags) (func, flags)
...
cudaEvent_t *event = NULL;
MY_MACRO(cudaEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

where cudaEventDisableTiming is a defined numeric literal and thus a nested MACRO:
#define cudaEventDisableTiming 0x02 /**< Event will not record timing data */

After hipifying now:
MY_MACRO(hipEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

Should be:
MY_MACRO(hipEventCreateWithFlags(event, hipEventDisableTiming), NULL);


[ROCm/hip commit: 2aacb02358]
2016-08-11 22:29:55 +03:00
Evgeny Mankov 2aacb02358 clang-hipify: Add support for nested macro expansion and translation.
Fixes bug “HIPIFY: nested macro is not hipified”
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/33

Example:
#include "cuda_runtime.h"
#define MY_MACRO(func, flags) (func, flags)
...
cudaEvent_t *event = NULL;
MY_MACRO(cudaEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

where cudaEventDisableTiming is a defined numeric literal and thus a nested MACRO:
#define cudaEventDisableTiming 0x02 /**< Event will not record timing data */

After hipifying now:
MY_MACRO(hipEventCreateWithFlags(event, cudaEventDisableTiming), NULL);

Should be:
MY_MACRO(hipEventCreateWithFlags(event, hipEventDisableTiming), NULL);
2016-08-11 22:29:55 +03:00
foreman 65217be249 P4 to Git Change 1301678 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/08/11 03:00:14
SWDEV-2 - Change OpenCL version number from 2192 to 2193.

Affected files ...

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


[ROCm/clr commit: 3bbba6ae4f]
2016-08-11 03:08:11 -04:00
foreman 3bbba6ae4f P4 to Git Change 1301678 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/08/11 03:00:14
SWDEV-2 - Change OpenCL version number from 2192 to 2193.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1939 edit
2016-08-11 03:08:11 -04:00
pensun e0a47d1e32 add note in hip_faq regarding workaround that add keyword of static for all forceinline functions
Change-Id: Ia13ba59b1e54df8ead5a96a952084144431ec72a


[ROCm/clr commit: 3b268c54f8]
2016-08-10 11:31:13 -05:00
pensun 3b268c54f8 add note in hip_faq regarding workaround that add keyword of static for all forceinline functions
Change-Id: Ia13ba59b1e54df8ead5a96a952084144431ec72a
2016-08-10 11:31:13 -05:00
pensun 6322747871 add note in hip_faq regarding workaround that add keyword of static for all forceinline functions
Change-Id: Ia13ba59b1e54df8ead5a96a952084144431ec72a


[ROCm/hip commit: 4553e4e7f7]
2016-08-10 11:31:13 -05:00
pensun 4553e4e7f7 add note in hip_faq regarding workaround that add keyword of static for all forceinline functions
Change-Id: Ia13ba59b1e54df8ead5a96a952084144431ec72a
2016-08-10 11:31:13 -05:00
Ben Sander a4bfccf628 Context update.
- Remove tls_deviceID.
- Add first passing test.

Change-Id: If3e2f254abf589028cfe4f9e6369745f04160de0


[ROCm/clr commit: a9bcee3d77]
2016-08-10 08:59:47 -05:00
Ben Sander a9bcee3d77 Context update.
- Remove tls_deviceID.
- Add first passing test.

Change-Id: If3e2f254abf589028cfe4f9e6369745f04160de0
2016-08-10 08:59:47 -05:00
Ben Sander 0221323977 Context update.
- Remove tls_deviceID.
- Add first passing test.

Change-Id: If3e2f254abf589028cfe4f9e6369745f04160de0


[ROCm/hip commit: 89164259ab]
2016-08-10 08:59:47 -05:00
Ben Sander 89164259ab Context update.
- Remove tls_deviceID.
- Add first passing test.

Change-Id: If3e2f254abf589028cfe4f9e6369745f04160de0
2016-08-10 08:59:47 -05:00
Ben Sander f7c955104a Document workaround for parenthesis+macro+hipLaunchKernel
Change-Id: Ie04c99db92d6499ddde93028a96f9d8f72d3f992


[ROCm/clr commit: e23cd0dd3c]
2016-08-10 08:59:47 -05:00
Ben Sander e23cd0dd3c Document workaround for parenthesis+macro+hipLaunchKernel
Change-Id: Ie04c99db92d6499ddde93028a96f9d8f72d3f992
2016-08-10 08:59:47 -05:00
Ben Sander c9c8c1323f Document workaround for parenthesis+macro+hipLaunchKernel
Change-Id: Ie04c99db92d6499ddde93028a96f9d8f72d3f992


[ROCm/hip commit: 1786b120ed]
2016-08-10 08:59:47 -05:00
Ben Sander 1786b120ed Document workaround for parenthesis+macro+hipLaunchKernel
Change-Id: Ie04c99db92d6499ddde93028a96f9d8f72d3f992
2016-08-10 08:59:47 -05:00
foreman bc7dbe7743 P4 to Git Change 1301135 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/08/10 03:00:08
SWDEV-2 - Change OpenCL version number from 2191 to 2192.

Affected files ...

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


[ROCm/clr commit: 6cadecccfb]
2016-08-10 03:04:42 -04:00
foreman 6cadecccfb P4 to Git Change 1301135 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/08/10 03:00:08
SWDEV-2 - Change OpenCL version number from 2191 to 2192.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1938 edit
2016-08-10 03:04:42 -04:00
Maneesh Gupta 9816ef5452 Allow cmake to be run multiple times in directed tests
Change-Id: I9d68fdefd9f72895ad4bdb310fcf3c6e52dbbf02


[ROCm/clr commit: 5fe7159baf]
2016-08-10 09:49:07 +05:30
Maneesh Gupta 5fe7159baf Allow cmake to be run multiple times in directed tests
Change-Id: I9d68fdefd9f72895ad4bdb310fcf3c6e52dbbf02
2016-08-10 09:49:07 +05:30
Maneesh Gupta 8e648b1a33 Allow cmake to be run multiple times in directed tests
Change-Id: I9d68fdefd9f72895ad4bdb310fcf3c6e52dbbf02


[ROCm/hip commit: 2e9adefd71]
2016-08-10 09:49:07 +05:30
Maneesh Gupta 2e9adefd71 Allow cmake to be run multiple times in directed tests
Change-Id: I9d68fdefd9f72895ad4bdb310fcf3c6e52dbbf02
2016-08-10 09:49:07 +05:30
foreman 8765b6d785 P4 to Git Change 1300823 by smekhano@stas-nova-hsa on 2016/08/09 15:13:33
SWDEV-100152 - HSA HLC: replace family names with GFX#
	Testing: smoke, precheckin
	Reviewed by Evgeny Mankov

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#34 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#29 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAIL.h#43 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAIL.td#12 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILISelLowering.cpp#121 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILSubtarget.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILSubtarget.h#17 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/bin/test_driver.pl#32 edit


[ROCm/clr commit: c3f326baf2]
2016-08-09 15:31:20 -04:00
foreman c3f326baf2 P4 to Git Change 1300823 by smekhano@stas-nova-hsa on 2016/08/09 15:13:33
SWDEV-100152 - HSA HLC: replace family names with GFX#
	Testing: smoke, precheckin
	Reviewed by Evgeny Mankov

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#34 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#29 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAIL.h#43 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAIL.td#12 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILISelLowering.cpp#121 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILSubtarget.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILSubtarget.h#17 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/bin/test_driver.pl#32 edit
2016-08-09 15:31:20 -04:00
Maneesh Gupta 0dd56073db Fix build issues due to refactoring changes
Change-Id: I0a709ff4864244ba1b49e1a25327e3901ed6e17f


[ROCm/clr commit: fcafb975a6]
2016-08-09 22:49:32 +05:30