Compare commits

...
3 Commits
Author SHA1 Message Date
Jonathan Peyton e62ab1ab82 Merging r292349:
------------------------------------------------------------------------
r292349 | jlpeyton | 2017-01-18 01:02:21 -0600 (Wed, 18 Jan 2017) | 6 lines

Fix memory error in case of reinit using kmp_set_defaults() for lock code.

The lock tables were being reallocated if kmp_set_defaults() was called.
In the env_init code it says that the user should be able to switch between
different KMP_CONSISTENCY_CHECK values which is what this change enables.

------------------------------------------------------------------------


git-svn-id: https://llvm.org/svn/llvm-project/openmp/branches/release_40@292678 91177308-0d34-0410-b5e6-96231b3b80d8
2017-01-20 23:32:49 +00:00
Jonathan Peyton 57d5483742 Merging r292348:
------------------------------------------------------------------------
r292348 | jlpeyton | 2017-01-18 00:40:19 -0600 (Wed, 18 Jan 2017) | 5 lines

Fix small memory leak regarding __kmp_nested_proc_bind

There is no corresponding free() for this expandable array.  The logic is
added in __kmp_cleanup() next to the freeing of __kmp_nested_nth.

------------------------------------------------------------------------


git-svn-id: https://llvm.org/svn/llvm-project/openmp/branches/release_40@292677 91177308-0d34-0410-b5e6-96231b3b80d8
2017-01-20 23:31:21 +00:00
Hans Wennborg fc80b280f9 Creating release_40 branch off revision 291814
git-svn-id: https://llvm.org/svn/llvm-project/openmp/branches/release_40@291826 91177308-0d34-0410-b5e6-96231b3b80d8
2017-01-12 21:26:15 +00:00
3 changed files with 63 additions and 0 deletions
+6
View File
@@ -3573,6 +3573,12 @@ __kmp_init_dynamic_user_locks()
__kmp_indirect_unset = indirect_unset;
__kmp_indirect_test = indirect_test;
}
// If the user locks have already been initialized, then return.
// Allow the switch between different KMP_CONSISTENCY_CHECK values,
// but do not allocate new lock tables if they have already been
// allocated.
if (__kmp_init_user_locks)
return;
// Initialize lock index table
__kmp_i_lock_table.size = KMP_I_LOCK_CHUNK;
+4
View File
@@ -7293,6 +7293,10 @@ __kmp_cleanup( void )
__kmp_nested_nth.nth = NULL;
__kmp_nested_nth.size = 0;
__kmp_nested_nth.used = 0;
KMP_INTERNAL_FREE( __kmp_nested_proc_bind.bind_types );
__kmp_nested_proc_bind.bind_types = NULL;
__kmp_nested_proc_bind.size = 0;
__kmp_nested_proc_bind.used = 0;
__kmp_i18n_catclose();
@@ -0,0 +1,53 @@
// RUN: %libomp-compile-and-run
#include <stdio.h>
#include "omp_testsuite.h"
/* The bug occurs if the lock table is reallocated after
kmp_set_defaults() is called. If the table is reallocated,
then the lock will not point to a valid lock object after the
kmp_set_defaults() call.*/
omp_lock_t lock;
int test_kmp_set_defaults_lock_bug()
{
/* checks that omp_get_num_threads is equal to the number of
threads */
int nthreads_lib;
int nthreads = 0;
nthreads_lib = -1;
#pragma omp parallel
{
omp_set_lock(&lock);
nthreads++;
omp_unset_lock(&lock);
#pragma omp single
{
nthreads_lib = omp_get_num_threads ();
} /* end of single */
} /* end of parallel */
kmp_set_defaults("OMP_NUM_THREADS");
#pragma omp parallel
{
omp_set_lock(&lock);
nthreads++;
omp_unset_lock(&lock);
} /* end of parallel */
return (nthreads == 2*nthreads_lib);
}
int main()
{
int i;
int num_failed=0;
omp_init_lock(&lock);
for(i = 0; i < REPETITIONS; i++) {
if(!test_kmp_set_defaults_lock_bug()) {
num_failed++;
}
}
omp_destroy_lock(&lock);
return num_failed;
}