76333 Коммитов

Автор SHA1 Сообщение Дата
Oak Zeng c3dcb0a7bb Revert "Revert "More cleanup of fmm.c""
This reverts commit 5b0ba9550c.

Change-Id: I31afe4889794df8cf1e96f5f18771bed75a213d9
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>


[ROCm/ROCR-Runtime commit: c2dc301792]
2017-12-04 15:48:11 -05:00
Oak Zeng 786e470241 Revert "Revert "Cleanup fmm.c""
This reverts commit f7689d4fef,
Plus a bug fix to patch "Cleanup fmm.c":
Call id_in_array with correct parameter. The third parameter
of id_in_array is size in byte of the array, not the number
of array items. Call it correctly.

Change-Id: I72d8e2fcc0df32af76c72967386e92c1be18c159
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>
2017-12-04 15:48:11 -05:00
Oak Zeng 6c763e99fe Revert "Revert "Cleanup fmm.c""
This reverts commit dbd9a8736c,
Plus a bug fix to patch "Cleanup fmm.c":
Call id_in_array with correct parameter. The third parameter
of id_in_array is size in byte of the array, not the number
of array items. Call it correctly.

Change-Id: I72d8e2fcc0df32af76c72967386e92c1be18c159
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>


[ROCm/ROCR-Runtime commit: 786e470241]
2017-12-04 15:48:11 -05:00
Felix Kuehling 587d4f4bdf Rename fmm_allocate_memory_in_device
to fmm_allocate_memory_object. This function name was confusingly
similar to fmm_allocate_device and __fmm_allocate_device. The new name
reflects its function better: allocate the VM object and the kernel
mode buffer object.

Change-Id: I6604d228004b4d41e871d4de784786823608b5d6
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
2017-12-04 10:23:55 -05:00
Felix Kuehling cfd86f5b7e Rename fmm_allocate_memory_in_device
to fmm_allocate_memory_object. This function name was confusingly
similar to fmm_allocate_device and __fmm_allocate_device. The new name
reflects its function better: allocate the VM object and the kernel
mode buffer object.

Change-Id: I6604d228004b4d41e871d4de784786823608b5d6
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>


[ROCm/ROCR-Runtime commit: 587d4f4bdf]
2017-12-04 10:23:55 -05:00
Jenkins 7ca3b9472f Merge 'master' into 'amd-master'
Change-Id: I1558ce7892abab30345a426d60976af9e852351d


[ROCm/clr commit: 46a5ce4e1e]
2017-12-04 04:48:51 -06:00
Jenkins 46a5ce4e1e Merge 'master' into 'amd-master'
Change-Id: I1558ce7892abab30345a426d60976af9e852351d
2017-12-04 04:48:51 -06:00
Jenkins e547608c5e Merge 'master' into 'amd-master'
Change-Id: I1558ce7892abab30345a426d60976af9e852351d


[ROCm/hip commit: 45f7febc21]
2017-12-04 04:48:51 -06:00
Jenkins 45f7febc21 Merge 'master' into 'amd-master'
Change-Id: I1558ce7892abab30345a426d60976af9e852351d
2017-12-04 04:48:51 -06:00
Ben Sander 88d6676359 Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Clean up kernel retrieval code / module management

[ROCm/clr commit: c7f9dbf789]
2017-12-03 18:41:27 -06:00
Ben Sander c7f9dbf789 Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Clean up kernel retrieval code / module management
2017-12-03 18:41:27 -06:00
Ben Sander ee0114f1f3 Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Clean up kernel retrieval code / module management

[ROCm/hip commit: d62074e3fc]
2017-12-03 18:41:27 -06:00
Ben Sander d62074e3fc Merge pull request #279 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Clean up kernel retrieval code / module management
2017-12-03 18:41:27 -06:00
Ben Sander eae70713b5 Merge pull request #276 from bensander/temp_disable_tests
Temporarily disable a couple tests pending some HCC work

[ROCm/clr commit: 4dfcd401b0]
2017-12-03 18:33:47 -06:00
Ben Sander 4dfcd401b0 Merge pull request #276 from bensander/temp_disable_tests
Temporarily disable a couple tests pending some HCC work
2017-12-03 18:33:47 -06:00
Ben Sander ff543f328b Merge pull request #276 from bensander/temp_disable_tests
Temporarily disable a couple tests pending some HCC work

[ROCm/hip commit: 2ae6882d4f]
2017-12-03 18:33:47 -06:00
Ben Sander 2ae6882d4f Merge pull request #276 from bensander/temp_disable_tests
Temporarily disable a couple tests pending some HCC work
2017-12-03 18:33:47 -06:00
Alex Voicu 8294d086a8 Re-sync with upstream.
[ROCm/clr commit: 76614f15af]
2017-12-03 23:14:58 +00:00
Alex Voicu 76614f15af Re-sync with upstream. 2017-12-03 23:14:58 +00:00
Alex Voicu 6e56aa7188 Re-sync with upstream.
[ROCm/hip commit: 5ca3176a91]
2017-12-03 23:14:58 +00:00
Alex Voicu 5ca3176a91 Re-sync with upstream. 2017-12-03 23:14:58 +00:00
Alex Voicu 37e40fcd40 This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
[ROCm/clr commit: e186bd9533]
2017-12-03 23:09:06 +00:00
Alex Voicu e186bd9533 This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail. 2017-12-03 23:09:06 +00:00
Alex Voicu abe3c22cf1 This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail.
[ROCm/hip commit: 5127ce67e8]
2017-12-03 23:09:06 +00:00
Alex Voicu 5127ce67e8 This is primarily intended as an additional cleanup of the module functionality, in the aftermath of adopting module based dispatch. The main effort was associated with refactoring the questionable ihipModuleGetSymbol. It was quaintly written and misleading, in that it had little to do with getting symbols, and was exactly retrieving a kernel object. Error handling is modified so as to reduce branching depth. Functions which serve as interfaces to the HSA RT are moved in a separate helper header. Code object readers are properly deleted. Some leftover dead functionality pertaining to associating namespace scope variables with their allocated memory is removed. Executable loading is changed to use a string which holds the ELF image of the code object being loaded, thus avoiding some corner cases where using a istream would fail. 2017-12-03 23:09:06 +00:00
Ben Sander 5b5bbd0b99 Merge pull request #271 from bensander/cppcheck
Cppcheck

[ROCm/clr commit: 6e2e029b39]
2017-12-02 08:36:17 -06:00
Ben Sander 6e2e029b39 Merge pull request #271 from bensander/cppcheck
Cppcheck
2017-12-02 08:36:17 -06:00
Ben Sander 1706feba74 Merge pull request #271 from bensander/cppcheck
Cppcheck

[ROCm/hip commit: 6f3ed5e3cf]
2017-12-02 08:36:17 -06:00
Ben Sander 6f3ed5e3cf Merge pull request #271 from bensander/cppcheck
Cppcheck
2017-12-02 08:36:17 -06:00
Ben Sander 345f23e6c1 Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
Since these are now supported directly.


[ROCm/clr commit: a431bf6ba2]
2017-12-02 07:44:54 -06:00
Ben Sander a431bf6ba2 Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
Since these are now supported directly.
2017-12-02 07:44:54 -06:00
Ben Sander ca1a6b3895 Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
Since these are now supported directly.


[ROCm/hip commit: 657e65733f]
2017-12-02 07:44:54 -06:00
Ben Sander 657e65733f Remove coordinate conversions (threadIdx.x -> hipThreadIdx_x)
Since these are now supported directly.
2017-12-02 07:44:54 -06:00
Ben Sander 7d24011bdd Update square sample for recent HIP ease-of-use improvements
[ROCm/hip-tests commit: 421a50e830]
2017-12-02 07:44:27 -06:00
Ben Sander 421a50e830 Update square sample for recent HIP ease-of-use improvements 2017-12-02 07:44:27 -06:00
Ben Sander 113335f857 Update square sample for recent HIP ease-of-use improvements
[ROCm/clr commit: 4192c8b54a]
2017-12-02 07:44:27 -06:00
Ben Sander 4192c8b54a Update square sample for recent HIP ease-of-use improvements 2017-12-02 07:44:27 -06:00
Ben Sander 2bd4446721 Update square sample for recent HIP ease-of-use improvements
[ROCm/hip commit: b9fa704521]
2017-12-02 07:44:27 -06:00
Ben Sander b9fa704521 Update square sample for recent HIP ease-of-use improvements 2017-12-02 07:44:27 -06:00
Ben Sander 032ef0370a Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Fix hang by purging archaisms

[ROCm/clr commit: a833ec9f7f]
2017-12-02 07:11:55 -06:00
Ben Sander a833ec9f7f Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Fix hang by purging archaisms
2017-12-02 07:11:55 -06:00
Ben Sander 444c0afc2c Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Fix hang by purging archaisms

[ROCm/hip commit: 5a642c1717]
2017-12-02 07:11:55 -06:00
Ben Sander 5a642c1717 Merge pull request #277 from AlexVlx/feature_use_module_based_dispatch_instead_of_pfe
Fix hang by purging archaisms
2017-12-02 07:11:55 -06:00
foreman 369519a005 P4 to Git Change 1489603 by johtaylo@johtaylo-jtincrementor2-increment on 2017/12/02 03:00:04
SWDEV-2 - Change OpenCL version number from 2548 to 2549.

Affected files ...

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


[ROCm/clr commit: 7ad48b4fb4]
2017-12-02 03:13:55 -05:00
foreman 7ad48b4fb4 P4 to Git Change 1489603 by johtaylo@johtaylo-jtincrementor2-increment on 2017/12/02 03:00:04
SWDEV-2 - Change OpenCL version number from 2548 to 2549.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2296 edit
2017-12-02 03:13:55 -05:00
Alex Voicu 1ba0d0ca14 Remove stray leftover comment.
[ROCm/clr commit: 954b7dadf7]
2017-12-02 00:03:10 +00:00
Alex Voicu 954b7dadf7 Remove stray leftover comment. 2017-12-02 00:03:10 +00:00
Alex Voicu 8eff1b3af4 Remove stray leftover comment.
[ROCm/hip commit: 02fc25de4c]
2017-12-02 00:03:10 +00:00
Alex Voicu 02fc25de4c Remove stray leftover comment. 2017-12-02 00:03:10 +00:00
Alex Voicu 6bdde982ff Replace archaic use of homebrew functionality with calls to the HC maths library. This fixes a hang observed when building hipTestDeviceDouble.
[ROCm/clr commit: b8c80bd0b2]
2017-12-02 00:01:47 +00:00