コミットグラフ

1424 コミット

作成者 SHA1 メッセージ 日付
Aditya Atluri fe81d08987 Added new API, hipMemPtrGetInfo
1. This API returns memory allocation size of pointer
2. Added test to check its functionality

Change-Id: I87976d817b5a6ca5530336c09e7cb0420601cb2c


[ROCm/hip commit: 1546732604]
2017-03-07 13:46:29 -06:00
Aditya Atluri 6cbeeb8e59 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


[ROCm/hip commit: f86f3b3b33]
2017-03-07 11:24:32 -06:00
Maneesh Gupta d898444c44 FindHIP: better handling for custom HCC_HOME
Change-Id: Ica267de11cde58d1e759cd1fd053b699649ea76a


[ROCm/hip commit: 12e8d635aa]
2017-03-07 14:40:04 +05:30
Ben Sander 0dd1393f97 Modify memcpy and memset to follow C/C++ standard:
- memcpy src is const
    - memset val is int


[ROCm/hip commit: d572e0616e]
2017-03-06 16:38:22 -06:00
Rahul Garg 6e13b64b35 Removed hsakmt headers
Change-Id: I4ffc95d5823489195ebc5638226b49ea2995f603


[ROCm/hip commit: c8e985f83c]
2017-03-06 22:37:05 +05:30
Siu Chi Chan c441371fef fix hcc version detection in hipcc
Change-Id: I880be03ad67e99280a259369bfe25488bf53f0bd


[ROCm/hip commit: 910df3d80f]
2017-03-06 15:34:30 +05:30
Siu Chi Chan 7d91578dcd fix hcc version string extraction
Change-Id: Ie209b6deae55c779a577aaccb1bc21f969f69e14


[ROCm/hip commit: c3126bab8a]
2017-03-06 15:33:43 +05:30
Maneesh Gupta 6d72290788 CMakeLists: Create test targets only if HIP install location is writable
Change-Id: I79f28884b0f117f2824ca8877c25b586bce62e5b


[ROCm/hip commit: aca015c47d]
2017-03-06 15:32:21 +05:30
Evgeny Mankov 3223473f95 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ update all Cuda 7.5 RT API enum values.


[ROCm/hip commit: aa2fc24482]
2017-03-03 22:05:23 +03:00
Evgeny Mankov 5c0ec42554 [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.


[ROCm/hip commit: 749803c849]
2017-03-03 21:59:05 +03:00
Evgeny Mankov b8fbb0ea23 [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).


[ROCm/hip commit: 6421a1e79e]
2017-03-01 23:04:34 +03:00
Aditya Atluri 921825f7b5 changed __half enabling from 4 to >3
Change-Id: Id974c6d5326e87a4c5941f831c5bb2747cdebd2d


[ROCm/hip commit: e7ccc995ee]
2017-02-28 17:13:29 -06:00
pensun 0157d13a56 Define __HIPCC__ flag at compile time when using HIPCC on HCC path
Change-Id: I5e967e0e2327264d5d3b0ca705c2504fcd33d75e


[ROCm/hip commit: fd610e497b]
2017-02-28 16:20:48 -06:00
Evgeny Mankov c019df92e3 [HIP] Add missing Device attribute on nvcc path.
+ missing cudaDevAttrComputeCapabilityMinor case as added for hipDeviceGetAttribute query for hipDeviceAttributeComputeCapabilityMinor.


[ROCm/hip commit: f9ad2dca7e]
2017-02-28 18:40:13 +03:00
pensun 1cdf972180 update hip_porting_guide regarding platform depended macros
Change-Id: I3029c6ae6cb280500bba294925ed6e9dc9dcc94d


[ROCm/hip commit: ac4b7e3f91]
2017-02-28 07:33:01 -06:00
Maneesh Gupta cee901e66f packaging script changes for hip_hcc
Change-Id: I06cce6048204315a891e3a12638a3067644cfb43


[ROCm/hip commit: 0672b19264]
2017-02-28 12:02:53 +05:30
pensun d86f186d66 remove extra spaces for hip_common.h platform defines
Change-Id: Ie0e39256abba307429985371671cde01f5ea2cc9


[ROCm/hip commit: df9cbb6067]
2017-02-27 12:55:22 -06:00
Rahul Garg 4dc60f9990 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


[ROCm/hip commit: bddd6b73c0]
2017-02-27 15:24:17 +05:30
Maneesh Gupta 605343ecd4 Fix nvcc path samples that include math_functions.h
Change-Id: I94bb577b93983535178d8f0dcae57aaa72871534


[ROCm/hip commit: 4a6166cd86]
2017-02-27 13:20:05 +05:30
Maneesh Gupta 3a726819e8 Disable some tests which are broken on nvcc path
Change-Id: I6f8df7687ff1798dc17f6c9b8a7f4cd029ce45d8


[ROCm/hip commit: a0b51c69a7]
2017-02-27 13:19:06 +05:30
Maneesh Gupta 2799863a54 Fix compilation of some broken tests on nvcc path
Change-Id: I92406af00c2de09d728e9b7f661c1f3873470560


[ROCm/hip commit: f1c3dd0dff]
2017-02-27 13:17:51 +05:30
Maneesh Gupta dd6f21070a 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


[ROCm/hip commit: 5f689cb986]
2017-02-27 13:14:08 +05:30
Maneesh Gupta 09da9ae434 FindHIP: added new macro HIP_RESET_FLAGS
Change-Id: I0af491f6689abf1c1b5691261fe1f3e61a5d916d


[ROCm/hip commit: 470dd2fbcf]
2017-02-27 13:11:11 +05:30
Aditya Atluri c6969c157a Added initial support for hipMemcpyFromSymbol. But not working!
Change-Id: I48d8c7de4ec9f85c6c942be995fb488a3931f5d7


[ROCm/hip commit: 2e245ae58c]
2017-02-23 11:29:06 -06:00
Maneesh Gupta e5682bd659 Fix export interfaces in hip-config.cmake
Change-Id: Ifad4661ab17d7e6edb6ab300f1e92552ed917950


[ROCm/hip commit: 270054859a]
2017-02-23 11:18:06 +05:30
Aditya Atluri d24435ea9b added runtime api hipMemcpyFromSymbolAsync
Change-Id: Ibaf925faf0ba464dd0ed6c5ea74c224c2ce38889


[ROCm/hip commit: 639fd4dd5e]
2017-02-22 19:16:35 -06:00
Aditya Atluri 9e1a6a4013 Enable symbol tests
Change-Id: I6bd036bf00c8051c8ff728ee60562c4ebd222160


[ROCm/hip commit: d52c5867f2]
2017-02-22 13:42:03 -06:00
Paul b98e396fc9 Update for lower case hip
[ROCm/hip commit: 5dbf7e0618]
2017-02-22 15:18:38 +05:30
Paul 7831962f6d Change order of find_dependency
[ROCm/hip commit: 2e83e3a01d]
2017-02-22 15:18:11 +05:30
Aditya Atluri a89ef49454 added typedef for half and half2
Change-Id: Ic844fa31b64a0354484b418df71869c2807200cc


[ROCm/hip commit: a1f3955860]
2017-02-21 14:44:37 -06:00
Evgeny Mankov ed1915ad97 [HIP] annotation update.
cudaStreamAddCallback and cudaStreamWaitEvent were excluded from unsupported.


[ROCm/hip commit: 2461ddd79d]
2017-02-20 21:26:40 +03:00
Evgeny Mankov cfb607a21d [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
cudaDeviceGetPCIBusId -> hipDeviceGetPCIBusId


[ROCm/hip commit: bd9b674d3d]
2017-02-20 21:21:47 +03:00
Evgeny Mankov d52c918b47 [HIPIFY] sync with HIP by HIP_UNSUPPORTED Runtime functions.
[ROCm/hip commit: 6e611aa574]
2017-02-20 21:19:34 +03:00
Evgeny Mankov 240b46d3b0 [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).


[ROCm/hip commit: 5c11789358]
2017-02-20 18:32:54 +03:00
Evgeny Mankov 091d377ce5 [HIPIFY] Sync HIPIFY with HIP by data types.
[ROCm/hip commit: 0cbe335c8f]
2017-02-20 18:28:59 +03:00
Evgeny Mankov b01385b687 [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.


[ROCm/hip commit: ee157678b9]
2017-02-17 18:09:08 +03:00
Evgeny Mankov a1c15ab0fb [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).


[ROCm/hip commit: a35d4b75c5]
2017-02-17 18:06:47 +03:00
Aditya Atluri 6cd3764009 removed hipblas samples as it is not yet supported
Change-Id: I354b710e652ce0d0413d670530ceb8b70f4993d5


[ROCm/hip commit: 39548fb023]
2017-02-17 08:51:02 -06:00
Evgeny Mankov 3c7eb4ba4e [HIPIFY] Add more Stream and Occupancy functions.
[ROCm/hip commit: dc8e8caf41]
2017-02-17 15:04:15 +03:00
Evgeny Mankov 451704189e [HIPIFY] Add missing Memcpy functions.
+ cudaChooseDevice


[ROCm/hip commit: 3b6990c8d6]
2017-02-16 23:03:01 +03:00
Evgeny Mankov 4883e82185 [HIPIFY] Add more Memory Management functions
[ROCm/hip commit: 7b44dbbe37]
2017-02-16 21:26:44 +03:00
Evgeny Mankov e97beff540 [HIPIFY] Add Channel (Textures) support.
[ROCm/hip commit: b135b24200]
2017-02-16 21:10:10 +03:00
Evgeny Mankov 07ffedbbf3 [HIPIFY] Add Inter-Process Communications (IPC) support.
[ROCm/hip commit: ea95f3166a]
2017-02-16 20:24:53 +03:00
Evgeny Mankov 2951f80caf [HIPIFY] Add CUDA Driver LAUNCH_PARAM defines.
[ROCm/hip commit: bbbe5814c1]
2017-02-16 20:00:36 +03:00
Evgeny Mankov c98017e483 [HIPIFY] Add safe type check for cudaChooseDevice matcher.
[ROCm/hip commit: 93c1e31b36]
2017-02-16 19:38:35 +03:00
Siu Chi Chan 3cd2b00059 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)


[ROCm/hip commit: 806deeb476]
2017-02-16 13:12:32 +05:30
Evgeny Mankov 6f5ad4e7e6 [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.


[ROCm/hip commit: 950434f4af]
2017-02-15 19:48:31 +03:00
Evgeny Mankov 8a8a7bc843 [HIPIFY] Add file:line:col info to [HIPIFY] warnings/errors.
[ROCm/hip commit: e39ed24a50]
2017-02-14 21:36:49 +03:00
scchan f8ad2028a4 calls isfinite,isinf,isnan from the std namespace on the host
Change-Id: Ica2370075b89713eecfd96102e2f4e0ab9961ce4


[ROCm/hip commit: ad9d9b25c1]
2017-02-14 11:52:09 -05:00
Evgeny Mankov ffedb9388f [HIPIFY] Add more unhandled refs for opaque pointers.
CUfunc_st -> hipFunction_t *
CUctx_st -> hipCtx_t *
CUmod_st -> hipModule_t *


[ROCm/hip commit: b3941dd546]
2017-02-14 17:34:10 +03:00