diff options
Diffstat (limited to 'gcc')
-rw-r--r-- | gcc/omp-low.c | 1 | ||||
-rw-r--r-- | gcc/testsuite/gcc.dg/asan/pr97294.c | 41 | ||||
-rw-r--r-- | gcc/tree-cfg.c | 2 |
3 files changed, 44 insertions, 0 deletions
diff --git a/gcc/omp-low.c b/gcc/omp-low.c index b054961..b3e2468 100644 --- a/gcc/omp-low.c +++ b/gcc/omp-low.c @@ -5112,6 +5112,7 @@ lower_rec_input_clauses (tree clauses, gimple_seq *ilist, gimple_seq *dlist, atmp = builtin_decl_explicit (BUILT_IN_ALLOCA_WITH_ALIGN); stmt = gimple_build_call (atmp, 2, x, size_int (DECL_ALIGN (var))); + cfun->calls_alloca = 1; tmp = create_tmp_var_raw (ptr_type_node); gimple_add_tmp_var (tmp); gimple_call_set_lhs (stmt, tmp); diff --git a/gcc/testsuite/gcc.dg/asan/pr97294.c b/gcc/testsuite/gcc.dg/asan/pr97294.c new file mode 100644 index 0000000..6de6c3e --- /dev/null +++ b/gcc/testsuite/gcc.dg/asan/pr97294.c @@ -0,0 +1,41 @@ +/* PR sanitizer/97294 */ +/* { dg-do compile { target fopenmp } } */ +/* { dg-skip-if "" { *-*-* } { "*" } { "-O0" } } */ +/* { dg-options "-O0 -fsanitize=address -fopenmp" } */ +/* { dg-final { scan-assembler "foo._omp_fn.\[0-9]\[1-9]*:.*call\[ \t]\*__*asan_allocas_unpoison.*\.size\[ \t]\*foo._omp_fn.\[0-9]\[1-9]*," { target x86_64-*-linux* i?86-*-linux* } } } */ + +__attribute__((noipa)) void +foo (int *p, int n) +{ + int i; + #pragma omp parallel for num_threads(2) reduction(+:p[:n]) + for (i = 0; i < 10; i++) + { + p[0]++; + p[n - 1] += 2; + } +} + +__attribute__((noipa)) void +bar (void) +{ + unsigned char buf[1024]; + int i; + asm volatile ("" : : "r" (&buf[0]) : "memory"); + for (i = 0; i < 1024; i++) + buf[i] = i; + asm volatile ("" : : "r" (&buf[0]) : "memory"); +} + +int +main () +{ + int p[50], i; + for (i = 0; i < 50; i++) + p[i] = 0; + foo (p, 50); + bar (); + if (p[0] != 10 || p[49] != 20) + __builtin_abort (); + return 0; +} diff --git a/gcc/tree-cfg.c b/gcc/tree-cfg.c index 4064417..5caf3b6 100644 --- a/gcc/tree-cfg.c +++ b/gcc/tree-cfg.c @@ -7220,6 +7220,8 @@ move_block_to_fn (struct function *dest_cfun, basic_block bb, free_stmt_operands (cfun, stmt); push_cfun (dest_cfun); update_stmt (stmt); + if (is_gimple_call (stmt)) + notice_special_calls (as_a <gcall *> (stmt)); pop_cfun (); } |