From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mail-wm1-x330.google.com (mail-wm1-x330.google.com [IPv6:2a00:1450:4864:20::330]) by sourceware.org (Postfix) with ESMTPS id 8941F3858C50 for ; Sun, 23 Apr 2023 01:53:49 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 8941F3858C50 Authentication-Results: sourceware.org; dmarc=pass (p=none dis=none) header.from=linaro.org Authentication-Results: sourceware.org; spf=pass smtp.mailfrom=linaro.org Received: by mail-wm1-x330.google.com with SMTP id 5b1f17b1804b1-3f1e2555b5aso805855e9.0 for ; Sat, 22 Apr 2023 18:53:49 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=linaro.org; s=google; t=1682214827; x=1684806827; h=to:subject:message-id:date:from:in-reply-to:references:mime-version :from:to:cc:subject:date:message-id:reply-to; bh=n/+jaQEP7E/qEOpbb4BbG8T5s70yDF7MujCdq/BjthQ=; b=RnPZaaLW2MC8Og5kRKSLWAJVWNFo0V96jsMKD/YG1XjWs7ITnijmYuX243XuA3+J15 Bu6XzyFIOpSpG92tuewqiwGCo4nu+PgBdN9JlLYM9J2lqypp9jo85crnz5S49ICM/9+D M0NlZr7kztHxhQNOjp6qs9yGZAgqU0bJkR6Gopdv/wSE+W7FJakNmLvrFlHaqn5pkvBt xar/7JLQn1nY8GnN8lwRCgGN6+A6HGxaII4qJ0qjZBWmh4eOWgwh26gxwOSkCtvQvrba 8cU8jAWz6VXfLuFobKNIjnTFhkzYj+VcEdn4rDxfa/R29cByPZarV+OeXIH5vnZqKfym m/kg== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20221208; t=1682214827; x=1684806827; h=to:subject:message-id:date:from:in-reply-to:references:mime-version :x-gm-message-state:from:to:cc:subject:date:message-id:reply-to; bh=n/+jaQEP7E/qEOpbb4BbG8T5s70yDF7MujCdq/BjthQ=; b=ktazeQYUyl4GHWc+SucgfB3lYAbovqDkUKft7x1BysT2yhR7ROZvfDD4uCa5Rtzow3 LWzIC99TcKJKf3QbI1Ji2g7OtAUStvLemeckTWp9G727xhQ8AprPSe6mDFO1X0mFdH/5 KE/Xa5X7FnNHhduBGd6coFiMU1wD45GILvtEcdzX3LLx1Sbfc9I9dMWr5v8vZDpFwtWt ieyVZr1mou1L8lZI5mLWwLnhgOQb3HpVTj9/00hEym86iD31cxEjixRPBIjrkQXyMXV8 9QSaPPxS5vo8wS6Wg2bykdo/87b1/spgERNj8+BS8t4ybwK1/kv9iDJtnYQW7aR+NB/L QRzw== X-Gm-Message-State: AAQBX9c8GKjH9PvAuXV2PAtbk+VtWyyLMiVQaFrZpEq3T/EGL3kkmv0q jfJO78SJ8ZKnyTIEA+TZNNFxxGMarAbCsjNuJxL6aw== X-Google-Smtp-Source: AKy350Znr2fDBaiw6cS0CWkAe0jWprkhtqKxs1q2KvH3eE+/Rw+qNcQGDDZiQcH+l7D5f5glnKvBvxI1XQlKyx7rBks= X-Received: by 2002:adf:f30a:0:b0:2f1:78ca:cdea with SMTP id i10-20020adff30a000000b002f178cacdeamr6861247wro.52.1682214827378; Sat, 22 Apr 2023 18:53:47 -0700 (PDT) MIME-Version: 1.0 References: In-Reply-To: From: Prathamesh Kulkarni Date: Sun, 23 Apr 2023 07:23:11 +0530 Message-ID: Subject: Re: [aarch64] Use dup and zip1 for interleaving elements in initializing vector To: Prathamesh Kulkarni , Richard Biener , gcc Patches , richard.sandiford@arm.com Content-Type: multipart/mixed; boundary="00000000000038f67005f9f72935" X-Spam-Status: No, score=-9.5 required=5.0 tests=BAYES_00,DKIM_SIGNED,DKIM_VALID,DKIM_VALID_AU,DKIM_VALID_EF,GIT_PATCH_0,KAM_SHORT,RCVD_IN_DNSWL_NONE,SPF_HELO_NONE,SPF_PASS,TXREP,T_SCC_BODY_TEXT_LINE autolearn=ham autolearn_force=no version=3.4.6 X-Spam-Checker-Version: SpamAssassin 3.4.6 (2021-04-09) on server2.sourceware.org List-Id: --00000000000038f67005f9f72935 Content-Type: text/plain; charset="UTF-8" On Fri, 21 Apr 2023 at 20:45, Prathamesh Kulkarni wrote: > > On Fri, 21 Apr 2023 at 14:47, Richard Sandiford > wrote: > > > > Prathamesh Kulkarni writes: > > > Hi, > > > I tested the interleave+zip1 for vector init patch and it segfaulted > > > during bootstrap while trying to build > > > libgfortran/generated/matmul_i2.c. > > > Rebuilding with --enable-checking=rtl showed out of bounds access in > > > aarch64_unzip_vector_init in following hunk: > > > > > > + rtvec vec = rtvec_alloc (n / 2); > > > + for (int i = 0; i < n; i++) > > > + RTVEC_ELT (vec, i) = (even_p) ? XVECEXP (vals, 0, 2 * i) > > > + : XVECEXP (vals, 0, 2 * i + 1); > > > > > > which is incorrect since it allocates n/2 but iterates and stores upto n. > > > The attached patch fixes the issue, which passed bootstrap, however > > > resulted in following fallout during testsuite run: > > > > > > 1] sve/acle/general/dupq_[1-4].c tests fail. > > > For the following test: > > > int32x4_t f(int32_t x) > > > { > > > return (int32x4_t) { x, 1, 2, 3 }; > > > } > > > > > > Code-gen without patch: > > > f: > > > adrp x1, .LC0 > > > ldr q0, [x1, #:lo12:.LC0] > > > ins v0.s[0], w0 > > > ret > > > > > > Code-gen with patch: > > > f: > > > movi v0.2s, 0x2 > > > adrp x1, .LC0 > > > ldr d1, [x1, #:lo12:.LC0] > > > ins v0.s[0], w0 > > > zip1 v0.4s, v0.4s, v1.4s > > > ret > > > > > > It shows, fallback_seq_cost = 20, seq_total_cost = 16 > > > where seq_total_cost determines the cost for interleave+zip1 sequence > > > and fallback_seq_cost is the cost for fallback sequence. > > > Altho it shows lesser cost, I am not sure if the interleave+zip1 > > > sequence is better in this case ? > > > > Debugging the patch, it looks like this is because the fallback sequence > > contains a redundant pseudo-to-pseudo move, which is costed as 1 > > instruction (4 units). The RTL equivalent of the: > > > > movi v0.2s, 0x2 > > ins v0.s[0], w0 > > > > has a similar redundant move, but the cost of that move is subsumed by > > the cost of the other arm (the load from LC0), which is costed as 3 > > instructions (12 units). So we have 12 + 4 for the parallel version > > (correct) but 12 + 4 + 4 for the serial version (one instruction too > > many). > > > > The reason we have redundant moves is that the expansion code uses > > copy_to_mode_reg to force a value into a register. This creates a > > new pseudo even if the original value was already a register. > > Using force_reg removes the moves and makes the test pass. > > > > So I think the first step is to use force_reg instead of > > copy_to_mode_reg in aarch64_simd_dup_constant and > > aarch64_expand_vector_init (as a preparatory patch). > Thanks for the clarification! > > > > > 2] sve/acle/general/dupq_[5-6].c tests fail: > > > int32x4_t f(int32_t x0, int32_t x1, int32_t x2, int32_t x3) > > > { > > > return (int32x4_t) { x0, x1, x2, x3 }; > > > } > > > > > > code-gen without patch: > > > f: > > > fmov s0, w0 > > > ins v0.s[1], w1 > > > ins v0.s[2], w2 > > > ins v0.s[3], w3 > > > ret > > > > > > code-gen with patch: > > > f: > > > fmov s0, w0 > > > fmov s1, w1 > > > ins v0.s[1], w2 > > > ins v1.s[1], w3 > > > zip1 v0.4s, v0.4s, v1.4s > > > ret > > > > > > It shows fallback_seq_cost = 28, seq_total_cost = 16 > > > > The zip verson still wins after the fix above, but by a lesser amount. > > It seems like a borderline case. > > > > > > > > 3] aarch64/ldp_stp_16.c's cons2_8_float test fails. > > > Test case: > > > void cons2_8_float(float *x, float val0, float val1) > > > { > > > #pragma GCC unroll(8) > > > for (int i = 0; i < 8 * 2; i += 2) { > > > x[i + 0] = val0; > > > x[i + 1] = val1; > > > } > > > } > > > > > > which is lowered to: > > > void cons2_8_float (float * x, float val0, float val1) > > > { > > > vector(4) float _86; > > > > > > [local count: 119292720]: > > > _86 = {val0_11(D), val1_13(D), val0_11(D), val1_13(D)}; > > > MEM [(float *)x_10(D)] = _86; > > > MEM [(float *)x_10(D) + 16B] = _86; > > > MEM [(float *)x_10(D) + 32B] = _86; > > > MEM [(float *)x_10(D) + 48B] = _86; > > > return; > > > } > > > > > > code-gen without patch: > > > cons2_8_float: > > > dup v0.4s, v0.s[0] > > > ins v0.s[1], v1.s[0] > > > ins v0.s[3], v1.s[0] > > > stp q0, q0, [x0] > > > stp q0, q0, [x0, 32] > > > ret > > > > > > code-gen with patch: > > > cons2_8_float: > > > dup v1.2s, v1.s[0] > > > dup v0.2s, v0.s[0] > > > zip1 v0.4s, v0.4s, v1.4s > > > stp q0, q0, [x0] > > > stp q0, q0, [x0, 32] > > > ret > > > > > > It shows fallback_seq_cost = 28, seq_total_cost = 16 > > > > > > I think the test fails because it doesn't match: > > > ** dup v([0-9]+)\.4s, .* > > > > > > Shall it be OK to amend the test assuming code-gen with patch is better ? > > > > Yeah, the new code seems like an improvement. > > > > > 4] aarch64/pr109072_1.c s32x4_3 test fails: > > > For the following test: > > > int32x4_t s32x4_3 (int32_t x, int32_t y) > > > { > > > int32_t arr[] = { x, y, y, y }; > > > return vld1q_s32 (arr); > > > } > > > > > > code-gen without patch: > > > s32x4_3: > > > dup v0.4s, w1 > > > ins v0.s[0], w0 > > > ret > > > > > > code-gen with patch: > > > s32x4_3: > > > fmov s1, w1 > > > fmov s0, w0 > > > ins v0.s[1], v1.s[0] > > > dup v1.2s, v1.s[0] > > > zip1 v0.4s, v0.4s, v1.4s > > > ret > > > > > > It shows fallback_seq_cost = 20, seq_total_cost = 16 > > > I am not sure how interleave+zip1 cost is lesser than fallback seq > > > cost for this case. > > > I assume that the fallback sequence is better here ? > > > > The fix for 1] works for this case too. > Indeed, I verified using force_reg fixes the issues. > I will send a follow up patch after the preparatory patch using force_reg. The attached patch adjusts ldp_stp_16.c, and dupq_[5-6.c] to scan for new code-gen. It passes bootstrap with no regressions reported for testsuite results. For the adjusted tests, it reports "old tests that pass have disappeared", which I assume is OK since they now scan for new code-gen ? Does the patch look OK to commit ? Thanks, Prathamesh > > Thanks, > Prathamesh > > > > Thanks, > > Richard --00000000000038f67005f9f72935 Content-Type: text/plain; charset="US-ASCII"; name="gnu-821-8.txt" Content-Disposition: attachment; filename="gnu-821-8.txt" Content-Transfer-Encoding: base64 Content-ID: X-Attachment-Id: f_lgsr5e7p0 W2FhcmNoNjRdIFJlY3Vyc2l2ZWx5IGludGlhbGl6ZSBldmVuIGFuZCBvZGQgc3ViLXBhcnRzIGFu ZCBtZXJnZSB3aXRoIHppcDEuCgpnY2MvQ2hhbmdlTG9nOgoJKiBjb25maWcvYWFyY2g2NC9hYXJj aDY0LmNjIChhYXJjaDY0X2V4cGFuZF92ZWN0b3JfaW5pdF9mYWxsYmFjayk6IFJlbmFtZQoJYWFy Y2g2NF9leHBhbmRfdmVjdG9yX2luaXQgdG8gdGhpcywgYW5kIHJlbW92ZSAJaW50ZXJsZWF2aW5n IGNhc2UuCglSZWN1cnNpdmVseSBjYWxsIGFhcmNoNjRfZXhwYW5kX3ZlY3Rvcl9pbml0X2ZhbGxi YWNrLCBpbnN0ZWFkIG9mCglhYXJjaDY0X2V4cGFuZF92ZWN0b3JfaW5pdC4KCShhYXJjaDY0X3Vu emlwX3ZlY3Rvcl9pbml0KTogTmV3IGZ1bmN0aW9uLgoJKGFhcmNoNjRfZXhwYW5kX3ZlY3Rvcl9p bml0KTogTGlrZXdpc2UuCgpnY2MvdGVzdHN1aXRlL0NoYW5nZUxvZzoKCSogZ2NjLnRhcmdldC9h YXJjaDY0L2xkcF9zdHBfMTYuYyAoY29uczJfOF9mbG9hdCk6IEFkanVzdCBmb3IgbmV3Cgljb2Rl LWdlbi4KCSogZ2NjLnRhcmdldC9hYXJjaDY0L3N2ZS9hY2xlL2dlbmVyYWwvZHVwcV81LmM6IExp a2V3aXNlLgoJKiBnY2MudGFyZ2V0L2FhcmNoNjQvc3ZlL2FjbGUvZ2VuZXJhbC9kdXBxXzYuYzog TGlrZXdpc2UuCgkqIGdjYy50YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0xOC5jOiBSZW5hbWUgaW50 ZXJsZWF2ZS1pbml0LTEuYyB0bwoJdGhpcy4KCSogZ2NjLnRhcmdldC9hYXJjaDY0L3ZlYy1pbml0 LTE5LmM6IE5ldyB0ZXN0LgoJKiBnY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMjAuYzogTGlr ZXdpc2UuCgkqIGdjYy50YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0yMS5jOiBMaWtld2lzZS4KCSog Z2NjLnRhcmdldC9hYXJjaDY0L3ZlYy1pbml0LTIyLXNpemUuYzogTGlrZXdpc2UuCgkqIGdjYy50 YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0yMi1zcGVlZC5jOiBMaWtld2lzZS4KCSogZ2NjLnRhcmdl dC9hYXJjaDY0L3ZlYy1pbml0LTIyLmg6IE5ldyBoZWFkZXIuCgpkaWZmIC0tZ2l0IGEvZ2NjL2Nv bmZpZy9hYXJjaDY0L2FhcmNoNjQuY2MgYi9nY2MvY29uZmlnL2FhcmNoNjQvYWFyY2g2NC5jYwpp bmRleCBkN2U4OTVmOGQzNC4uNDE2ZTA2MjgyOWMgMTAwNjQ0Ci0tLSBhL2djYy9jb25maWcvYWFy Y2g2NC9hYXJjaDY0LmNjCisrKyBiL2djYy9jb25maWcvYWFyY2g2NC9hYXJjaDY0LmNjCkBAIC0y MjAyNiwxMSArMjIwMjYsMTIgQEAgYWFyY2g2NF9zaW1kX21ha2VfY29uc3RhbnQgKHJ0eCB2YWxz KQogICAgIHJldHVybiBOVUxMX1JUWDsKIH0KIAotLyogRXhwYW5kIGEgdmVjdG9yIGluaXRpYWxp c2F0aW9uIHNlcXVlbmNlLCBzdWNoIHRoYXQgVEFSR0VUIGlzCi0gICBpbml0aWFsaXNlZCB0byBj b250YWluIFZBTFMuICAqLworLyogQSBzdWJyb3V0aW5lIG9mIGFhcmNoNjRfZXhwYW5kX3ZlY3Rv cl9pbml0LCB3aXRoIHRoZSBzYW1lIGludGVyZmFjZS4KKyAgIFRoZSBjYWxsZXIgaGFzIGFscmVh ZHkgdHJpZWQgYSBkaXZpZGUtYW5kLWNvbnF1ZXIgYXBwcm9hY2gsIHNvIGRvCisgICBub3QgY29u c2lkZXIgdGhhdCBjYXNlIGhlcmUuICAqLwogCiB2b2lkCi1hYXJjaDY0X2V4cGFuZF92ZWN0b3Jf aW5pdCAocnR4IHRhcmdldCwgcnR4IHZhbHMpCithYXJjaDY0X2V4cGFuZF92ZWN0b3JfaW5pdF9m YWxsYmFjayAocnR4IHRhcmdldCwgcnR4IHZhbHMpCiB7CiAgIG1hY2hpbmVfbW9kZSBtb2RlID0g R0VUX01PREUgKHRhcmdldCk7CiAgIHNjYWxhcl9tb2RlIGlubmVyX21vZGUgPSBHRVRfTU9ERV9J Tk5FUiAobW9kZSk7CkBAIC0yMjA5MCwzOCArMjIwOTEsNiBAQCBhYXJjaDY0X2V4cGFuZF92ZWN0 b3JfaW5pdCAocnR4IHRhcmdldCwgcnR4IHZhbHMpCiAgICAgICByZXR1cm47CiAgICAgfQogCi0g IC8qIENoZWNrIGZvciBpbnRlcmxlYXZpbmcgY2FzZS4KLSAgICAgRm9yIGVnIGlmIGluaXRpYWxp emVyIGlzIChpbnQxNng4X3QpIHt4LCB5LCB4LCB5LCB4LCB5LCB4LCB5fS4KLSAgICAgR2VuZXJh dGUgZm9sbG93aW5nIGNvZGU6Ci0gICAgIGR1cCB2MC5oLCB4Ci0gICAgIGR1cCB2MS5oLCB5Ci0g ICAgIHppcDEgdjAuaCwgdjAuaCwgdjEuaAotICAgICBmb3IgImxhcmdlIGVub3VnaCIgaW5pdGlh bGl6ZXIuICAqLwotCi0gIGlmIChuX2VsdHMgPj0gOCkKLSAgICB7Ci0gICAgICBpbnQgaTsKLSAg ICAgIGZvciAoaSA9IDI7IGkgPCBuX2VsdHM7IGkrKykKLQlpZiAoIXJ0eF9lcXVhbF9wIChYVkVD RVhQICh2YWxzLCAwLCBpKSwgWFZFQ0VYUCAodmFscywgMCwgaSAlIDIpKSkKLQkgIGJyZWFrOwot Ci0gICAgICBpZiAoaSA9PSBuX2VsdHMpCi0JewotCSAgbWFjaGluZV9tb2RlIG1vZGUgPSBHRVRf TU9ERSAodGFyZ2V0KTsKLQkgIHJ0eCBkZXN0WzJdOwotCi0JICBmb3IgKGludCBpID0gMDsgaSA8 IDI7IGkrKykKLQkgICAgewotCSAgICAgIHJ0eCB4ID0gZXhwYW5kX3ZlY3Rvcl9icm9hZGNhc3Qg KG1vZGUsIFhWRUNFWFAgKHZhbHMsIDAsIGkpKTsKLQkgICAgICBkZXN0W2ldID0gZm9yY2VfcmVn IChtb2RlLCB4KTsKLQkgICAgfQotCi0JICBydHZlYyB2ID0gZ2VuX3J0dmVjICgyLCBkZXN0WzBd LCBkZXN0WzFdKTsKLQkgIGVtaXRfc2V0X2luc24gKHRhcmdldCwgZ2VuX3J0eF9VTlNQRUMgKG1v ZGUsIHYsIFVOU1BFQ19aSVAxKSk7Ci0JICByZXR1cm47Ci0JfQotICAgIH0KLQogICBlbnVtIGlu c25fY29kZSBpY29kZSA9IG9wdGFiX2hhbmRsZXIgKHZlY19zZXRfb3B0YWIsIG1vZGUpOwogICBn Y2NfYXNzZXJ0IChpY29kZSAhPSBDT0RFX0ZPUl9ub3RoaW5nKTsKIApAQCAtMjIyNDMsNyArMjIy MTIsNyBAQCBhYXJjaDY0X2V4cGFuZF92ZWN0b3JfaW5pdCAocnR4IHRhcmdldCwgcnR4IHZhbHMp CiAJICAgIH0KIAkgIFhWRUNFWFAgKGNvcHksIDAsIGkpID0gc3Vic3Q7CiAJfQotICAgICAgYWFy Y2g2NF9leHBhbmRfdmVjdG9yX2luaXQgKHRhcmdldCwgY29weSk7CisgICAgICBhYXJjaDY0X2V4 cGFuZF92ZWN0b3JfaW5pdF9mYWxsYmFjayAodGFyZ2V0LCBjb3B5KTsKICAgICB9CiAKICAgLyog SW5zZXJ0IHRoZSB2YXJpYWJsZSBsYW5lcyBkaXJlY3RseS4gICovCkBAIC0yMjI1Nyw2ICsyMjIy Niw4MSBAQCBhYXJjaDY0X2V4cGFuZF92ZWN0b3JfaW5pdCAocnR4IHRhcmdldCwgcnR4IHZhbHMp CiAgICAgfQogfQogCisvKiBSZXR1cm4gZXZlbiBvciBvZGQgaGFsZiBvZiBWQUxTIGRlcGVuZGlu ZyBvbiBFVkVOX1AuICAqLworCitzdGF0aWMgcnR4CithYXJjaDY0X3VuemlwX3ZlY3Rvcl9pbml0 IChtYWNoaW5lX21vZGUgbW9kZSwgcnR4IHZhbHMsIGJvb2wgZXZlbl9wKQoreworICBpbnQgbiA9 IFhWRUNMRU4gKHZhbHMsIDApOworICBtYWNoaW5lX21vZGUgbmV3X21vZGUKKyAgICA9IGFhcmNo NjRfc2ltZF9jb250YWluZXJfbW9kZSAoR0VUX01PREVfSU5ORVIgKG1vZGUpLAorCQkJCSAgIEdF VF9NT0RFX0JJVFNJWkUgKG1vZGUpLnRvX2NvbnN0YW50ICgpIC8gMik7CisgIHJ0dmVjIHZlYyA9 IHJ0dmVjX2FsbG9jIChuIC8gMik7CisgIGZvciAoaW50IGkgPSAwOyBpIDwgbi8yOyBpKyspCisg ICAgUlRWRUNfRUxUICh2ZWMsIGkpID0gKGV2ZW5fcCkgPyBYVkVDRVhQICh2YWxzLCAwLCAyICog aSkKKwkJCQkgIDogWFZFQ0VYUCAodmFscywgMCwgMiAqIGkgKyAxKTsKKyAgcmV0dXJuIGdlbl9y dHhfUEFSQUxMRUwgKG5ld19tb2RlLCB2ZWMpOworfQorCisvKiBFeHBhbmQgYSB2ZWN0b3IgaW5p dGlhbGlzYXRpb24gc2VxdWVuY2UsIHN1Y2ggdGhhdCBUQVJHRVQgaXMKKyAgIGluaXRpYWxpemVk IHRvIGNvbnRhaW4gVkFMUy4gICovCisKK3ZvaWQKK2FhcmNoNjRfZXhwYW5kX3ZlY3Rvcl9pbml0 IChydHggdGFyZ2V0LCBydHggdmFscykKK3sKKyAgLyogVHJ5IGRlY29tcG9zaW5nIHRoZSBpbml0 aWFsaXplciBpbnRvIGV2ZW4gYW5kIG9kZCBoYWx2ZXMgYW5kCisgICAgIHRoZW4gWklQIHRoZW0g dG9nZXRoZXIuICBVc2UgdGhlIHJlc3VsdGluZyBzZXF1ZW5jZSBpZiBpdCBpcworICAgICBzdHJp Y3RseSBjaGVhcGVyIHRoYW4gbG9hZGluZyBWQUxTIGRpcmVjdGx5LgorCisgICAgIFByZWZlciB0 aGUgZmFsbGJhY2sgc2VxdWVuY2UgaW4gdGhlIGV2ZW50IG9mIGEgdGllLCBzaW5jZSBpdAorICAg ICB3aWxsIHRlbmQgdG8gdXNlIGZld2VyIHJlZ2lzdGVycy4gICovCisKKyAgbWFjaGluZV9tb2Rl IG1vZGUgPSBHRVRfTU9ERSAodGFyZ2V0KTsKKyAgaW50IG5fZWx0cyA9IFhWRUNMRU4gKHZhbHMs IDApOworCisgIGlmIChuX2VsdHMgPCA0CisgICAgICB8fCBtYXliZV9uZSAoR0VUX01PREVfQklU U0laRSAobW9kZSksIDEyOCkpCisgICAgeworICAgICAgYWFyY2g2NF9leHBhbmRfdmVjdG9yX2lu aXRfZmFsbGJhY2sgKHRhcmdldCwgdmFscyk7CisgICAgICByZXR1cm47CisgICAgfQorCisgIHN0 YXJ0X3NlcXVlbmNlICgpOworICBydHggaGFsdmVzWzJdOworICB1bnNpZ25lZCBjb3N0c1syXTsK KyAgZm9yIChpbnQgaSA9IDA7IGkgPCAyOyBpKyspCisgICAgeworICAgICAgc3RhcnRfc2VxdWVu Y2UgKCk7CisgICAgICBydHggbmV3X3ZhbHMKKwk9IGFhcmNoNjRfdW56aXBfdmVjdG9yX2luaXQg KG1vZGUsIHZhbHMsIChpICUgMikgPT0gMCk7CisgICAgICBydHggdG1wX3JlZyA9IGdlbl9yZWdf cnR4IChHRVRfTU9ERSAobmV3X3ZhbHMpKTsKKyAgICAgIGFhcmNoNjRfZXhwYW5kX3ZlY3Rvcl9p bml0ICh0bXBfcmVnLCBuZXdfdmFscyk7CisgICAgICBoYWx2ZXNbaV0gPSBnZW5fcnR4X1NVQlJF RyAobW9kZSwgdG1wX3JlZywgMCk7CisgICAgICBydHhfaW5zbiAqcmVjX3NlcSA9IGdldF9pbnNu cyAoKTsKKyAgICAgIGVuZF9zZXF1ZW5jZSAoKTsKKyAgICAgIGNvc3RzW2ldID0gc2VxX2Nvc3Qg KHJlY19zZXEsICFvcHRpbWl6ZV9zaXplKTsKKyAgICAgIGVtaXRfaW5zbiAocmVjX3NlcSk7Cisg ICAgfQorCisgIHJ0dmVjIHYgPSBnZW5fcnR2ZWMgKDIsIGhhbHZlc1swXSwgaGFsdmVzWzFdKTsK KyAgcnR4X2luc24gKnppcDFfaW5zbgorICAgID0gZW1pdF9zZXRfaW5zbiAodGFyZ2V0LCBnZW5f cnR4X1VOU1BFQyAobW9kZSwgdiwgVU5TUEVDX1pJUDEpKTsKKyAgdW5zaWduZWQgc2VxX3RvdGFs X2Nvc3QKKyAgICA9ICghb3B0aW1pemVfc2l6ZSkgPyBzdGQ6Om1heCAoY29zdHNbMF0sIGNvc3Rz WzFdKSA6IGNvc3RzWzBdICsgY29zdHNbMV07CisgIHNlcV90b3RhbF9jb3N0ICs9IGluc25fY29z dCAoemlwMV9pbnNuLCAhb3B0aW1pemVfc2l6ZSk7CisKKyAgcnR4X2luc24gKnNlcSA9IGdldF9p bnNucyAoKTsKKyAgZW5kX3NlcXVlbmNlICgpOworCisgIHN0YXJ0X3NlcXVlbmNlICgpOworICBh YXJjaDY0X2V4cGFuZF92ZWN0b3JfaW5pdF9mYWxsYmFjayAodGFyZ2V0LCB2YWxzKTsKKyAgcnR4 X2luc24gKmZhbGxiYWNrX3NlcSA9IGdldF9pbnNucyAoKTsKKyAgdW5zaWduZWQgZmFsbGJhY2tf c2VxX2Nvc3QgPSBzZXFfY29zdCAoZmFsbGJhY2tfc2VxLCAhb3B0aW1pemVfc2l6ZSk7CisgIGVu ZF9zZXF1ZW5jZSAoKTsKKworICBlbWl0X2luc24gKHNlcV90b3RhbF9jb3N0IDwgZmFsbGJhY2tf c2VxX2Nvc3QgPyBzZXEgOiBmYWxsYmFja19zZXEpOworfQorCiAvKiBFbWl0IFJUTCBjb3JyZXNw b25kaW5nIHRvOgogICAgaW5zciBUQVJHRVQsIEVMRU0uICAqLwogCmRpZmYgLS1naXQgYS9nY2Mv dGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC9sZHBfc3RwXzE2LmMgYi9nY2MvdGVzdHN1aXRl L2djYy50YXJnZXQvYWFyY2g2NC9sZHBfc3RwXzE2LmMKaW5kZXggOGFiMTE3YzRkY2QuLjMwYzg2 MDE4NzczIDEwMDY0NAotLS0gYS9nY2MvdGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC9sZHBf c3RwXzE2LmMKKysrIGIvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvbGRwX3N0cF8x Ni5jCkBAIC05NiwxMCArOTYsMTAgQEAgQ09OUzJfRk4gKDQsIGZsb2F0KTsKIAogLyoKICoqIGNv bnMyXzhfZmxvYXQ6Ci0qKglkdXAJdihbMC05XSspXC40cywgLioKKyoqCWR1cAl2KFswLTldKylc LjJzLCB2MS5zXFswXF0KICoqCS4uLgotKioJc3RwCXFcMSwgcVwxLCBcW3gwXF0KLSoqCXN0cAlx XDEsIHFcMSwgXFt4MCwgIz8zMlxdCisqKglzdHAJcTAsIHEwLCBcW3gwXF0KKyoqCXN0cAlxMCwg cTAsIFxbeDAsICM/MzJcXQogKioJcmV0CiAqLwogQ09OUzJfRk4gKDgsIGZsb2F0KTsKZGlmZiAt LWdpdCBhL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9hYXJjaDY0L3N2ZS9hY2xlL2dlbmVyYWwv ZHVwcV81LmMgYi9nY2MvdGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC9zdmUvYWNsZS9nZW5l cmFsL2R1cHFfNS5jCmluZGV4IDUzNDI2YzlhZjVhLi5jN2Q2ZjNmZjM5MCAxMDA2NDQKLS0tIGEv Z2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvc3ZlL2FjbGUvZ2VuZXJhbC9kdXBxXzUu YworKysgYi9nY2MvdGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC9zdmUvYWNsZS9nZW5lcmFs L2R1cHFfNS5jCkBAIC0xMSw3ICsxMSw3IEBAIGR1cHEgKGludCB4MSwgaW50IHgyLCBpbnQgeDMs IGludCB4NCkKIAogLyogeyBkZy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyLW5vdCB7XHRsZHJcdH0g fSB9ICovCiAvKiB7IGRnLWZpbmFsIHsgc2Nhbi1hc3NlbWJsZXIgeywgW3d4XTBcbn0gfSB9ICov Ci0vKiB7IGRnLWZpbmFsIHsgc2Nhbi1hc3NlbWJsZXIge1x0aW5zXHR2WzAtOV0rXC5zXFsxXF0s IHcxXG59IH0gfSAqLwotLyogeyBkZy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyIHtcdGluc1x0dlsw LTldK1wuc1xbMlxdLCB3MlxufSB9IH0gKi8KLS8qIHsgZGctZmluYWwgeyBzY2FuLWFzc2VtYmxl ciB7XHRpbnNcdHZbMC05XStcLnNcWzNcXSwgdzNcbn0gfSB9ICovCisvKiB7IGRnLWZpbmFsIHsg c2Nhbi1hc3NlbWJsZXIge1x0aW5zXHR2WzAtOV0rXC5zXFsxXF0sIHcyXG59IH0gfSAqLworLyog eyBkZy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyIHtcdGluc1x0dlswLTldK1wuc1xbMVxdLCB3M1xu fSB9IH0gKi8KKy8qIHsgZGctZmluYWwgeyBzY2FuLWFzc2VtYmxlciB7XHR6aXAxXHR2WzAtOV0r XC40cywgdlswLTldK1wuNHMsIHZbMC05XVwuNHNcbn0gfSB9ICovCiAvKiB7IGRnLWZpbmFsIHsg c2Nhbi1hc3NlbWJsZXIge1x0ZHVwXHR6WzAtOV0rXC5xLCB6WzAtOV0rXC5xXFswXF1cbn0gfSB9 ICovCmRpZmYgLS1naXQgYS9nY2MvdGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC9zdmUvYWNs ZS9nZW5lcmFsL2R1cHFfNi5jIGIvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvc3Zl L2FjbGUvZ2VuZXJhbC9kdXBxXzYuYwppbmRleCBkZmNlNWU3YTEyYS4uNDc0NWEzODE1YjAgMTAw NjQ0Ci0tLSBhL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9hYXJjaDY0L3N2ZS9hY2xlL2dlbmVy YWwvZHVwcV82LmMKKysrIGIvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvc3ZlL2Fj bGUvZ2VuZXJhbC9kdXBxXzYuYwpAQCAtMTIsNyArMTIsNyBAQCBkdXBxIChpbnQgeDEsIGludCB4 MiwgaW50IHgzLCBpbnQgeDQpCiAKIC8qIHsgZGctZmluYWwgeyBzY2FuLWFzc2VtYmxlci1ub3Qg e1x0bGRyXHR9IH0gfSAqLwogLyogeyBkZy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyIHssIFt3eF0w XG59IH0gfSAqLwotLyogeyBkZy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyIHtcdGluc1x0dlswLTld K1wuc1xbMVxdLCB3MVxufSB9IH0gKi8KLS8qIHsgZGctZmluYWwgeyBzY2FuLWFzc2VtYmxlciB7 XHRpbnNcdHZbMC05XStcLnNcWzJcXSwgdzJcbn0gfSB9ICovCi0vKiB7IGRnLWZpbmFsIHsgc2Nh bi1hc3NlbWJsZXIge1x0aW5zXHR2WzAtOV0rXC5zXFszXF0sIHczXG59IH0gfSAqLworLyogeyBk Zy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyIHtcdGluc1x0dlswLTldK1wuc1xbMVxdLCB3MlxufSB9 IH0gKi8KKy8qIHsgZGctZmluYWwgeyBzY2FuLWFzc2VtYmxlciB7XHRpbnNcdHZbMC05XStcLnNc WzFcXSwgdzNcbn0gfSB9ICovCisvKiB7IGRnLWZpbmFsIHsgc2Nhbi1hc3NlbWJsZXIge1x0emlw MVx0dlswLTldK1wuNHMsIHZbMC05XStcLjRzLCB2WzAtOV1cLjRzXG59IH0gfSAqLwogLyogeyBk Zy1maW5hbCB7IHNjYW4tYXNzZW1ibGVyIHtcdGR1cFx0elswLTldK1wucSwgelswLTldK1wucVxb MFxdXG59IH0gfSAqLwpkaWZmIC0tZ2l0IGEvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNo NjQvaW50ZXJsZWF2ZS1pbml0LTEuYyBiL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9hYXJjaDY0 L3ZlYy1pbml0LTE4LmMKc2ltaWxhcml0eSBpbmRleCA4MiUKcmVuYW1lIGZyb20gZ2NjL3Rlc3Rz dWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvaW50ZXJsZWF2ZS1pbml0LTEuYwpyZW5hbWUgdG8gZ2Nj L3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMTguYwppbmRleCBlZTc3NTA0 ODU4OS4uZTgxMmQzOTQ2ZGUgMTAwNjQ0Ci0tLSBhL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9h YXJjaDY0L2ludGVybGVhdmUtaW5pdC0xLmMKKysrIGIvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0 L2FhcmNoNjQvdmVjLWluaXQtMTguYwpAQCAtNyw4ICs3LDggQEAKIC8qCiAqKiBmb286CiAqKgku Li4KLSoqCWR1cAl2WzAtOV0rXC44aCwgd1swLTldKwotKioJZHVwCXZbMC05XStcLjhoLCB3WzAt OV0rCisqKglkdXAJdlswLTldK1wuNGgsIHdbMC05XSsKKyoqCWR1cAl2WzAtOV0rXC40aCwgd1sw LTldKwogKioJemlwMQl2WzAtOV0rXC44aCwgdlswLTldK1wuOGgsIHZbMC05XStcLjhoCiAqKgku Li4KICoqCXJldApAQCAtMjMsOCArMjMsOCBAQCBpbnQxNng4X3QgZm9vKGludDE2X3QgeCwgaW50 IHkpCiAvKgogKiogZm9vMjoKICoqCS4uLgotKioJZHVwCXZbMC05XStcLjhoLCB3WzAtOV0rCi0q Kgltb3ZpCXZbMC05XStcLjhoLCAweDEKKyoqCWR1cAl2WzAtOV0rXC40aCwgd1swLTldKworKioJ bW92aQl2WzAtOV0rXC40aCwgMHgxCiAqKgl6aXAxCXZbMC05XStcLjhoLCB2WzAtOV0rXC44aCwg dlswLTldK1wuOGgKICoqCS4uLgogKioJcmV0CmRpZmYgLS1naXQgYS9nY2MvdGVzdHN1aXRlL2dj Yy50YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0xOS5jIGIvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0 L2FhcmNoNjQvdmVjLWluaXQtMTkuYwpuZXcgZmlsZSBtb2RlIDEwMDY0NAppbmRleCAwMDAwMDAw MDAwMC4uZTI4ZmRjZGEyOWQKLS0tIC9kZXYvbnVsbAorKysgYi9nY2MvdGVzdHN1aXRlL2djYy50 YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0xOS5jCkBAIC0wLDAgKzEsMjEgQEAKKy8qIHsgZGctZG8g Y29tcGlsZSB9ICovCisvKiB7IGRnLW9wdGlvbnMgIi1PMyIgfSAqLworLyogeyBkZy1maW5hbCB7 IGNoZWNrLWZ1bmN0aW9uLWJvZGllcyAiKioiICIiICIiIH0gfSAqLworCisjaW5jbHVkZSA8YXJt X25lb24uaD4KKworLyoKKyoqIGZfczg6CisqKgkuLi4KKyoqCWR1cAl2WzAtOV0rXC44Yiwgd1sw LTldKworKioJYWRycAl4WzAtOV0rLCBcLkxDWzAtOV0rCisqKglsZHIJZFswLTldKywgXFt4WzAt OV0rLCAjOmxvMTI6LkxDWzAtOV0rXF0KKyoqCXppcDEJdlswLTldK1wuMTZiLCB2WzAtOV0rXC4x NmIsIHZbMC05XStcLjE2YgorKioJcmV0CisqLworCitpbnQ4eDE2X3QgZl9zOChpbnQ4X3QgeCkK K3sKKyAgcmV0dXJuIChpbnQ4eDE2X3QpIHsgeCwgMSwgeCwgMiwgeCwgMywgeCwgNCwKKyAgICAg ICAgICAgICAgICAgICAgICAgeCwgNSwgeCwgNiwgeCwgNywgeCwgOCB9OworfQpkaWZmIC0tZ2l0 IGEvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMjAuYyBiL2djYy90 ZXN0c3VpdGUvZ2NjLnRhcmdldC9hYXJjaDY0L3ZlYy1pbml0LTIwLmMKbmV3IGZpbGUgbW9kZSAx MDA2NDQKaW5kZXggMDAwMDAwMDAwMDAuLjkzNjZjYTM0OWI2Ci0tLSAvZGV2L251bGwKKysrIGIv Z2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMjAuYwpAQCAtMCwwICsx LDIyIEBACisvKiB7IGRnLWRvIGNvbXBpbGUgfSAqLworLyogeyBkZy1vcHRpb25zICItTzMiIH0g Ki8KKy8qIHsgZGctZmluYWwgeyBjaGVjay1mdW5jdGlvbi1ib2RpZXMgIioqIiAiIiAiIiB9IH0g Ki8KKworI2luY2x1ZGUgPGFybV9uZW9uLmg+CisKKy8qCisqKiBmX3M4OgorKioJLi4uCisqKglh ZHJwCXhbMC05XSssIFwuTENbMC05XSsKKyoqCWR1cAl2WzAtOV0rXC44Yiwgd1swLTldKworKioJ bGRyCWRbMC05XSssIFxbeFswLTldKywgIzpsbzEyOlwuTENbMC05XStcXQorKioJaW5zCXYwXC5i XFswXF0sIHcwCisqKgl6aXAxCXZbMC05XStcLjE2YiwgdlswLTldK1wuMTZiLCB2WzAtOV0rXC4x NmIKKyoqCXJldAorKi8KKworaW50OHgxNl90IGZfczgoaW50OF90IHgsIGludDhfdCB5KQorewor ICByZXR1cm4gKGludDh4MTZfdCkgeyB4LCB5LCAxLCB5LCAyLCB5LCAzLCB5LAorICAgICAgICAg ICAgICAgICAgICAgICA0LCB5LCA1LCB5LCA2LCB5LCA3LCB5IH07Cit9CmRpZmYgLS1naXQgYS9n Y2MvdGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0yMS5jIGIvZ2NjL3Rlc3Rz dWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMjEuYwpuZXcgZmlsZSBtb2RlIDEwMDY0 NAppbmRleCAwMDAwMDAwMDAwMC4uZTE2NDU5NDg2ZDcKLS0tIC9kZXYvbnVsbAorKysgYi9nY2Mv dGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC92ZWMtaW5pdC0yMS5jCkBAIC0wLDAgKzEsMjIg QEAKKy8qIHsgZGctZG8gY29tcGlsZSB9ICovCisvKiB7IGRnLW9wdGlvbnMgIi1PMyIgfSAqLwor LyogeyBkZy1maW5hbCB7IGNoZWNrLWZ1bmN0aW9uLWJvZGllcyAiKioiICIiICIiIH0gfSAqLwor CisjaW5jbHVkZSA8YXJtX25lb24uaD4KKworLyoKKyoqIGZfczg6CisqKgkuLi4KKyoqCWFkcnAJ eFswLTldKywgXC5MQ1swLTldKworKioJbGRyCXFbMC05XSssIFxbeFswLTldKywgIzpsbzEyOlwu TENbMC05XStcXQorKioJaW5zCXYwXC5iXFswXF0sIHcwCisqKglpbnMJdjBcLmJcWzFcXSwgdzEK KyoqCS4uLgorKioJcmV0CisqLworCitpbnQ4eDE2X3QgZl9zOChpbnQ4X3QgeCwgaW50OF90IHkp Cit7CisgIHJldHVybiAoaW50OHgxNl90KSB7IHgsIHksIDEsIDIsIDMsIDQsIDUsIDYsCisgICAg ICAgICAgICAgICAgICAgICAgIDcsIDgsIDksIDEwLCAxMSwgMTIsIDEzLCAxNCB9OworfQpkaWZm IC0tZ2l0IGEvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMjItc2l6 ZS5jIGIvZ2NjL3Rlc3RzdWl0ZS9nY2MudGFyZ2V0L2FhcmNoNjQvdmVjLWluaXQtMjItc2l6ZS5j Cm5ldyBmaWxlIG1vZGUgMTAwNjQ0CmluZGV4IDAwMDAwMDAwMDAwLi44ZjM1ODU0YzAwOAotLS0g L2Rldi9udWxsCisrKyBiL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9hYXJjaDY0L3ZlYy1pbml0 LTIyLXNpemUuYwpAQCAtMCwwICsxLDI0IEBACisvKiB7IGRnLWRvIGNvbXBpbGUgfSAqLworLyog eyBkZy1vcHRpb25zICItT3MiIH0gKi8KKy8qIHsgZGctZmluYWwgeyBjaGVjay1mdW5jdGlvbi1i b2RpZXMgIioqIiAiIiAiIiB9IH0gKi8KKworLyogVmVyaWZ5IHRoYXQgZmFsbGJhY2sgY29kZS1z ZXF1ZW5jZSBpcyBjaG9zZW4gb3ZlcgorICAgcmVjdXJzaXZlbHkgZ2VuZXJhdGVkIGNvZGUtc2Vx dWVuY2UgbWVyZ2VkIHdpdGggemlwMS4gICovCisKKy8qCisqKiBmX3MxNjoKKyoqCS4uLgorKioJ c3h0aAl3MCwgdzAKKyoqCWZtb3YJczAsIHcwCisqKglpbnMJdjBcLmhcWzFcXSwgdzEKKyoqCWlu cwl2MFwuaFxbMlxdLCB3MgorKioJaW5zCXYwXC5oXFszXF0sIHczCisqKglpbnMJdjBcLmhcWzRc XSwgdzQKKyoqCWlucwl2MFwuaFxbNVxdLCB3NQorKioJaW5zCXYwXC5oXFs2XF0sIHc2CisqKglp bnMJdjBcLmhcWzdcXSwgdzcKKyoqCS4uLgorKioJcmV0CisqLworCisjaW5jbHVkZSAidmVjLWlu aXQtMjIuaCIKZGlmZiAtLWdpdCBhL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9hYXJjaDY0L3Zl Yy1pbml0LTIyLXNwZWVkLmMgYi9nY2MvdGVzdHN1aXRlL2djYy50YXJnZXQvYWFyY2g2NC92ZWMt aW5pdC0yMi1zcGVlZC5jCm5ldyBmaWxlIG1vZGUgMTAwNjQ0CmluZGV4IDAwMDAwMDAwMDAwLi4x NzJkNTZmZmRmMQotLS0gL2Rldi9udWxsCisrKyBiL2djYy90ZXN0c3VpdGUvZ2NjLnRhcmdldC9h YXJjaDY0L3ZlYy1pbml0LTIyLXNwZWVkLmMKQEAgLTAsMCArMSwyNyBAQAorLyogeyBkZy1kbyBj b21waWxlIH0gKi8KKy8qIHsgZGctb3B0aW9ucyAiLU8zIiB9ICovCisvKiB7IGRnLWZpbmFsIHsg Y2hlY2stZnVuY3Rpb24tYm9kaWVzICIqKiIgIiIgIiIgfSB9ICovCisKKy8qIFZlcmlmeSB0aGF0 IHdlIHJlY3Vyc2l2ZWx5IGdlbmVyYXRlIGNvZGUgZm9yIGV2ZW4gYW5kIG9kZCBoYWx2ZXMKKyAg IGluc3RlYWQgb2YgZmFsbGJhY2sgY29kZS4gVGhpcyBpcyBzbyBkZXNwaXRlIHRoZSBsb25nZXIg Y29kZS1nZW4KKyAgIGJlY2F1c2UgaXQgaGFzIGZld2VyIGRlcGVuZGVuY2llcyBhbmQgdGh1cyBo YXMgbGVzc2VyIGNvc3QuICAqLworCisvKgorKiogZl9zMTY6CisqKgkuLi4KKyoqCXN4dGgJdzAs IHcwCisqKglzeHRoCXcxLCB3MQorKioJZm1vdglkMCwgeDAKKyoqCWZtb3YJZDEsIHgxCisqKglp bnMJdlswLTldK1wuaFxbMVxdLCB3MgorKioJaW5zCXZbMC05XStcLmhcWzFcXSwgdzMKKyoqCWlu cwl2WzAtOV0rXC5oXFsyXF0sIHc0CisqKglpbnMJdlswLTldK1wuaFxbMlxdLCB3NQorKioJaW5z CXZbMC05XStcLmhcWzNcXSwgdzYKKyoqCWlucwl2WzAtOV0rXC5oXFszXF0sIHc3CisqKgl6aXAx CXZbMC05XStcLjhoLCB2WzAtOV0rXC44aCwgdlswLTldK1wuOGgKKyoqCS4uLgorKioJcmV0Cisq LworCisjaW5jbHVkZSAidmVjLWluaXQtMjIuaCIKZGlmZiAtLWdpdCBhL2djYy90ZXN0c3VpdGUv Z2NjLnRhcmdldC9hYXJjaDY0L3ZlYy1pbml0LTIyLmggYi9nY2MvdGVzdHN1aXRlL2djYy50YXJn ZXQvYWFyY2g2NC92ZWMtaW5pdC0yMi5oCm5ldyBmaWxlIG1vZGUgMTAwNjQ0CmluZGV4IDAwMDAw MDAwMDAwLi4xNWI4ODlkNDA5NwotLS0gL2Rldi9udWxsCisrKyBiL2djYy90ZXN0c3VpdGUvZ2Nj LnRhcmdldC9hYXJjaDY0L3ZlYy1pbml0LTIyLmgKQEAgLTAsMCArMSw3IEBACisjaW5jbHVkZSA8 YXJtX25lb24uaD4KKworaW50MTZ4OF90IGZfczE2IChpbnQxNl90IHgwLCBpbnQxNl90IHgxLCBp bnQxNl90IHgyLCBpbnQxNl90IHgzLAorICAgICAgICAgICAgICAgICBpbnQxNl90IHg0LCBpbnQx Nl90IHg1LCBpbnQxNl90IHg2LCBpbnQxNl90IHg3KQoreworICByZXR1cm4gKGludDE2eDhfdCkg eyB4MCwgeDEsIHgyLCB4MywgeDQsIHg1LCB4NiwgeDcgfTsKK30K --00000000000038f67005f9f72935--