| 1 | /*
|
|---|
| 2 | Copyright (c) 2017, Lawrence Livermore National Security, LLC.
|
|---|
| 3 | Produced at the Lawrence Livermore National Laboratory
|
|---|
| 4 | Written by Chunhua Liao, Pei-Hung Lin, Joshua Asplund,
|
|---|
| 5 | Markus Schordan, and Ian Karlin
|
|---|
| 6 | (email: liao6@llnl.gov, lin32@llnl.gov, asplund1@llnl.gov,
|
|---|
| 7 | schordan1@llnl.gov, karlin1@llnl.gov)
|
|---|
| 8 | LLNL-CODE-732144
|
|---|
| 9 | All rights reserved.
|
|---|
| 10 |
|
|---|
| 11 | This file is part of DataRaceBench. For details, see
|
|---|
| 12 | https://github.com/LLNL/dataracebench. Please also see the LICENSE file
|
|---|
| 13 | for our additional BSD notice.
|
|---|
| 14 |
|
|---|
| 15 | Redistribution and use in source and binary forms, with
|
|---|
| 16 | or without modification, are permitted provided that the following
|
|---|
| 17 | conditions are met:
|
|---|
| 18 |
|
|---|
| 19 | * Redistributions of source code must retain the above copyright
|
|---|
| 20 | notice, this list of conditions and the disclaimer below.
|
|---|
| 21 |
|
|---|
| 22 | * Redistributions in binary form must reproduce the above copyright
|
|---|
| 23 | notice, this list of conditions and the disclaimer (as noted below)
|
|---|
| 24 | in the documentation and/or other materials provided with the
|
|---|
| 25 | distribution.
|
|---|
| 26 |
|
|---|
| 27 | * Neither the name of the LLNS/LLNL nor the names of its contributors
|
|---|
| 28 | may be used to endorse or promote products derived from this
|
|---|
| 29 | software without specific prior written permission.
|
|---|
| 30 |
|
|---|
| 31 | THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND
|
|---|
| 32 | CONTRIBUTORS "AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES,
|
|---|
| 33 | INCLUDING, BUT NOT LIMITED TO, THE IMPLIED WARRANTIES OF
|
|---|
| 34 | MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE ARE
|
|---|
| 35 | DISCLAIMED. IN NO EVENT SHALL LAWRENCE LIVERMORE NATIONAL
|
|---|
| 36 | SECURITY, LLC, THE U.S. DEPARTMENT OF ENERGY OR CONTRIBUTORS BE
|
|---|
| 37 | LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY,
|
|---|
| 38 | OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO,
|
|---|
| 39 | PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE,
|
|---|
| 40 | DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND
|
|---|
| 41 | ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT
|
|---|
| 42 | LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING
|
|---|
| 43 | IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED OF
|
|---|
| 44 | THE POSSIBILITY OF SUCH DAMAGE.
|
|---|
| 45 | */
|
|---|
| 46 | /*
|
|---|
| 47 | This program is extracted from a real application at LLNL.
|
|---|
| 48 | Two pointers (xa1 and xa2) have a pair of values with a distance of 12.
|
|---|
| 49 | They are used as start base addresses for two 1-D arrays.
|
|---|
| 50 | Their index set has two indices with distance of 12: 999 +12 = 1011.
|
|---|
| 51 | So there is loop carried dependence.
|
|---|
| 52 |
|
|---|
| 53 | However, having loop carried dependence does not mean data races will always happen.
|
|---|
| 54 | The iterations with loop carried dependence must be scheduled to
|
|---|
| 55 | different threads in order for data races to happen.
|
|---|
| 56 |
|
|---|
| 57 | In this example, we use schedule(static,1) to increase the chance that
|
|---|
| 58 | the dependent loop iterations will be scheduled to different threads.
|
|---|
| 59 | Data race pair: xa1[idx]@128:5 vs. xa2[idx]@129:5
|
|---|
| 60 | */
|
|---|
| 61 | #include <assert.h>
|
|---|
| 62 | #include <stdio.h>
|
|---|
| 63 | #include <stdlib.h>
|
|---|
| 64 |
|
|---|
| 65 | #define N 180
|
|---|
| 66 | int indexSet[N] = {
|
|---|
| 67 | 521, 523, 525, 527, 529, 531,
|
|---|
| 68 | 547, 549, 551, 553, 555, 557,
|
|---|
| 69 | 573, 575, 577, 579, 581, 583,
|
|---|
| 70 | 599, 601, 603, 605, 607, 609,
|
|---|
| 71 | 625, 627, 629, 631, 633, 635,
|
|---|
| 72 |
|
|---|
| 73 | 651, 653, 655, 657, 659, 661,
|
|---|
| 74 | 859, 861, 863, 865, 867, 869,
|
|---|
| 75 | 885, 887, 889, 891, 893, 895,
|
|---|
| 76 | 911, 913, 915, 917, 919, 923, // change original 921 to 923 = 911+12
|
|---|
| 77 | 937, 939, 941, 943, 945, 947,
|
|---|
| 78 |
|
|---|
| 79 | 963, 965, 967, 969, 971, 973,
|
|---|
| 80 | 989, 991, 993, 995, 997, 999,
|
|---|
| 81 | 1197, 1199, 1201, 1203, 1205, 1207,
|
|---|
| 82 | 1223, 1225, 1227, 1229, 1231, 1233,
|
|---|
| 83 | 1249, 1251, 1253, 1255, 1257, 1259,
|
|---|
| 84 |
|
|---|
| 85 | 1275, 1277, 1279, 1281, 1283, 1285,
|
|---|
| 86 | 1301, 1303, 1305, 1307, 1309, 1311,
|
|---|
| 87 | 1327, 1329, 1331, 1333, 1335, 1337,
|
|---|
| 88 | 1535, 1537, 1539, 1541, 1543, 1545,
|
|---|
| 89 | 1561, 1563, 1565, 1567, 1569, 1571,
|
|---|
| 90 |
|
|---|
| 91 | 1587, 1589, 1591, 1593, 1595, 1597,
|
|---|
| 92 | 1613, 1615, 1617, 1619, 1621, 1623,
|
|---|
| 93 | 1639, 1641, 1643, 1645, 1647, 1649,
|
|---|
| 94 | 1665, 1667, 1669, 1671, 1673, 1675,
|
|---|
| 95 | 1873, 1875, 1877, 1879, 1881, 1883,
|
|---|
| 96 |
|
|---|
| 97 | 1899, 1901, 1903, 1905, 1907, 1909,
|
|---|
| 98 | 1925, 1927, 1929, 1931, 1933, 1935,
|
|---|
| 99 | 1951, 1953, 1955, 1957, 1959, 1961,
|
|---|
| 100 | 1977, 1979, 1981, 1983, 1985, 1987,
|
|---|
| 101 | 2003, 2005, 2007, 2009, 2011, 2013};
|
|---|
| 102 |
|
|---|
| 103 | int main (int argc, char* argv[])
|
|---|
| 104 | {
|
|---|
| 105 | // max index value is 2013. +12 to obtain a valid xa2[idx] after xa1+12.
|
|---|
| 106 | // +1 to ensure a reference like base[2015] is within the bound.
|
|---|
| 107 | double * base = (double*) malloc(sizeof(double)* (2013+12+1));
|
|---|
| 108 | if (base == 0)
|
|---|
| 109 | {
|
|---|
| 110 | printf ("Error in malloc(). Aborting ...\n");
|
|---|
| 111 | return 1;
|
|---|
| 112 | }
|
|---|
| 113 |
|
|---|
| 114 | double * xa1 = base;
|
|---|
| 115 | double * xa2 = xa1 + 12;
|
|---|
| 116 | int i;
|
|---|
| 117 |
|
|---|
| 118 | // initialize segments touched by indexSet
|
|---|
| 119 | for (i =521; i<= 2025; ++i)
|
|---|
| 120 | {
|
|---|
| 121 | base[i]=0.5*i;
|
|---|
| 122 | }
|
|---|
| 123 | // default static even scheduling may not trigger data race, using static,1 instead.
|
|---|
| 124 | #pragma omp parallel for schedule(static,1)
|
|---|
| 125 | for (i =0; i< N; ++i)
|
|---|
| 126 | {
|
|---|
| 127 | xa1[i] += 1.0 + i;
|
|---|
| 128 | xa2[i - 12] += 3.0 + i;
|
|---|
| 129 | }
|
|---|
| 130 |
|
|---|
| 131 | printf("x1[999]=%f xa2[1285]=%f\n", xa1[999], xa2[1285]);
|
|---|
| 132 | free (base);
|
|---|
| 133 | return 0;
|
|---|
| 134 | }
|
|---|
| 135 |
|
|---|