123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159160161162163164165166167168169170171172173174175176177178179180181182183184185186187188189190191192193194195196197198199200201202203204205206207208209210211212213 |
- /* This testcase is part of GDB, the GNU debugger.
- Copyright 2017-2022 Free Software Foundation, Inc.
- This program is free software; you can redistribute it and/or modify
- it under the terms of the GNU General Public License as published by
- the Free Software Foundation; either version 3 of the License, or
- (at your option) any later version.
- This program is distributed in the hope that it will be useful,
- but WITHOUT ANY WARRANTY; without even the implied warranty of
- MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
- GNU General Public License for more details.
- You should have received a copy of the GNU General Public License
- along with this program. If not, see <http://www.gnu.org/licenses/>. */
- #include <stdio.h>
- #include <omp.h>
- omp_lock_t lock;
- omp_lock_t lock2;
- /* Enforce execution order between two threads using a lock. */
- static void
- omp_set_lock_in_order (int num, omp_lock_t *lock)
- {
- /* Ensure that thread num 0 first sets the lock. */
- if (num == 0)
- omp_set_lock (lock);
- #pragma omp barrier
- /* Block thread num 1 until it can set the lock. */
- if (num == 1)
- omp_set_lock (lock);
- /* This bit here is guaranteed to be executed first by thread num 0, and
- once thread num 0 unsets the lock, to be executed by thread num 1. */
- ;
- }
- /* Testcase for checking access to variables in a single / outer scope.
- Make sure that variables not referred to in the parallel section are
- accessible from the debugger. */
- void
- single_scope (void)
- {
- static int s1 = -41, s2 = -42, s3 = -43;
- int i1 = 11, i2 = 12, i3 = 13;
- #pragma omp parallel num_threads (2) shared (s1, i1) private (s2, i2)
- {
- int thread_num = omp_get_thread_num ();
- omp_set_lock_in_order (thread_num, &lock);
- s2 = 100 * (thread_num + 1) + 2;
- i2 = s2 + 10;
- #pragma omp critical
- printf ("single_scope: thread_num=%d, s1=%d, i1=%d, s2=%d, i2=%d\n",
- thread_num, s1, i1, s2, i2);
- omp_unset_lock (&lock);
- }
- printf ("single_scope: s1=%d, s2=%d, s3=%d, i1=%d, i2=%d, i3=%d\n",
- s1, s2, s3, i1, i2, i3);
- }
- static int file_scope_var = 9876;
- /* Testcase for checking access to variables from parallel region
- nested within more than one lexical scope. Of particular interest
- are variables which are not referenced in the parallel section. */
- void
- multi_scope (void)
- {
- int i01 = 1, i02 = 2;
- {
- int i11 = 11, i12 = 12;
- {
- int i21 = -21, i22 = 22;
- #pragma omp parallel num_threads (2) \
- firstprivate (i01) \
- shared (i11) \
- private (i21)
- {
- int thread_num = omp_get_thread_num ();
- omp_set_lock_in_order (thread_num, &lock);
- i21 = 100 * (thread_num + 1) + 21;
- #pragma omp critical
- printf ("multi_scope: thread_num=%d, i01=%d, i11=%d, i21=%d\n",
- thread_num, i01, i11, i21);
- omp_unset_lock (&lock);
- }
- printf ("multi_scope: i01=%d, i02=%d, i11=%d, "
- "i12=%d, i21=%d, i22=%d\n",
- i01, i02, i11, i12, i21, i22);
- }
- }
- }
- /* Nested functions in C is a GNU extension. Some non-GNU compilers
- define __GNUC__, but they don't support nested functions. So,
- unfortunately, we can't use that for our test. */
- #if HAVE_NESTED_FUNCTION_SUPPORT
- /* Testcase for checking access of variables from within parallel
- region in a lexically nested function. */
- void
- nested_func (void)
- {
- static int s1 = -42;
- int i = 1, j = 2, k = 3;
- void
- foo (int p, int q, int r)
- {
- int x = 4;
- {
- int y = 5, z = 6;
- #pragma omp parallel num_threads (2) shared (i, p, x) private (j, q, y)
- {
- int tn = omp_get_thread_num ();
- omp_set_lock_in_order (tn, &lock);
- j = 1000 * (tn + 1);
- q = j + 1;
- y = q + 1;
- #pragma omp critical
- printf ("nested_func: tn=%d: i=%d, p=%d, x=%d, j=%d, q=%d, y=%d\n",
- tn, i, p, x, j, q, y);
- omp_unset_lock (&lock);
- }
- }
- }
- foo (10, 11, 12);
- i = 101; j = 102; k = 103;
- foo (20, 21, 22);
- }
- #endif
- /* Testcase for checking access to variables from within a nested parallel
- region. */
- void
- nested_parallel (void)
- {
- int i = 1, j = 2;
- int l = -1;
- omp_set_nested (1);
- omp_set_dynamic (0);
- #pragma omp parallel num_threads (2) private (l)
- {
- int num = omp_get_thread_num ();
- omp_set_lock_in_order (num, &lock);
- int nthr = omp_get_num_threads ();
- int off = num * nthr;
- int k = off + 101;
- l = off + 102;
- #pragma omp parallel num_threads (2) shared (num)
- {
- int inner_num = omp_get_thread_num ();
- omp_set_lock_in_order (inner_num, &lock2);
- #pragma omp critical
- printf ("nested_parallel (inner threads): outer thread num = %d, thread num = %d\n", num, inner_num);
- omp_unset_lock (&lock2);
- }
- #pragma omp critical
- printf ("nested_parallel (outer threads) %d: k = %d, l = %d\n", num, k, l);
- omp_unset_lock (&lock);
- }
- }
- int
- main (int argc, char **argv)
- {
- omp_init_lock (&lock);
- omp_init_lock (&lock2);
- single_scope ();
- multi_scope ();
- #if HAVE_NESTED_FUNCTION_SUPPORT
- nested_func ();
- #endif
- nested_parallel ();
- omp_destroy_lock (&lock);
- omp_destroy_lock (&lock2);
- return 0;
- }
|