Commit Graph

1448 Commits

Author SHA1 Message Date
Aditya Atluri 1546732604 Added new API, hipMemPtrGetInfo
1. This API returns memory allocation size of pointer
2. Added test to check its functionality

Change-Id: I87976d817b5a6ca5530336c09e7cb0420601cb2c
2017-03-07 13:46:29 -06:00
Aditya Atluri f86f3b3b33 added new field to hipDeviceProp_t structure gcnArch.
1. It is an integer containing gfx values 701, 801, 802, 803
2. On NV path, it is zero

Change-Id: I2b4c7f48981d0214d8c6b1905d2cc85b16203419
2017-03-07 11:24:32 -06:00
Maneesh Gupta 12e8d635aa FindHIP: better handling for custom HCC_HOME
Change-Id: Ica267de11cde58d1e759cd1fd053b699649ea76a
2017-03-07 14:40:04 +05:30
Ben Sander d572e0616e Modify memcpy and memset to follow C/C++ standard:
- memcpy src is const
    - memset val is int
2017-03-06 16:38:22 -06:00
Rahul Garg c8e985f83c Removed hsakmt headers
Change-Id: I4ffc95d5823489195ebc5638226b49ea2995f603
2017-03-06 22:37:05 +05:30
Siu Chi Chan 910df3d80f fix hcc version detection in hipcc
Change-Id: I880be03ad67e99280a259369bfe25488bf53f0bd
2017-03-06 15:34:30 +05:30
Siu Chi Chan c3126bab8a fix hcc version string extraction
Change-Id: Ie209b6deae55c779a577aaccb1bc21f969f69e14
2017-03-06 15:33:43 +05:30
Maneesh Gupta aca015c47d CMakeLists: Create test targets only if HIP install location is writable
Change-Id: I79f28884b0f117f2824ca8877c25b586bce62e5b
2017-03-06 15:32:21 +05:30
Evgeny Mankov aa2fc24482 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ update all Cuda 7.5 RT API enum values.
2017-03-03 22:05:23 +03:00
Evgeny Mankov 749803c849 [HIPIFY] Sync HIPIFY with HIP by enum values.
+ all Cuda 7.5 RT API enum values are synced.
+ a few missing functions are added.
+ CONV_EXEC type is added for Execution control functions and data types.
2017-03-03 21:59:05 +03:00
Evgeny Mankov 6421a1e79e [HIP] [FIX] Memcpy Async functions on nvcc path.
+ in hipMemcpyDtoDAsync: cuMemcpyDtoD -> cuMemcpyDtoDAsync
+ in hipMemcpyDtoHAsync: cuMemcpyDtoH -> cuMemcpyDtoHAsync

P.S.
"The types CUstream and cudaStream_t are identical and may be used interchangeably", thus explicit c-like type cast is not needed, aka CUstream(stream).
2017-03-01 23:04:34 +03:00
Aditya Atluri e7ccc995ee changed __half enabling from 4 to >3
Change-Id: Id974c6d5326e87a4c5941f831c5bb2747cdebd2d
2017-02-28 17:13:29 -06:00
pensun fd610e497b Define __HIPCC__ flag at compile time when using HIPCC on HCC path
Change-Id: I5e967e0e2327264d5d3b0ca705c2504fcd33d75e
2017-02-28 16:20:48 -06:00
Evgeny Mankov f9ad2dca7e [HIP] Add missing Device attribute on nvcc path.
+ missing cudaDevAttrComputeCapabilityMinor case as added for hipDeviceGetAttribute query for hipDeviceAttributeComputeCapabilityMinor.
2017-02-28 18:40:13 +03:00
pensun ac4b7e3f91 update hip_porting_guide regarding platform depended macros
Change-Id: I3029c6ae6cb280500bba294925ed6e9dc9dcc94d
2017-02-28 07:33:01 -06:00
Maneesh Gupta 0672b19264 packaging script changes for hip_hcc
Change-Id: I06cce6048204315a891e3a12638a3067644cfb43
2017-02-28 12:02:53 +05:30
pensun df9cbb6067 remove extra spaces for hip_common.h platform defines
Change-Id: Ie0e39256abba307429985371671cde01f5ea2cc9
2017-02-27 12:55:22 -06:00
Rahul Garg bddd6b73c0 Context management related changes in HIP.
-
-Contexts across threads are listed under device
-Device reset cleans up all contexts and re-initializes _primaryCtx

Change-Id: Ie1cfbb26d43a8dc6869be3e6ebaf7344ce374643
2017-02-27 15:24:17 +05:30
Maneesh Gupta 4a6166cd86 Fix nvcc path samples that include math_functions.h
Change-Id: I94bb577b93983535178d8f0dcae57aaa72871534
2017-02-27 13:20:05 +05:30
Maneesh Gupta a0b51c69a7 Disable some tests which are broken on nvcc path
Change-Id: I6f8df7687ff1798dc17f6c9b8a7f4cd029ce45d8
2017-02-27 13:19:06 +05:30
Maneesh Gupta f1c3dd0dff Fix compilation of some broken tests on nvcc path
Change-Id: I92406af00c2de09d728e9b7f661c1f3873470560
2017-02-27 13:17:51 +05:30
Maneesh Gupta 5f689cb986 directed tests no longer run in an subdirectory
- target "make test" will no longer build and run tests. It will only run the tests.
- added new target "make check" which will build and run the tests.
- target "make check" will build tests serially. Use -j<N> to build tests in parallel.

Change-Id: I24c7932bf9798364a59f44631fbabcf9a5da5e17
2017-02-27 13:14:08 +05:30
Maneesh Gupta 470dd2fbcf FindHIP: added new macro HIP_RESET_FLAGS
Change-Id: I0af491f6689abf1c1b5691261fe1f3e61a5d916d
2017-02-27 13:11:11 +05:30
Aditya Atluri 2e245ae58c Added initial support for hipMemcpyFromSymbol. But not working!
Change-Id: I48d8c7de4ec9f85c6c942be995fb488a3931f5d7
2017-02-23 11:29:06 -06:00
Maneesh Gupta 270054859a Fix export interfaces in hip-config.cmake
Change-Id: Ifad4661ab17d7e6edb6ab300f1e92552ed917950
2017-02-23 11:18:06 +05:30
Aditya Atluri 639fd4dd5e added runtime api hipMemcpyFromSymbolAsync
Change-Id: Ibaf925faf0ba464dd0ed6c5ea74c224c2ce38889
2017-02-22 19:16:35 -06:00
Aditya Atluri d52c5867f2 Enable symbol tests
Change-Id: I6bd036bf00c8051c8ff728ee60562c4ebd222160
2017-02-22 13:42:03 -06:00
Paul 5dbf7e0618 Update for lower case hip 2017-02-22 15:18:38 +05:30
Paul 2e83e3a01d Change order of find_dependency 2017-02-22 15:18:11 +05:30
Aditya Atluri a1f3955860 added typedef for half and half2
Change-Id: Ic844fa31b64a0354484b418df71869c2807200cc
2017-02-21 14:44:37 -06:00
Evgeny Mankov 2461ddd79d [HIP] annotation update.
cudaStreamAddCallback and cudaStreamWaitEvent were excluded from unsupported.
2017-02-20 21:26:40 +03:00
Evgeny Mankov bd9b674d3d [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
cudaDeviceGetPCIBusId -> hipDeviceGetPCIBusId
2017-02-20 21:21:47 +03:00
Evgeny Mankov 6e611aa574 [HIPIFY] sync with HIP by HIP_UNSUPPORTED Runtime functions. 2017-02-20 21:19:34 +03:00
Evgeny Mankov 5c11789358 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
Section "20. Data types used by CUDA Runtime API and supported by HIP" is added.

+ 44 supported data types are added
- 46 at least to support

All the supported data types are also supported by hipify-clang (synced).
2017-02-20 18:32:54 +03:00
Evgeny Mankov 0cbe335c8f [HIPIFY] Sync HIPIFY with HIP by data types. 2017-02-20 18:28:59 +03:00
Evgeny Mankov ee157678b9 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
Move hipBindTexture and hipUnbindTexture to "18. C++ API Routines" from "13. Texture Reference Management". They are C++, not C.
2017-02-17 18:09:08 +03:00
Evgeny Mankov a35d4b75c5 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ 21 supported functions
- 99 at least to support

All the supported functions are also supported by hipify-clang (synced).
2017-02-17 18:06:47 +03:00
Aditya Atluri 39548fb023 removed hipblas samples as it is not yet supported
Change-Id: I354b710e652ce0d0413d670530ceb8b70f4993d5
2017-02-17 08:51:02 -06:00
Evgeny Mankov dc8e8caf41 [HIPIFY] Add more Stream and Occupancy functions. 2017-02-17 15:04:15 +03:00
Evgeny Mankov 3b6990c8d6 [HIPIFY] Add missing Memcpy functions.
+ cudaChooseDevice
2017-02-16 23:03:01 +03:00
Evgeny Mankov 7b44dbbe37 [HIPIFY] Add more Memory Management functions 2017-02-16 21:26:44 +03:00
Evgeny Mankov b135b24200 [HIPIFY] Add Channel (Textures) support. 2017-02-16 21:10:10 +03:00
Evgeny Mankov ea95f3166a [HIPIFY] Add Inter-Process Communications (IPC) support. 2017-02-16 20:24:53 +03:00
Evgeny Mankov bbbe5814c1 [HIPIFY] Add CUDA Driver LAUNCH_PARAM defines. 2017-02-16 20:00:36 +03:00
Evgeny Mankov 93c1e31b36 [HIPIFY] Add safe type check for cudaChooseDevice matcher. 2017-02-16 19:38:35 +03:00
Siu Chi Chan 806deeb476 Squashed commit of the following:
commit 931d3de6c1c903cfd47842bc5026a9294ac492b4
Author: Siu Chi Chan <siuchi.chan@amd.com>
Date:   Mon Feb 13 10:54:06 2017 -0500

    only force to libstdc++ if the g++ is older than version 5 since hcc already defaults to libstdc++ with newer g++

commit 1ef8d71aa788de7b9eead4906fe56186f06d7d3f
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:44:11 2017 -0500

    remove hardcoded -lc++ in tests

commit 5d99ef338eb3a66523cc9ddd139e86c6fd707b9c
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:35:46 2017 -0500

    force include libstdc++ headers and stdc++ only if g++ version < 5 since hcc uses libstdc++ by default if g++ > 5 is present

commit a2bc21b24d100feefe91cd3cb2271238bda0738a
Author: scchan <siuchi.chan@amd.com>
Date:   Fri Feb 10 04:36:27 2017 -0500

    use hcc-config to generate compiler and linker flags

Change-Id: I13a79629c0adfd75439a47d0488ff4fd619c55ba
(cherry picked from commit 866e744e40cf1378af8a679b54959bf5226c340f)
2017-02-16 13:12:32 +05:30
Evgeny Mankov 950434f4af [HIPIFY] [Fix] Crash on thrust example fallback_allocator.cu.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/65

[Bug]
Access violation in cudaStructVar matcher.

      StringRef name = structVar->getType()
        ->getAsStructureType()
        ->getDecl() // <--- Access Violation
        ->getNameAsString();

[Solution]
Add isStructureType() check before getting type as Struct.

[ToDo]
Find case-studies for that StructVar matcher with types other than Struct.
2017-02-15 19:48:31 +03:00
Evgeny Mankov e39ed24a50 [HIPIFY] Add file:line:col info to [HIPIFY] warnings/errors. 2017-02-14 21:36:49 +03:00
scchan ad9d9b25c1 calls isfinite,isinf,isnan from the std namespace on the host
Change-Id: Ica2370075b89713eecfd96102e2f4e0ab9961ce4
2017-02-14 11:52:09 -05:00
Evgeny Mankov b3941dd546 [HIPIFY] Add more unhandled refs for opaque pointers.
CUfunc_st -> hipFunction_t *
CUctx_st -> hipCtx_t *
CUmod_st -> hipModule_t *
2017-02-14 17:34:10 +03:00