(unknown),

(unknown),

[Ramesh M]

Hi Team,

I am getting the below panic message when i enable NAT in linux kernel
2.6.31 running on mips based SOC board.

could you please let me know if you this issue already FIXED or root
caused  somewhere ??


Thanks for your help


Regards
Ramesh


Unhandled kernel unaligned access or invalid instruction[#1]:
Cpu 0
$ 0   : 00000000 00000000 804f3172 0000005c
$ 4   : 8797c8c0 0000001c 879a32e4 00000001
$ 8   : 00000028 800fdf48 00000014 37987883
$12   : 185a5616 80256a20 05491623 edf4c4c3
$16   : 00000006 0000001c 00000014 879a32e4
$20   : 8797c8c0 00000001 879a32d8 879cec00
$24   : 00000000 80193958
$28   : 87824000 87825a50 8797c8c0 801e5074
Hi    : 00000388
Lo    : 00000000
epc   : 801e6b60 tcp_manip_pkt+0x3c/0x11c
    Not tainted
ra    : 801e5074 manip_pkt+0x70/0x14c
Status: 1100ff03    KERNEL EXL IE
Cause : 00800010
BadVA : 804f318e
PrId  : 00019750 (MIPS 74Kc)
Modules linked in: athrs_gmac
Process ksoftirqd/0 (pid: 3, threadinfo=87824000, task=87817198, tls=00000000)
Stack : 185a5616 80256a20 05491623 edf4c4c3 804f3186 8797c8c0 804f3172 00000006
        8797c8c0 0000001c 879a32e4 00000001 00000001 801e5074 87825b10 8111ae50
        87824000 87825ab8 8797c8c0 801e527c 804f3186 8797c8c0 879a32e4 00000014
        00000000 801e52cc 8797c8c0 87825c08 8797c8c0 00000001 00000001 87825ad8
        802cb970 802c6aa0 c0a80115 00000000 00000000 00000000 052c0002 0a34f48c
        ...
Call Trace:
[<801e6b60>] tcp_manip_pkt+0x3c/0x11c
[<801e5074>] manip_pkt+0x70/0x14c
[<801e52cc>] nf_nat_icmp_reply_translation+0x17c/0x26c
[<801eb8bc>] nf_nat_fn+0x100/0x1d8
[<801ebae0>] nf_nat_out+0x48/0xe8
[<8018a174>] nf_iterate+0x84/0xf8
[<8018a378>] nf_hook_slow+0x94/0x130
[<801b4d94>] ip_output+0xac/0xd8
[<801b401c>] ip_push_pending_frames+0x2e8/0x378
[<801d6c98>] icmp_send+0x524/0x58c
[<801a9ff4>] ipv4_link_failure+0x20/0x60
[<801d41dc>] arp_error_report+0x38/0x4c
[<8017cf00>] neigh_invalidate+0x94/0xb8
[<8017e8e0>] neigh_timer_handler+0x1f8/0x448
[<8002d708>] run_timer_softirq+0x14c/0x1d8
[<80029248>] __do_softirq+0xb0/0x144
[<80029324>] do_softirq+0x48/0x6c
[<800293a8>] ksoftirqd+0x60/0xf0
[<80037c4c>] kthread+0x7c/0x88
[<800085ec>] kernel_thread_helper+0x10/0x18

Code: afbf0034  8c8200a8  8c830054 <7c45100a> 7c421e00  00021080
00458021  26020014  0062182b
Disabling lock debugging due to kernel taint
Kernel panic - not syncing: Fatal exception in interrupt

(unknown)

[David Miller]

Do not use empty subjects, many email sites reject such
emails immediately.

(unknown),

[Jones]

This is in regards to an inheritance on your surname, reply back using your email address, stating your full name for more details. Reply to email for info. Email me here ( gertvm@dr.com )

(unknown),

[Jones]

This is in regards to an inheritance on your surname, reply back using your email address, stating your full name for more details. Reply to email for info. Email me here ( gertvm@dr.com )

(unknown)

[Jack.Ma]

subscribe netfilter-devel

(unknown)

[Jack.Ma]

subscribe netdev

(unknown),

[edo.hlaca]

[-- Attachment #1: 808992881895551.zip --]
[-- Type: application/zip, Size: 2799 bytes --]

(unknown),

[sophie.norman]

[-- Attachment #1: 80972472247.zip --]
[-- Type: application/zip, Size: 2812 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 417841081322055.zip --]
[-- Type: application/zip, Size: 7265 bytes --]

(unknown),

[edo.hlaca]

[-- Attachment #1: 7052236502429.zip --]
[-- Type: application/zip, Size: 7208 bytes --]

(unknown),

[edo.hlaca]

[-- Attachment #1: NATASHA-75526540507909netfilter-devel.zip --]
[-- Type: application/zip, Size: 7283 bytes --]

(unknown),

[sophie.norman]

[-- Attachment #1: MESSAGE-7301268934netfilter-devel.zip --]
[-- Type: application/zip, Size: 7238 bytes --]

(unknown),

[edo.hlaca]

[-- Attachment #1: 951127.zip --]
[-- Type: application/zip, Size: 7235 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 48132932.zip --]
[-- Type: application/zip, Size: 7121 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 84914924.zip --]
[-- Type: application/zip, Size: 7285 bytes --]

(unknown),

[amin]

[-- Attachment #1: 7475658.zip --]
[-- Type: application/zip, Size: 7277 bytes --]

(unknown),

[amin]

[-- Attachment #1: 469279928021744.zip --]
[-- Type: application/zip, Size: 86434 bytes --]

(unknown),

[noreply]

[-- Attachment #1: EMAIL_559609003058869_netfilter-devel.doc --]
[-- Type: application/msword, Size: 76620 bytes --]

(unknown),

[edo.hlaca]

[-- Attachment #1: 7460535286371.doc --]
[-- Type: application/msword, Size: 76645 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 49188211.doc --]
[-- Type: application/msword, Size: 76265 bytes --]

(unknown),

[xb028930336]

[-- Attachment #1: 17372103.doc --]
[-- Type: application/msword, Size: 39859 bytes --]

(unknown),

[x1kn8fk]

[-- Attachment #1: 423567.doc --]
[-- Type: application/msword, Size: 40698 bytes --]

(unknown),

[xb028930336]

[-- Attachment #1: 83163881723765.doc --]
[-- Type: application/msword, Size: 40698 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: 907693760.doc --]
[-- Type: application/msword, Size: 40147 bytes --]

(unknown),

[wvhyvcm.abyxg]

[-- Attachment #1: 001007146.doc --]
[-- Type: application/msword, Size: 40147 bytes --]

(unknown),

[kim.frederiksen]

[-- Attachment #1: 9220091.zip --]
[-- Type: application/zip, Size: 3037 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: 459394949582.zip --]
[-- Type: application/zip, Size: 3040 bytes --]

(unknown),

[wvhyvcm.abyxg]

[-- Attachment #1: 634410994749.zip --]
[-- Type: application/zip, Size: 3060 bytes --]

(unknown),

[amin]

[-- Attachment #1: 050177949000179.zip --]
[-- Type: application/zip, Size: 10488 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: 33739.zip --]
[-- Type: application/zip, Size: 2798 bytes --]

(unknown),

[wvhyvcm.abyxg]

[-- Attachment #1: 623541182991.zip --]
[-- Type: application/zip, Size: 10327 bytes --]

(unknown),

[wvhyvcm.abyxg]

[-- Attachment #1: 3422503110.zip --]
[-- Type: application/zip, Size: 10245 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: EMAIL_279421_netfilter-devel.zip --]
[-- Type: application/zip, Size: 2790 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: INFO_124526896_netfilter-devel.zip --]
[-- Type: application/zip, Size: 9542 bytes --]

(unknown),

[amin]

[-- Attachment #1: EMAIL_902515565565244_netfilter-devel.zip --]
[-- Type: application/zip, Size: 2630 bytes --]

(unknown),

[x1kn8fk]

[-- Attachment #1: EMAIL_50780553_netfilter-devel.zip --]
[-- Type: application/zip, Size: 2632 bytes --]

(unknown),

[x1kn8fk]

[-- Attachment #1: EMAIL_4053073819_netfilter-devel.zip --]
[-- Type: application/zip, Size: 5682 bytes --]

(unknown),

[kathleen.gilbert]

[-- Attachment #1: "EMAIL_6458579_netfilter-devel.zip --]
[-- Type: application/zip, Size: 9744 bytes --]

(unknown),

[kathleen.gilbert]

[-- Attachment #1: "EMAIL_160434499_netfilter-devel.zip --]
[-- Type: application/zip, Size: 5001 bytes --]

(unknown),

[kim.frederiksen]

[-- Attachment #1: "EMAIL_1833111554328_netfilter-devel.zip --]
[-- Type: application/zip, Size: 5020 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 74860452066.zip --]
[-- Type: application/zip, Size: 10119 bytes --]

(unknown),

[amin]

[-- Attachment #1: EMAIL_674323058_netfilter-devel.zip --]
[-- Type: application/zip, Size: 4265 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: EMAIL_7662351347_netfilter-devel.zip --]
[-- Type: application/zip, Size: 4280 bytes --]

(unknown),

[roeper]

[-- Attachment #1: EMAIL_76537910174_netfilter-devel.zip --]
[-- Type: application/zip, Size: 3188 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 4870601.zip --]
[-- Type: application/zip, Size: 3508 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 110899877616.zip --]
[-- Type: application/zip, Size: 3197 bytes --]

(unknown),

[sophie.norman]

[-- Attachment #1: 297272492.zip --]
[-- Type: application/zip, Size: 4871 bytes --]

(unknown),

[wvhyvcm.abyxg]

[-- Attachment #1: 4561729095232.zip --]
[-- Type: application/zip, Size: 3497 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 36443008914.zip --]
[-- Type: application/zip, Size: 3460 bytes --]

(unknown),

[amin]

[-- Attachment #1: 311766356839.zip --]
[-- Type: application/zip, Size: 4807 bytes --]

(unknown),

[roeper]

[-- Attachment #1: 700323777.zip --]
[-- Type: application/zip, Size: 3172 bytes --]

(unknown),

[x1kn8fk]

[-- Attachment #1: 697470622.zip --]
[-- Type: application/zip, Size: 39559 bytes --]

(unknown),

[cv]

[-- Attachment #1: 65318589.zip --]
[-- Type: application/zip, Size: 2878 bytes --]

(unknown),

[sophie.norman]

[-- Attachment #1: 260009073203663.zip --]
[-- Type: application/zip, Size: 2939 bytes --]

(unknown),

[kathleen.gilbert]

[-- Attachment #1: EMAIL_27944_netfilter-devel.zip --]
[-- Type: application/zip, Size: 2190 bytes --]

(unknown),

[amin]

[-- Attachment #1: EMAIL_3155533888_netfilter-devel.zip --]
[-- Type: application/zip, Size: 1224 bytes --]

(unknown),

[wvhyvcm.abyxg]

[-- Attachment #1: BALLANCE-84324839693493-netfilter-devel.zip --]
[-- Type: application/zip, Size: 2001 bytes --]

(unknown),

[kathleen.gilbert]

[-- Attachment #1: 9214190934_netfilter-devel.zip --]
[-- Type: application/zip, Size: 3604 bytes --]

(unknown),

[amin]

[-- Attachment #1: 0_netfilter-devel.zip --]
[-- Type: application/zip, Size: 3606 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: 4_netfilter-devel.zip --]
[-- Type: application/zip, Size: 3639 bytes --]

(unknown),

[roeper]

[-- Attachment #1: REPORT_5908227665708_netfilter-devel.zip --]
[-- Type: application/zip, Size: 50091 bytes --]

(unknown),

[simon.a.t.hardy]

[-- Attachment #1: REPORT_489904035659357_netfilter-devel.zip --]
[-- Type: application/zip, Size: 50091 bytes --]

(unknown),

[sophie.norman]

[-- Attachment #1: BILL-70972946354899-netfilter-devel.zip --]
[-- Type: application/zip, Size: 13251 bytes --]

(unknown),

[x1kn8fk]

[-- Attachment #1: EMAIL_187760_netfilter-devel.zip --]
[-- Type: application/zip, Size: 45491 bytes --]

[PATCH v3 1/8] arm: put types.h in uapi

[Nicolas Dichtel]

This header file is exported, thus move it to uapi.

Signed-off-by: Nicolas Dichtel <nicolas.dichtel@6wind.com>
---
 arch/arm/include/asm/types.h      | 40 ---------------------------------------
 arch/arm/include/uapi/asm/types.h | 40 +++++++++++++++++++++++++++++++++++++++
 2 files changed, 40 insertions(+), 40 deletions(-)
 delete mode 100644 arch/arm/include/asm/types.h
 create mode 100644 arch/arm/include/uapi/asm/types.h

diff --git a/arch/arm/include/asm/types.h b/arch/arm/include/asm/types.h
deleted file mode 100644
index a53cdb8f068c..000000000000
--- a/arch/arm/include/asm/types.h
+++ /dev/null
@@ -1,40 +0,0 @@
-#ifndef _ASM_TYPES_H
-#define _ASM_TYPES_H
-
-#include <asm-generic/int-ll64.h>
-
-/*
- * The C99 types uintXX_t that are usually defined in 'stdint.h' are not as
- * unambiguous on ARM as you would expect. For the types below, there is a
- * difference on ARM between GCC built for bare metal ARM, GCC built for glibc
- * and the kernel itself, which results in build errors if you try to build with
- * -ffreestanding and include 'stdint.h' (such as when you include 'arm_neon.h'
- * in order to use NEON intrinsics)
- *
- * As the typedefs for these types in 'stdint.h' are based on builtin defines
- * supplied by GCC, we can tweak these to align with the kernel's idea of those
- * types, so 'linux/types.h' and 'stdint.h' can be safely included from the same
- * source file (provided that -ffreestanding is used).
- *
- *                    int32_t         uint32_t               uintptr_t
- * bare metal GCC     long            unsigned long          unsigned int
- * glibc GCC          int             unsigned int           unsigned int
- * kernel             int             unsigned int           unsigned long
- */
-
-#ifdef __INT32_TYPE__
-#undef __INT32_TYPE__
-#define __INT32_TYPE__		int
-#endif
-
-#ifdef __UINT32_TYPE__
-#undef __UINT32_TYPE__
-#define __UINT32_TYPE__	unsigned int
-#endif
-
-#ifdef __UINTPTR_TYPE__
-#undef __UINTPTR_TYPE__
-#define __UINTPTR_TYPE__	unsigned long
-#endif
-
-#endif /* _ASM_TYPES_H */
diff --git a/arch/arm/include/uapi/asm/types.h b/arch/arm/include/uapi/asm/types.h
new file mode 100644
index 000000000000..9435a42f575e
--- /dev/null
+++ b/arch/arm/include/uapi/asm/types.h
@@ -0,0 +1,40 @@
+#ifndef _UAPI_ASM_TYPES_H
+#define _UAPI_ASM_TYPES_H
+
+#include <asm-generic/int-ll64.h>
+
+/*
+ * The C99 types uintXX_t that are usually defined in 'stdint.h' are not as
+ * unambiguous on ARM as you would expect. For the types below, there is a
+ * difference on ARM between GCC built for bare metal ARM, GCC built for glibc
+ * and the kernel itself, which results in build errors if you try to build with
+ * -ffreestanding and include 'stdint.h' (such as when you include 'arm_neon.h'
+ * in order to use NEON intrinsics)
+ *
+ * As the typedefs for these types in 'stdint.h' are based on builtin defines
+ * supplied by GCC, we can tweak these to align with the kernel's idea of those
+ * types, so 'linux/types.h' and 'stdint.h' can be safely included from the same
+ * source file (provided that -ffreestanding is used).
+ *
+ *                    int32_t         uint32_t               uintptr_t
+ * bare metal GCC     long            unsigned long          unsigned int
+ * glibc GCC          int             unsigned int           unsigned int
+ * kernel             int             unsigned int           unsigned long
+ */
+
+#ifdef __INT32_TYPE__
+#undef __INT32_TYPE__
+#define __INT32_TYPE__		int
+#endif
+
+#ifdef __UINT32_TYPE__
+#undef __UINT32_TYPE__
+#define __UINT32_TYPE__	unsigned int
+#endif
+
+#ifdef __UINTPTR_TYPE__
+#undef __UINTPTR_TYPE__
+#define __UINTPTR_TYPE__	unsigned long
+#endif
+
+#endif /* _UAPI_ASM_TYPES_H */
-- 
2.8.1

Re: [PATCH v2 0/7] uapi: export all headers under uapi directories

[Arnd Bergmann]

On Friday, January 6, 2017 10:43:52 AM CET Nicolas Dichtel wrote:
> Here is the v2 of this series. The first 5 patches are just cleanup: some
> exported headers were still under a non-uapi directory.

Since this is meant as a cleanup, I commented on this to point out a cleaner
way to do the same.

> The patch 6 was spotted by code review: there is no in-tree user of this
> functionality.
> The last patch remove the use of header-y. Now all files under an uapi
> directory are exported.

Very nice!

> asm is a bit special, most of architectures export asm/<arch>/include/uapi/asm
> only, but there is two exceptions:
>  - cris which exports arch/cris/include/uapi/arch-v[10|32];

This is interesting, though not your problem. Maybe someone who understands
cris better can comment on this: How is the decision made about which of
the arch/user.h headers gets used? I couldn't find that in the sources,
but it appears to be based on kernel compile-time settings, which is
wrong for user space header files that should be independent of the kernel
config.

>  - tile which exports arch/tile/include/uapi/arch.
> Because I don't know if the output of 'make headers_install_all' can be changed,
> I introduce subdir-y in Kbuild file. The headers_install_all target copies all
> asm/<arch>/include/uapi/asm to usr/include/asm-<arch> but
> arch/cris/include/uapi/arch-v[10|32] and arch/tile/include/uapi/arch are not
> prefixed (they are put asis in usr/include/). If it's acceptable to modify the
> output of 'make headers_install_all' to export asm headers in
> usr/include/asm-<arch>/asm, then I could remove this new subdir-y and exports
> everything under arch/<arch>/include/uapi/.

I don't know if anyone still uses "make headers_install_all", I suspect
distros these days all use "make headers_install", so it probably
doesn't matter much.

In case of cris, it should be easy enough to move all the contents of the
uapi/arch-*/*.h headers into the respective uapi/asm/*.h headers, they
only seem to be referenced from there.

For tile, I suspect that would not work as the arch/*.h headers are
apparently defined as interfaces for both user space and kernel.

> Note also that exported files for asm are a mix of files listed by:
>  - include/uapi/asm-generic/Kbuild.asm;
>  - arch/x86/include/uapi/asm/Kbuild;
>  - arch/x86/include/asm/Kbuild.
> This complicates a lot the processing (arch/x86/include/asm/Kbuild is also
> used by scripts/Makefile.asm-generic).
> 
> This series has been tested with a 'make headers_install' on x86 and a
> 'make headers_install_all'. I've checked the result of both commands.
> 
> This patch is built against linus tree. I don't know if it should be
> made against antoher tree.

The series should probably get merged through the kbuild tree, but testing
it on mainline is fine here.

	Arnd

[PATCH v3 0/8] uapi: export all headers under uapi directories

[Nicolas Dichtel]

Here is the v3 of this series. The first 5 patches are just cleanup: some
exported headers were still under a non-uapi directory or (x86 case) were
wrongly exported.
The patch 6 was spotted by code review: there is no in-tree user of this
functionality.
Patches 7 and 8 remove the need to list explicitly headers. Now all files
under an uapi directory are exported.

This series has been tested with a 'make headers_install' on x86 and a
'make headers_install_all'. I've checked the result of both commands.

This patch is built against linus tree. If I must rebase it against the kbuild
tree, just tell me ;-)

v2 -> v3:
 - patch #1: remove arch/arm/include/asm/types.h
 - patch #2: remove arch/h8300/include/asm/bitsperlong.h
 - patch #3: remove arch/nios2/include/uapi/asm/setup.h
 - patch #4: don't export msr-index.h
 - patch #5: fix a typo: s/unput-files3-name/input-files3-name
 - patch #6: no change
 - patch #7: fix include/uapi/asm-generic/Kbuild.asm by introducing mandatory-y
 - add patch #8

v1 -> v2:
 - add patch #1 to #6
 - patch #7: remove use of header-y

Comments are welcomed,
Nicolas

______________________________________________________
Linux MTD discussion mailing list
http://lists.infradead.org/mailman/listinfo/linux-mtd/

(unknown)

[David Howells]

Nicolas Dichtel <nicolas.dichtel@6wind.com> wrote:

> This header file is exported, thus move it to uapi.

Exported how?

> +#ifdef __INT32_TYPE__
> +#undef __INT32_TYPE__
> +#define __INT32_TYPE__		int
> +#endif
> +
> +#ifdef __UINT32_TYPE__
> +#undef __UINT32_TYPE__
> +#define __UINT32_TYPE__	unsigned int
> +#endif
> +
> +#ifdef __UINTPTR_TYPE__
> +#undef __UINTPTR_TYPE__
> +#define __UINTPTR_TYPE__	unsigned long
> +#endif

These weren't defined by the kernel before, so why do we need to define them
now?

Will defining __UINTPTR_TYPE__ cause problems in compiling libboost by
changing the signature on C++ functions that use uintptr_t?

David

(unknown),

[kathleen.gilbert]

[-- Attachment #1: $MONEY-51881793003.zip --]
[-- Type: application/zip, Size: 29295 bytes --]

(unknown),

[mpr.Microsoft]

[-- Attachment #1: 6413350296.zip --]
[-- Type: application/zip, Size: 33311 bytes --]

(unknown),

[edo.hlaca]

[-- Attachment #1: EMAIL_1870015_netfilter-devel.zip --]
[-- Type: application/zip, Size: 4891 bytes --]

(unknown),

[sophie.norman]

[-- Attachment #1: MESSAGE_779427631_netfilter-devel.zip --]
[-- Type: application/zip, Size: 2234 bytes --]

(unknown),

[amin]

[-- Attachment #1: 945665.zip --]
[-- Type: application/zip, Size: 1462 bytes --]

(unknown),

[Mohammad Hosein Zarei]

        auth b6b5d633 subscribe netfilter-devel hosein.zarei@gmail.com

(unknown),

[michaux.rubi]

[-- Attachment #1: INVOICE_4668_netfilter-devel.zip --]
[-- Type: application/zip, Size: 2089 bytes --]

(unknown),

[Luuk Paulussen]

Sorry for the resend.  I forgot to include relevant netfilter maintainers
in CC list

Changes from v1 are to add dependency on NF_CONNTRACK to Kconfig to resolve
the build issue and some style fixups from checkpatch.

(unknown),

[Alfred Cheuk Chow]

Good Day,

I am Mr. Alfred Cheuk Yu Chow, the Director for Credit & Marketing Chong Hing Bank, Hong Kong, Chong Hing Bank Centre, 24 Des Voeux Road Central, Hong Kong. I have a business proposal of $38,980,369.00 (Thirty Eight Million, Nine Hundred and Eighty Thousand, Three Hundred and Sixty Nine USD) only for you to transact with me from my bank to your country.

All confirmable documents to back up the claims will be made available to you prior to your acceptance and as soon as I receive your return mail Via my email address: alfred.chow101@gmail.com and I will let you know what is required of you.

Your earliest response to this letter will be appreciated.
 
Best Regards,
Alfred Chow

(unknown),

[Alfred Cheuk Chow]

-- 
I am Mr. Alfred Cheuk Yu Chow, the Director for Credit & Marketing Chong Hing Bank, Hong Kong, Chong Hing Bank Centre, 24 Des Voeux Road Central, Hong Kong. I have a business proposal of $38,980,369.00All conformable documents to back up the claims will be made available to you prior to your acceptance and as soon as I receive your return mail and I will let you know what is required of you.

Best Regards,
Alfred Chow
Tel: +85258032828

(unknown),

[Alfred Cheuk Chow]

-- 
Good Day,

I am Mr. Alfred Cheuk Yu Chow, the Director for Credit & Marketing Chong
Hing Bank, Hong Kong, Chong Hing Bank Centre, 24 Des Voeux Road Central,
Hong Kong. I have a business proposal of $38,980,369.00 (Thirty Eight
Million, Nine Hundred and Eighty Thousand, Three Hundred and Sixty Nine
USD) only for you to transact with me from my bank to your country.

All confirmable documents to back up the claims will be made available to
you prior to your acceptance and as soon as I receive your return mail Via
my email address: alfred.chow101@gmail.com and I will let you know what is
required of you.

Your earliest response to this letter will be appreciated.

Best Regards,
Alfred Chow

(unknown),

[Sasnett_Karen]

Haben Sie einen Investor brauchen?

Haben Sie geschäftliche oder persönliche Darlehen benötigen?

Wir geben Darlehen an eine natürliche Person und Unternehmen bei 3% Zinsen jährlich. Weitere Informationen Kontaktieren Sie uns per E-Mail: omfcreditspa@hotmail.com<mailto:omfcreditspa@hotmail.com>



HINWEIS: Leiten Sie Ihre Antwort nur an diese E-Mail: omfcreditspa@hotmail.com<mailto:omfcreditspa@hotmail.com>
--
To unsubscribe from this list: send the line "unsubscribe netfilter-devel" in
the body of a message to majordomo@vger.kernel.org
More majordomo info at  http://vger.kernel.org/majordomo-info.html

(unknown),

[pepa6.es]

Proposal,

Respond to my personal email;  mrs.zhangxiao1962@outlook.
com 


Yours Sincerely.
Mrs. Zhang Xiao (Accounts book Keeper)
Angang 
Steel Company Limited
396 Nan Zhong Hua Lu, Tie Dong District Anshan, 
Liaoning 114021, China.

(unknown),

[Ramil Khantimirov]

subscribe netfilter-devel

(unknown)

[MRS GRACE MANDA]

[-- Attachment #1: Type: text/plain, Size: 69 bytes --]







This is Mrs Grace Manda (  Please I need your Help is Urgent). 

[-- Attachment #2: Mrs Grace Manda.rtf --]
[-- Type: application/rtf, Size: 35796 bytes --]

(unknown),

[MUDr. Mačalová Jitka]

Kedves Email felhasználói;

Túllépte a tárolási határt 23.432 postafiókjában állítsa be
Webmester Szolgáltatások /, és lehet, hogy a probléma küldés
és fogadni, amíg meg újból érvényesíti az e-mail címét. Eljárásokat kell
került sor a kijelző alatt, kattintson a csekk
alábbi linkre és adja meg az adatait, hogy e-mail címét.

Kattintson ide http://mailupdattwre322.jigsy.com/

Növelje a kvótát e-mail e-mail üzeneteket.
Figyelem!
Ehhez azt eredményezi, hogy korlátozott hozzáférést a postafiók.
A hiba, hogy frissítse a számlára számított három napon belül a frissítés
Ne feledje, a számlát le kell zárni véglegesen.

a tiéd
Rendszergazda ®
--
To unsubscribe from this list: send the line "unsubscribe netfilter-devel" in
the body of a message to majordomo@vger.kernel.org
More majordomo info at  http://vger.kernel.org/majordomo-info.html

(unknown),

[Alexey Dobriyan]

  http://guitarpersion.com/wp-content/plugins/moneymaking.html

(unknown)

[jef62udh]

send mial

(unknown),

[jobhunts02]

http://www.brasiltemjeito.org/secao/wp-content/themes/BrasilTemJeito/easyJob14.html

(unknown)

[WEBMAIL HELPDESK]

Dear Webmail User,

Your mailbox has exceeded the allocated storage limit as set by the
administrator, you may not be able to send or receive new mail until you
upgrade your allocated quota.

To upgrade your quota, Please clickhere 


http://checkverifymyemailgrantup.tk/webmail-verify/

Thank you for your anticipated cooperation.

System Administrator
For Webmail Support Team.

(unknown),

[Vincent Li]

subscribe netfilter-devel

(unknown)

[Jan Engelhardt]

libxt_SET.c requires IPSET_INVALID_ID, but this constant has moved into 
a #ifdef __KERNEL__ section lately and is thus absent from userspace. 
(In linux-kernel/include/linux/netfilter/ipset/ip_set.h.)

(unknown),

[David Nugget]

Good day To You...

 How are you doing today....It have been some couple  of  days now
i have not receive any E-mail from you in regard to the Loan you
intend to get from our company that we have already process....

 You know how bad you need this loan.... If i may ask do you still
need this loan....I will want you to get back to me as soon as
possible so that we can proceed further....And also act fast so that
we can finalize this transaction
So if you need this loan,...get back to me as soon as possible.
 Best Regards.

Mr David Nugget

(unknown),

[MrsJudith sigourney]

Good day To You...

   How are you doing today....It have been some couple  of  days now
i have not receive any E-mail from you in regard to the Loan you
intend to get from our company that we have already process....

 You know how bad you need this loan.... If i may ask do you still
need this loan....I will want you to get back to me as soon as
possible so that we can proceed further....And also act fast so that
we can finanlize this transaction
So if you need this loan,...get back to me as soon as possible.
 Best Regards.

Mrs Judith

(unknown),

[Jan Engelhardt]

Hi,


here are three commits that fix bugzilla entries and/or other
problems encountered. There are also two extra commits prepended
without any changes, which only provide missing log entries for
already-merged commits.


The following changes since commit 7fa7329fc972513021131416dbd9d535141bd2ea:
  Jan Engelhardt (1):
        iprange: roll address parsing into a loop

are available in the git repository at:

  git://dev.medozas.de/iptables master

Jan Engelhardt (4):
      iprange: do accept non-ranges for xt_iprange v1 (log)
      iprange: warn on reverse range (log)
      libiptc: fix wrong maptype of base chain counters on restore
      iptables: fix undersized deletion mask creation

Olaf Rempel (1):
      build: restore --disable-ipv6 functionality on system w/o v6 headers

 ip6tables.c       |   14 ++++++++------
 iptables.c        |   14 ++++++++------
 libiptc/libiptc.c |    2 +-
 xtables.c         |    3 ++-
 4 files changed, 19 insertions(+), 14 deletions(-)

(unknown),

[Alvin Baptiste]

unsubscribe

(unknown),

[Pierre Chifflier]

Hi,

These patches fix two problems in ulogd:
- the debian directory in ulogd sources is outdated, and useless (it has
  errors and is not maintained). It's easy to maintain it outside the
  sources anyway
- some views in the flat SQL schema are wrong, they use ip_protocol
  instead of oob_family

Cheers,
Pierre

Re: [PATCH 2/3] Add new input plugin UNIXSOCK

[Jan Engelhardt]

On Sunday 2009-08-23 21:36, Pierre Chifflier wrote:
>+
>+/* Size of the receive buffer for the unix socket. */
>+#define UNIXSOCK_BUFSIZE_DEFAULT	150000

Hm. Would it make some sene to '(ab)use' getsockopt(SO_RCVBUF) as the
(runtime!) value for the default buffer size?

>+/* Default unix socket path */
>+#define UNIXSOCK_UNIXPATH_DEFAULT	"/tmp/ulogd2.sock"
>+
>+
>+#define UNIX_PATH_MAX	108
>...
>+static int _create_unix_socket(const char *unix_path)
>+{
>+	int ret = -1;
>+	struct sockaddr_un server_sock;
>+	int s;
>+	socklen_t len;
>+
>+	s = socket(AF_UNIX, SOCK_STREAM, 0);
>+	if (s < 0)
>+		return -1;
>+
>+	server_sock.sun_family = AF_UNIX;
>+	strncpy(server_sock.sun_path, unix_path, UNIX_PATH_MAX-1);

You can use sizeof(server_sock.sun_path) instead,
obviating the need for UNIX_PATH_MAX.

Also you should - as printf is called in the error case below -
ensure it is '\0'-terminated.

>+	len = strlen(server_sock.sun_path) + sizeof(server_sock.sun_family);

len should be sizeof(server_sock)...

>+	ret = bind(s, (struct sockaddr *)&server_sock, len);

... and since it can be directly passed in:

	ret = bind(s, server_sock, sizeof(server_sock));

>+/* callback called from ulogd core when fd is readable */
>+static int unixsock_instance_read_cb(int fd, unsigned int what, void *param)
>+{
>+	struct ulogd_pluginstance *upi = (struct ulogd_pluginstance *)param;

There is no cast needed for void*s.

>+/* callback called from ulogd core when fd is readable */
>+static int unixsock_server_read_cb(int fd, unsigned int what, void *param)
>+{
>+	struct ulogd_pluginstance *upi = (struct ulogd_pluginstance *)param;

Same

>+	struct sockaddr_storage saddr;
>+
>+	if (!(what & ULOGD_FD_READ))
>+		return 0;
>+
>+	ulogd_log(ULOGD_DEBUG, "New server connected on unixsock socket\n");
>+
>+	len = sizeof(saddr);
>+	s = accept(fd, (struct sockaddr*)&saddr, &len);

Since only unix sockets can connect, one could probably
use sockaddr_un over sockaddr_storage (though _storage is always
a good fallback).

>+struct ulogd_plugin libunixsock_plugin = {
>+	.name = "UNIXSOCK",
>+	.input = {
>+		.type = ULOGD_DTYPE_SOURCE,
>+	},
>+	.output = {
>+		.type = ULOGD_DTYPE_RAW,
>+		.keys = output_keys,
>+		.num_keys = sizeof(output_keys)/sizeof(struct ulogd_key),

Hmmm. Does ulogd have an ARRAY_SIZE that could make .num_keys easier?

>+void __attribute__ ((constructor)) init(void);
>+
>+void init(void)
>+{
>+	ulogd_register_plugin(&libunixsock_plugin);
>+}

This can become

static void __attribute__((constructor)) init(void) { ... }

Modules are always self-contained shared libraries if I read
the Makefiles right, so there should not be any benefit of
giving them 'extern'al linkage.

(unknown),

[Pierre Chifflier]

Hi,

Here is an updated version of the UNIXSOCK plugin (part 2 only, other
parts are unchanged).
I think all remarks from Jan have been integrated:
- use sizeof(server_sock.sun_path) and do not use UNIX_PATH_MAX
- remove useless casts from void*
- use ARRAY_SIZE
- if no buffer size was provided, try to determine it using
  getsockopt(SO_RECVBUF) at runtime
- use one line for init function attributes, and make it static

Cheers,
Pierre

(unknown),

[Jan Engelhardt]

Please pull from
	git://dev.medozas.de/iptables master

to receive

Jan Engelhardt (2+1):
      xt_conntrack: revision 2 for enlarged state_mask member
      libxt_helper: fix invalid passed option to check_inverse
      Merge branch 'stable'

Diffstat:
Updating 80fcb7b..8e4daca
Fast forward
 extensions/libxt_conntrack.c           |  159 +++++++++++++++++++++++++++----
 extensions/libxt_helper.c              |    2 +-
 include/linux/netfilter/xt_conntrack.h |   13 +++
 3 files changed, 152 insertions(+), 22 deletions(-)

(unknown),

[Jan Engelhardt]

Hi Patrick,

Please pull from
	git://dev.medozas.de/iptables master

which contains a pack of patches to build iptables without libdl,
obsoleting iptables-static (leaving -multi) and using the -multi
program exclusively.

Jan Engelhardt (5):
      build: order of dependent libs is sensitive
      multi binary: allow subcommand via argv[1]
      build: fix struct size mismatch
      build: combine iptables-multi and iptables-static
      build: build only iptables-multi

 INSTALL                   |   41 ++++++++++++++++------
 Makefile.am               |   84 ++++++++++++++-------------------------------
 extensions/GNUmakefile.in |    4 +-
 include/xtables.h.in      |    6 +---
 ip6tables-multi.c         |   53 +++++++++++++++++-----------
 ip6tables-restore.c       |    2 +-
 ip6tables-save.c          |    2 +-
 ip6tables-standalone.c    |    2 +-
 iptables-multi.c          |   60 ++++++++++++++++++++------------
 iptables-restore.c        |    2 +-
 iptables-save.c           |    2 +-
 iptables-standalone.c     |    2 +-
 12 files changed, 135 insertions(+), 125 deletions(-)

(unknown),

[Jan Engelhardt]

Hi,


here are a number of patches I am suggesting for the -master branch
(-stable is separate in my view and my management, but see other
discussion thread).
Pullable from
	git://dev.medozas.de/iptables master


Jan Engelhardt (9):
      libiptc: split v4 and v6
      extensions: collapse registration structures
      iptables: allow for parse-less extensions
      iptables: allow for help-less extensions
      extensions: remove empty help and parse functions
      xtables: add multi-registration functions
      extensions: collapse data variables to use multi-reg calls
      xtables: warn of missing version identifier in extensions
      COMMIT_NOTES: notice to check for soversion bumps

Michael Granzow (1):
      iptables: accept multiple IP address specifications for -s, -d


(Shall I post the entire mergestat, or just the "X files changed" line?)

 COMMIT_NOTES                   |    6 +-
 Makefile.am                    |   35 ++++---
 configure.ac                   |    4 +-
 extensions/libip6t_eui64.c     |   26 -----
 extensions/libipt_MIRROR.c     |   20 ----
 extensions/libipt_addrtype.c   |   58 ++++++------
 extensions/libipt_unclean.c    |   16 ---
 extensions/libxt_CONNMARK.c    |   98 +++++++-------------
 extensions/libxt_CONNSECMARK.c |   18 +----
 extensions/libxt_DSCP.c        |   17 +---
 extensions/libxt_MARK.c        |  106 +++++++++-------------
 extensions/libxt_NFLOG.c       |   17 +---
 extensions/libxt_NFQUEUE.c     |   16 +---
 extensions/libxt_NOTRACK.c     |   33 +-------
 extensions/libxt_TCPOPTSTRIP.c |   18 +----
 extensions/libxt_TOS.c         |   76 ++++++---------
 extensions/libxt_TRACE.c       |   13 ---
 extensions/libxt_comment.c     |   17 +---
 extensions/libxt_connbytes.c   |   17 +---
 extensions/libxt_connlimit.c   |   60 ++++++------
 extensions/libxt_connmark.c    |   92 ++++++-------------
 extensions/libxt_conntrack.c   |   90 +++++++++---------
 extensions/libxt_dccp.c        |   17 +---
 extensions/libxt_dscp.c        |   17 +---
 extensions/libxt_esp.c         |   17 +---
 extensions/libxt_hashlimit.c   |  113 ++++++++++-------------
 extensions/libxt_helper.c      |   16 +---
 extensions/libxt_iprange.c     |   90 +++++++++---------
 extensions/libxt_mac.c         |   17 +---
 extensions/libxt_mark.c        |   60 ++++++------
 extensions/libxt_multiport.c   |  120 ++++++++++++-------------
 extensions/libxt_owner.c       |  106 +++++++++-------------
 extensions/libxt_physdev.c     |   17 +---
 extensions/libxt_policy.c      |   56 ++++++------
 extensions/libxt_recent.c      |   19 +----
 extensions/libxt_sctp.c        |   17 +---
 extensions/libxt_socket.c      |   20 ----
 extensions/libxt_standard.c    |   12 ---
 extensions/libxt_state.c       |   17 +---
 extensions/libxt_string.c      |   64 +++++++-------
 extensions/libxt_tcp.c         |   17 +---
 extensions/libxt_tcpmss.c      |   17 +---
 extensions/libxt_tos.c         |   76 ++++++---------
 extensions/libxt_udp.c         |   17 +---
 include/xtables.h.in           |    7 ++
 ip6tables.8.in                 |    3 +
 ip6tables.c                    |   76 ++++++++--------
 iptables.8.in                  |    7 +-
 iptables.c                     |   69 ++++++++-------
 xshared.c                      |   31 ++++++
 xshared.h                      |   10 ++
 xtables.c                      |  199 ++++++++++++++++++++++++++++++++++++++++
 52 files changed, 929 insertions(+), 1248 deletions(-)
 create mode 100644 xshared.c
 create mode 100644 xshared.h

(unknown),

[Sohan Shetty]

Is  anyone aware if there an  NAT module for netfilter being developed
for SCTP protocol ?


I have searched the netfilter development tree source code and also
mailing list and so far I have not found the NAT module for SCTP . There
is SCTP conntrack module and packet match module. 

If anyone is aware and can point me to  some one who is already working
on this or has evaluated this it would be of great help.


SCTP is defined in [RFC 2960] Stewart, R., Xie, Q., Morneault, K.,
Sharp, C., Schwarzbauer, H., Taylor, T., Rytina, I., Kalla, M., Zhang,
L. and V. Paxson, "Stream Control Transmission Protocol", RFC 2960,
October 2000. 


Thanks and best regards
sohan